Home
last modified time | relevance | path

Searched refs:R3 (Results 1 – 25 of 87) sorted by relevance

1234

/OK3568_Linux_fs/kernel/arch/x86/crypto/
H A Dtwofish-x86_64-asm_64.S44 #define R3 %rdx macro
215 movq (R3), R1
216 movq 8(R3), R3
218 input_whitening(R3,%r11,c_offset)
223 shr $32, R3
226 encrypt_round(R0,R1,R2,R3,0);
227 encrypt_round(R2,R3,R0,R1,8);
228 encrypt_round(R0,R1,R2,R3,2*8);
229 encrypt_round(R2,R3,R0,R1,3*8);
230 encrypt_round(R0,R1,R2,R3,4*8);
[all …]
H A Dtwofish-i586-asm_32.S231 encrypt_round(R0,R1,R2,R3,0);
232 encrypt_round(R2,R3,R0,R1,8);
233 encrypt_round(R0,R1,R2,R3,2*8);
234 encrypt_round(R2,R3,R0,R1,3*8);
235 encrypt_round(R0,R1,R2,R3,4*8);
236 encrypt_round(R2,R3,R0,R1,5*8);
237 encrypt_round(R0,R1,R2,R3,6*8);
238 encrypt_round(R2,R3,R0,R1,7*8);
239 encrypt_round(R0,R1,R2,R3,8*8);
240 encrypt_round(R2,R3,R0,R1,9*8);
[all …]
/OK3568_Linux_fs/kernel/arch/powerpc/lib/
H A Dhweight_64.S21 PPC_POPCNTB(R3,R3)
36 PPC_POPCNTB(R3,R3)
43 PPC_POPCNTW(R3,R3)
61 PPC_POPCNTB(R3,R3)
69 PPC_POPCNTW(R3,R3)
89 PPC_POPCNTB(R3,R3)
99 PPC_POPCNTD(R3,R3)
/OK3568_Linux_fs/kernel/arch/arm/crypto/
H A Dpoly1305-armv4.pl495 my ($R0,$R1,$S1,$R2,$S2,$R3,$S3,$R4,$S4) = map("d$_",(0..9));
538 vdup.32 $R3,r5
557 vmull.u32 $D3,$R3,${R0}[1]
564 vmlal.u32 $D4,$R3,${R1}[1]
566 vmlal.u32 $D0,$R3,${S2}[1]
573 vmlal.u32 $D3,$R0,${R3}[1]
574 vmlal.u32 $D1,$R3,${S3}[1]
576 vmlal.u32 $D4,$R1,${R3}[1]
581 vmlal.u32 $D2,$R3,${S4}[1]
609 @ H4 = H4*R0 + H3*R1 + H2*R2 + H1*R3 + H0 * R4,
[all …]
/OK3568_Linux_fs/kernel/lib/
H A Dtest_bpf.c42 #define R3 BPF_REG_3 macro
1182 BPF_ALU64_IMM(BPF_MOV, R3, 3),
1192 BPF_ALU64_IMM(BPF_ADD, R3, 20),
1202 BPF_ALU64_IMM(BPF_SUB, R3, 10),
1212 BPF_ALU64_REG(BPF_ADD, R0, R3),
1224 BPF_ALU64_REG(BPF_ADD, R1, R3),
1236 BPF_ALU64_REG(BPF_ADD, R2, R3),
1245 BPF_ALU64_REG(BPF_ADD, R3, R0),
1246 BPF_ALU64_REG(BPF_ADD, R3, R1),
1247 BPF_ALU64_REG(BPF_ADD, R3, R2),
[all …]
/OK3568_Linux_fs/kernel/arch/hexagon/kernel/
H A Dvm_entry.S134 { R3:2 = memd(R0 + #_PT_R0302); \
166 R3:2 = memd(R0 + #_PT_R0302); \
210 memd(R29 +#_PT_R0302) = R3:2; \
219 memd(R29 + #_PT_ER_VMPSP) = R3:2; \
231 memd(R29 + #(_PT_R0302 + -_PT_REGS_SIZE)) = R3:2; \
243 R3:2 = G3:2; \
247 memd(R29 + #_PT_ER_VMPSP) = R3:2; \
322 R3:2 = memd(R29 + #_PT_ER_VMPSP);
328 G3:2 = R3:2;
/OK3568_Linux_fs/kernel/drivers/net/wan/
H A Dz85230.c467 write_zsreg(chan, R3, chan->regs[3] | RxENABLE); in z8530_status()
472 write_zsreg(chan, R3, chan->regs[3] & ~RxENABLE); in z8530_status()
587 write_zsreg(chan, R3, chan->regs[3] | RxENABLE); in z8530_dma_status()
592 write_zsreg(chan, R3, chan->regs[3] & ~RxENABLE); in z8530_dma_status()
722 intr = read_zsreg(&dev->chanA, R3); in z8530_interrupt()
805 write_zsreg(c, R3, c->regs[R3]|RxENABLE); in z8530_sync_open()
834 write_zsreg(c, R3, c->regs[R3]); in z8530_sync_close()
958 write_zsreg(c, R3, c->regs[R3]|RxENABLE); in z8530_sync_dma_open()
1027 write_zsreg(c, R3, c->regs[R3]); in z8530_sync_dma_close()
1131 write_zsreg(c, R3, c->regs[R3]|RxENABLE); in z8530_sync_txdma_open()
[all …]
/OK3568_Linux_fs/external/rknpu2/examples/3rdparty/opencv/opencv-linux-aarch64/include/opencv2/core/cuda/detail/
H A Dreduce.hpp138 …typename R0, typename R1, typename R2, typename R3, typename R4, typename R5, typename R6, typenam…
140 … const thrust::tuple<R0, R1, R2, R3, R4, R5, R6, R7, R8, R9>& val, in loadToSmem() argument
146 …typename R0, typename R1, typename R2, typename R3, typename R4, typename R5, typename R6, typenam…
148 … const thrust::tuple<R0, R1, R2, R3, R4, R5, R6, R7, R8, R9>& val, in loadFromSmem() argument
167 …typename R0, typename R1, typename R2, typename R3, typename R4, typename R5, typename R6, typenam…
170 … const thrust::tuple<R0, R1, R2, R3, R4, R5, R6, R7, R8, R9>& val, in merge() argument
177 …template <typename R0, typename R1, typename R2, typename R3, typename R4, typename R5, typename R…
179 …__device__ __forceinline__ void mergeShfl(const thrust::tuple<R0, R1, R2, R3, R4, R5, R6, R7, R8, … in mergeShfl() argument
184 …For<0, thrust::tuple_size<thrust::tuple<R0, R1, R2, R3, R4, R5, R6, R7, R8, R9> >::value>::mergeSh… in mergeShfl()
/OK3568_Linux_fs/external/rknpu2/examples/3rdparty/opencv/OpenCV-android-sdk/sdk/native/jni/include/opencv2/core/cuda/detail/
H A Dreduce.hpp138 …typename R0, typename R1, typename R2, typename R3, typename R4, typename R5, typename R6, typenam…
140 … const thrust::tuple<R0, R1, R2, R3, R4, R5, R6, R7, R8, R9>& val, in loadToSmem() argument
146 …typename R0, typename R1, typename R2, typename R3, typename R4, typename R5, typename R6, typenam…
148 … const thrust::tuple<R0, R1, R2, R3, R4, R5, R6, R7, R8, R9>& val, in loadFromSmem() argument
167 …typename R0, typename R1, typename R2, typename R3, typename R4, typename R5, typename R6, typenam…
170 … const thrust::tuple<R0, R1, R2, R3, R4, R5, R6, R7, R8, R9>& val, in merge() argument
177 …template <typename R0, typename R1, typename R2, typename R3, typename R4, typename R5, typename R…
179 …__device__ __forceinline__ void mergeShfl(const thrust::tuple<R0, R1, R2, R3, R4, R5, R6, R7, R8, … in mergeShfl() argument
184 …For<0, thrust::tuple_size<thrust::tuple<R0, R1, R2, R3, R4, R5, R6, R7, R8, R9> >::value>::mergeSh… in mergeShfl()
/OK3568_Linux_fs/external/rknpu2/examples/3rdparty/opencv/opencv-linux-armhf/include/opencv2/core/cuda/detail/
H A Dreduce.hpp138 …typename R0, typename R1, typename R2, typename R3, typename R4, typename R5, typename R6, typenam…
140 … const thrust::tuple<R0, R1, R2, R3, R4, R5, R6, R7, R8, R9>& val, in loadToSmem() argument
146 …typename R0, typename R1, typename R2, typename R3, typename R4, typename R5, typename R6, typenam…
148 … const thrust::tuple<R0, R1, R2, R3, R4, R5, R6, R7, R8, R9>& val, in loadFromSmem() argument
167 …typename R0, typename R1, typename R2, typename R3, typename R4, typename R5, typename R6, typenam…
170 … const thrust::tuple<R0, R1, R2, R3, R4, R5, R6, R7, R8, R9>& val, in merge() argument
177 …template <typename R0, typename R1, typename R2, typename R3, typename R4, typename R5, typename R…
179 …__device__ __forceinline__ void mergeShfl(const thrust::tuple<R0, R1, R2, R3, R4, R5, R6, R7, R8, … in mergeShfl() argument
184 …For<0, thrust::tuple_size<thrust::tuple<R0, R1, R2, R3, R4, R5, R6, R7, R8, R9> >::value>::mergeSh… in mergeShfl()
/OK3568_Linux_fs/kernel/arch/arm64/crypto/
H A Dpoly1305-armv8.pl262 my ($R0,$R1,$S1,$R2,$S2,$R3,$S3,$R4,$S4) = map("v$_.4s",(0..8));
514 ld1 {$S2,$R3,$S3,$R4},[x15],#64
572 umull $ACC3,$IN23_0,${R3}[2]
585 umlal $ACC4,$IN23_1,${R3}[2]
651 umlal $ACC3,$IN01_0,${R3}[0]
665 umlal $ACC4,$IN01_1,${R3}[0]
766 umlal2 $ACC3,$IN23_0,${R3}
774 umlal2 $ACC4,$IN23_1,${R3}
803 umlal $ACC3,$IN01_0,${R3}
812 umlal $ACC4,$IN01_1,${R3}
/OK3568_Linux_fs/kernel/arch/sparc/net/
H A Dbpf_jit_comp_32.c273 #define emit_sub(R1, R2, R3) \ argument
274 *prog++ = (SUB | RS1(R1) | RS2(R2) | RD(R3))
276 #define emit_subi(R1, IMM, R3) \ argument
277 *prog++ = (SUB | IMMED | RS1(R1) | S13(IMM) | RD(R3))
279 #define emit_add(R1, R2, R3) \ argument
280 *prog++ = (ADD | RS1(R1) | RS2(R2) | RD(R3))
282 #define emit_addi(R1, IMM, R3) \ argument
283 *prog++ = (ADD | IMMED | RS1(R1) | S13(IMM) | RD(R3))
285 #define emit_and(R1, R2, R3) \ argument
286 *prog++ = (AND | RS1(R1) | RS2(R2) | RD(R3))
[all …]
/OK3568_Linux_fs/kernel/arch/powerpc/platforms/pseries/
H A DhvCall.S34 std r3,STK_PARAM(R3)(r1); \
46 ld r3,STACK_FRAME_OVERHEAD+STK_PARAM(R3)(r1); \
60 ld r0,STACK_FRAME_OVERHEAD+STK_PARAM(R3)(r1); \
61 std r3,STACK_FRAME_OVERHEAD+STK_PARAM(R3)(r1); \
67 ld r3,STK_PARAM(R3)(r1); \
/OK3568_Linux_fs/kernel/tools/perf/arch/arm/tests/
H A Dregs_load.S7 #define R3 0x18 macro
44 str r3, [r0, #R3]
/OK3568_Linux_fs/kernel/arch/parisc/kernel/
H A Dunaligned.c109 #define R3(i) ((i)&0x1f) macro
531 ret = emulate_ldh(regs, R3(regs->iir)); in handle_unaligned()
538 ret = emulate_ldw(regs, R3(regs->iir),0); in handle_unaligned()
555 ret = emulate_ldd(regs, R3(regs->iir),0); in handle_unaligned()
575 ret = emulate_ldd(regs,R3(regs->iir),1); in handle_unaligned()
589 ret = emulate_std(regs,R3(regs->iir),1); in handle_unaligned()
/OK3568_Linux_fs/kernel/tools/perf/arch/powerpc/tests/
H A Dregs_load.S8 #define R3 3 * 8 macro
47 std 3, R3(3)
/OK3568_Linux_fs/kernel/drivers/tty/serial/
H A Dsunzilog.c206 write_zsreg(channel, R3, regs[R3] & ~RxENAB); in __load_zsregs()
253 write_zsreg(channel, R3, regs[R3]); in __load_zsregs()
536 r3 = read_zsreg(channel, R3); in sunzilog_interrupt()
790 up->curregs[R3] |= RxENAB; in __sunzilog_startup()
850 up->curregs[R3] &= ~RxENAB; in sunzilog_shutdown()
880 up->curregs[R3] &= ~RxN_MASK; in sunzilog_convert_to_zs()
884 up->curregs[R3] |= Rx5; in sunzilog_convert_to_zs()
889 up->curregs[R3] |= Rx6; in sunzilog_convert_to_zs()
894 up->curregs[R3] |= Rx7; in sunzilog_convert_to_zs()
900 up->curregs[R3] |= Rx8; in sunzilog_convert_to_zs()
[all …]
H A Dip22zilog.c187 write_zsreg(channel, R3, regs[R3] & ~RxENAB); in __load_zsregs()
220 write_zsreg(channel, R3, regs[R3]); in __load_zsregs()
437 r3 = read_zsreg(channel, R3); in ip22zilog_interrupt()
725 up->curregs[R3] |= RxENAB; in __ip22zilog_startup()
785 up->curregs[R3] &= ~RxENAB; in ip22zilog_shutdown()
1142 up->curregs[R3] = RxENAB | Rx8; in ip22zilog_prepare()
H A Dpmac_zilog.c141 write_zsreg(uap, R3, regs[R3] & ~RxENABLE); in pmz_load_zsregs()
173 write_zsreg(uap, R3, regs[R3]); in pmz_load_zsregs()
447 r3 = read_zsreg(uap_a, R3); in pmz_interrupt()
858 uap->curregs[R3] = Rx8; in __pmz_startup()
875 write_zsreg(uap, R3, uap->curregs[R3] |= RxENABLE); in __pmz_startup()
969 uap->curregs[R3] &= ~RxENABLE; in pmz_shutdown()
/OK3568_Linux_fs/kernel/arch/powerpc/mm/nohash/
H A Dtlb_low.S202 PPC_TLBIVAX(0, R3)
306 PPC_TLBILX_VA(0,R3)
357 PPC_TLBILX_VA(0,R3)
372 PPC_TLBIVAX(0,R3)
/OK3568_Linux_fs/kernel/arch/powerpc/kernel/
H A Dfpu.S57 REST_32FPVSRS(0, R4, R3)
67 SAVE_32FPVSRS(0, R4, R3)
H A Dmisc_64.S173 LBZCIX(R3,R0,R3)
188 STBCIX(R3,R0,R4)
/OK3568_Linux_fs/kernel/arch/s390/crypto/
H A Dcrc32le-vx.S65 .quad 0x0ccaa009e, 0x1751997d0 # R4, R3
73 .quad 0x14cd00bd6, 0xf20c0dfe # R4, R3
/OK3568_Linux_fs/yocto/poky/meta/recipes-bsp/grub/files/
H A DCVE-2021-3695-video-readers-png-Drop-greyscale-support-to-fix-heap.patch12 d1[R3] = d2[1];
142 - d1[R3] = d2[1];
165 - d1[R3] = d2[0];
/OK3568_Linux_fs/kernel/drivers/net/hamradio/
H A Dscc.c360 or(scc,R3,ENT_HM|RxENABLE); /* enable the receiver, hunt mode */ in start_hunt()
473 cl(scc,R3,ENT_HM|RxENABLE); /* disable the receiver */ in scc_exint()
525 or(scc,R3,ENT_HM); /* enter hunt mode for next flag */ in scc_rxint()
539 or(scc, R3, ENT_HM); in scc_rxint()
555 or(scc, R3, ENT_HM); in scc_rxint()
579 or(scc,R3,ENT_HM); /* enter hunt mode for next flag */ in scc_spint()
676 for (k = 0; InReg(ctrl->chan_A,R3) && k < SCC_IRQTIMEOUT; k++) in scc_isr()
802 wr(scc,R3,Rx8|RxCRC_ENAB); /* RX 8 bits/char, CRC, disabled */ in init_channel()
924 cl(scc, R3, RxENABLE|ENT_HM); /* switch off receiver */ in scc_key_trx()
962 cl(scc, R3, RxENABLE); in scc_key_trx()
[all …]

1234