Home
last modified time | relevance | path

Searched refs:R0 (Results 1 – 25 of 89) sorted by relevance

1234

/OK3568_Linux_fs/kernel/arch/hexagon/kernel/
H A Dvm_entry.S37 memd(R0 + #_PT_R3130) = R31:30; \
38 { memw(R0 + #_PT_R2928) = R28; \
39 R31 = memw(R0 + #_PT_ER_VMPSP); }\
40 { memw(R0 + #(_PT_R2928 + 4)) = R31; \
42 { memd(R0 + #_PT_R2726) = R27:26; \
44 memd(R0 + #_PT_R2524) = R25:24; \
45 memd(R0 + #_PT_R2322) = R23:22; \
46 memd(R0 + #_PT_R2120) = R21:20; \
47 memd(R0 + #_PT_R1918) = R19:18; \
48 memd(R0 + #_PT_R1716) = R17:16; \
[all …]
H A Dvm_switch.S55 memw(R0+#_TASK_THREAD_INFO) = THREADINFO_REG;
56 memw(R0 +#(_TASK_STRUCT_THREAD + _THREAD_STRUCT_SWITCH_SP)) = R29;
/OK3568_Linux_fs/kernel/lib/
H A Dtest_bpf.c39 #define R0 BPF_REG_0 macro
277 insn[1] = BPF_ALU32_IMM(BPF_MOV, R0, 0xcbababab); in bpf_fill_maxinsns9()
281 insn[i] = BPF_ALU32_IMM(BPF_MOV, R0, 0xfefefefe); in bpf_fill_maxinsns9()
308 insn[hlen] = BPF_ALU32_IMM(BPF_MOV, R0, 0xabababac); in bpf_fill_maxinsns10()
438 insn[0] = BPF_ALU32_IMM(BPF_MOV, R0, 1); in __bpf_fill_stxdw()
442 insn[i] = BPF_STX_XADD(size, R10, R0, -40); in __bpf_fill_stxdw()
444 insn[len - 2] = BPF_LDX_MEM(size, R0, R10, -40); in __bpf_fill_stxdw()
1115 BPF_ALU64_REG(BPF_MOV, R0, R1),
1125 BPF_ALU64_IMM(BPF_MOV, R0, -1),
1131 BPF_ALU64_IMM(BPF_MOV, R0, 1),
[all …]
/OK3568_Linux_fs/kernel/arch/x86/crypto/
H A Dtwofish-x86_64-asm_64.S29 #define R0 %rax macro
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);
231 encrypt_round(R2,R3,R0,R1,5*8);
232 encrypt_round(R0,R1,R2,R3,6*8);
233 encrypt_round(R2,R3,R0,R1,7*8);
234 encrypt_round(R0,R1,R2,R3,8*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 …]
H A Dpoly1305-x86_64-cryptogams.pl2208 my ($R0,$R1,$R2,$R3,$R4, $S1,$S2,$S3,$S4) = map("%zmm$_",(16..24));
2249 vmovdqu `16*0-64`($ctx),%x#$D0 # will become expanded ${R0}
2260 vpermd $D0,$T2,$R0 # 00003412 -> 14243444
2265 vmovdqa64 $R0,0x00(%rsp){%k2} # save in case $len%128 != 0
2266 vpsrlq \$32,$R0,$T0 # 14243444 -> 01020304
2291 vpmuludq $T0,$R0,$D0 # d0 = r0'*r0
2299 vpmuludq $T1,$R0,$M1
2314 vpmuludq $T2,$R0,$M2
2323 vpmuludq $T3,$R0,$M3
2334 vpmuludq $T4,$R0,$M4
[all …]
/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));
530 vdup.32 $R0,r2 @ r^1 in both lanes
554 vmull.u32 $D0,$R0,${R0}[1]
555 vmull.u32 $D1,$R1,${R0}[1]
556 vmull.u32 $D2,$R2,${R0}[1]
557 vmull.u32 $D3,$R3,${R0}[1]
558 vmull.u32 $D4,$R4,${R0}[1]
561 vmlal.u32 $D1,$R0,${R1}[1]
569 vmlal.u32 $D2,$R0,${R2}[1]
573 vmlal.u32 $D3,$R0,${R3}[1]
[all …]
/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));
513 ld1 {$R0,$R1,$S1,$R2},[x15],#64
577 umull $ACC0,$IN23_0,${R0}[2]
591 umlal $ACC1,$IN23_1,${R0}[2]
600 umlal $ACC2,$IN23_2,${R0}[2]
609 umlal $ACC3,$IN23_3,${R0}[2]
620 umlal $ACC4,$IN23_4,${R0}[2]
642 umlal $ACC2,$IN01_2,${R0}[0]
656 umlal $ACC0,$IN01_0,${R0}[0]
671 umlal $ACC1,$IN01_1,${R0}[0]
[all …]
/OK3568_Linux_fs/kernel/arch/sh/kernel/cpu/sh3/
H A Dswsusp.S59 ! BL=0: R7->R0 is bank0
65 ! BL=1: R7->R0 is bank1
80 ! BL=0: R7->R0 is bank0
105 ! BL=0: R7->R0 is bank0
112 ! BL=1: R7->R0 is bank1
119 ! BL=0: R7->R0 is bank0
/OK3568_Linux_fs/kernel/drivers/tty/serial/
H A Dpmac_zilog.c169 write_zsreg(uap, R0, RES_EXT_INT); in pmz_load_zsregs()
170 write_zsreg(uap, R0, RES_EXT_INT); in pmz_load_zsregs()
237 write_zsreg(uap, R0, ERR_RES); in pmz_receive_chars()
310 ch = read_zsreg(uap, R0); in pmz_receive_chars()
326 status = read_zsreg(uap, R0); in pmz_status_handle()
327 write_zsreg(uap, R0, RES_EXT_INT); in pmz_status_handle()
360 unsigned char status = read_zsreg(uap, R0); in pmz_transmit_chars()
429 write_zsreg(uap, R0, RES_Tx_P); in pmz_transmit_chars()
459 write_zsreg(uap_a, R0, RES_H_IUS); in pmz_interrupt()
484 write_zsreg(uap_b, R0, RES_H_IUS); in pmz_interrupt()
[all …]
H A Dzs.c232 while ((read_zsreg(zport, R0) & Rx_CH_AV) && --loops) in zs_receive_drain()
242 while (!(read_zsreg(zport, R0) & Tx_BUF_EMP) && --loops) { in zs_transmit_drain()
324 status_a = read_zsreg(zport_a, R0); in zs_raw_get_ab_mctrl()
325 status_b = read_zsreg(zport_b, R0); in zs_raw_get_ab_mctrl()
421 write_zsreg(zport, R0, RES_Tx_P); in zs_raw_stop_tx()
498 write_zsreg(zport_a, R0, RES_EXT_INT); in zs_enable_ms()
547 avail = read_zsreg(zport, R0) & Rx_CH_AV; in zs_receive_chars()
572 write_zsreg(zport, R0, ERR_RES); in zs_receive_chars()
656 status = read_zsreg(zport, R0); in zs_status_handle()
693 write_zsreg(zport, R0, RES_EXT_INT); in zs_status_handle()
[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/drivers/net/hamradio/
H A Ddmascc.c495 if (read_scc(priv, R0) & Tx_BUF_EMP) { in setup_adapter()
517 write_scc(priv, R0, RES_EXT_INT); in setup_adapter()
536 write_scc(priv, R0, RES_EXT_INT); in setup_adapter()
845 priv->rr0 = read_scc(priv, R0); in scc_open()
1008 write_scc(priv, R0, RES_EOM_L); in tx_on()
1017 while (read_scc(priv, R0) & Rx_CH_AV) in rx_on()
1045 write_scc(priv, R0, ERR_RES); in rx_on()
1106 write_scc(&info->priv[0], R0, RES_H_IUS); in z8530_isr()
1161 write_scc(priv, R0, ERR_RES); in rx_isr()
1166 while (read_scc(priv, R0) & Rx_CH_AV) { in rx_isr()
[all …]
/OK3568_Linux_fs/yocto/poky/meta/recipes-multimedia/mpeg2dec/files/
H A D0001-Import-revision-1206-from-upstream-to-fix-PIE-build.patch110 .macro ADJ_ALIGN_QW shift, R0, R1, R2, R3, R4
111 mov \R0, \R0, lsr #(\shift)
145 .macro ADJ_ALIGN_DW shift, R0, R1, R2
146 mov \R0, \R0, lsr #(\shift)
/OK3568_Linux_fs/kernel/arch/hexagon/mm/
H A Dstrnlen_user.S102 R0 = sub(start,isrc); define
108 R0 = add(max,#1); define
116 R0 = #0; define
/OK3568_Linux_fs/kernel/arch/sh/math-emu/
H A Dmath.c50 #define R0 (regs->regs[0]) macro
160 READ(FRn, Rm + R0 + 4); in fmov_idx_reg()
162 READ(FRn, Rm + R0); in fmov_idx_reg()
164 READ(FRn, Rm + R0); in fmov_idx_reg()
210 WRITE(FRm, Rn + R0 + 4); in fmov_reg_idx()
212 WRITE(FRm, Rn + R0); in fmov_reg_idx()
214 WRITE(FRm, Rn + R0); in fmov_reg_idx()
/OK3568_Linux_fs/kernel/drivers/net/wan/
H A Dz85230.c339 if(!(read_zsreg(c, R0)&1)) in z8530_rx()
410 if(!(read_zsreg(c, R0)&4)) in z8530_tx()
451 status = read_zsreg(chan, R0); in z8530_status()
562 status=read_zsreg(chan, R0); in z8530_dma_status()
670 u8 status=read_zsreg(chan, R0); in z8530_status_clear()
833 chk=read_zsreg(c,R0); in z8530_sync_close()
1026 chk=read_zsreg(c,R0); in z8530_sync_dma_close()
1190 chk=read_zsreg(c,R0); in z8530_sync_txdma_close()
1278 if(read_zsreg(&dev->chanA, R0)&Tx_BUF_EMP) in do_z8530_init()
1401 c->status=read_zsreg(c, R0); in z8530_channel_load()
[all …]
/OK3568_Linux_fs/kernel/tools/perf/arch/arm/tests/
H A Dregs_load.S4 #define R0 0x00 macro
41 str r0, [r0, #R0]
/OK3568_Linux_fs/kernel/arch/powerpc/mm/nohash/
H A Dtlb_low.S259 PPC_TLBILX_ALL(0,R0)
272 PPC_TLBILX_PID(0,R0)
324 PPC_TLBILX_PID(0,R0)
336 PPC_TLBILX_PID(0,R0)
343 PPC_TLBILX_ALL(0,R0)
/OK3568_Linux_fs/kernel/tools/perf/arch/powerpc/tests/
H A Dregs_load.S5 #define R0 0 macro
44 std 0, R0(3)
/OK3568_Linux_fs/u-boot/arch/arm/mach-omap2/
H A Dlowlevel_init.S42 MRC p15, 4, R0, c1, c0, 0
45 MCR p15, 4, R0, c1, c0, 0
/OK3568_Linux_fs/kernel/drivers/gpu/drm/msm/disp/dpu1/
H A Ddpu_plane.c51 R0, enumerator
806 pstate[R0]->multirect_mode = DPU_SSPP_MULTIRECT_PARALLEL; in dpu_plane_validate_multirect_v2()
815 if (dst[R1].y1 >= dst[R0].y2 + buffer_lines || in dpu_plane_validate_multirect_v2()
816 dst[R0].y1 >= dst[R1].y2 + buffer_lines) { in dpu_plane_validate_multirect_v2()
817 pstate[R0]->multirect_mode = DPU_SSPP_MULTIRECT_TIME_MX; in dpu_plane_validate_multirect_v2()
822 drm_state[R0]->plane->base.id, in dpu_plane_validate_multirect_v2()
828 if (dpu_plane[R0]->is_virtual) { in dpu_plane_validate_multirect_v2()
829 pstate[R0]->multirect_index = DPU_SSPP_RECT_1; in dpu_plane_validate_multirect_v2()
832 pstate[R0]->multirect_index = DPU_SSPP_RECT_0; in dpu_plane_validate_multirect_v2()
836 DPU_DEBUG_PLANE(dpu_plane[R0], "R0: %d - %d\n", in dpu_plane_validate_multirect_v2()
[all …]
/OK3568_Linux_fs/kernel/arch/powerpc/kernel/
H A Dmisc_64.S173 LBZCIX(R3,R0,R3)
188 STBCIX(R3,R0,R4)
322 PPC_TLBILX_ALL(0,R0)

1234