Symbol: r3
common/lib/libc/arch/arm/atomic/atomic_op_asm.h
61
#define NLO r3
common/lib/libc/arch/arm/atomic/atomic_op_asm.h
68
#define NHI r3
common/lib/libc/arch/powerpc/atomic/atomic_op_asm.h
49
mr %r10,%r3 ; \
common/lib/libc/arch/powerpc/atomic/atomic_op_asm.h
50
1: lwarx %r3,0,%r10 ; \
common/lib/libc/arch/powerpc/atomic/atomic_op_asm.h
51
insn %r5,%r3,arg ; \
common/lib/libc/arch/powerpc/atomic/atomic_op_asm.h
61
mr %r10,%r3 ; \
common/lib/libc/arch/powerpc/atomic/atomic_op_asm.h
62
1: ldarx %r3,0,%r10 ; \
common/lib/libc/arch/powerpc/atomic/atomic_op_asm.h
63
insn %r5,%r3,arg ; \
common/lib/libc/arch/powerpc/atomic/atomic_op_asm.h
72
mr %r10,%r3 ; \
common/lib/libc/arch/powerpc/atomic/atomic_op_asm.h
73
1: lwarx %r3,0,%r10 ; \
common/lib/libc/arch/powerpc/atomic/atomic_op_asm.h
74
insn %r3,%r3,arg ; \
common/lib/libc/arch/powerpc/atomic/atomic_op_asm.h
76
stwcx. %r3,0,%r10 ; \
common/lib/libc/arch/powerpc/atomic/atomic_op_asm.h
84
mr %r10,%r3 ; \
common/lib/libc/arch/powerpc/atomic/atomic_op_asm.h
85
1: ldarx %r3,0,%r10 ; \
common/lib/libc/arch/powerpc/atomic/atomic_op_asm.h
86
insn %r3,%r3,arg ; \
common/lib/libc/arch/powerpc/atomic/atomic_op_asm.h
87
stdcx. %r3,0,%r10 ; \
games/rogue/level.c
210
make_room(short rn, short r1, short r2, short r3)
games/rogue/level.c
293
if ((rn != r1) && (rn != r2) && (rn != r3) && rand_percent(40)) {
lib/libc/arch/arm/SYS.h
89
bcc 86f; push {r3,lr}; bl CERROR; pop {r3,pc}; 86:
lib/libc/arch/powerpc64/SYS.h
16
mr %r31,%r3 ;\
lib/libc/arch/powerpc64/SYS.h
19
stint %r31,0(%r3) ;\
lib/libc/arch/powerpc64/SYS.h
24
li %r3,-1 ;\
lib/libc/arch/powerpc64/SYS.h
29
stw %r3,0(%r4) ;\
lib/libc/arch/powerpc64/SYS.h
30
li %r3,-1 ;\
lib/libc/arch/sh3/SYS.h
72
mov.l @(r0, r2), r3; \
lib/libc/arch/sh3/SYS.h
73
jmp @r3; \
lib/libc/arch/sh3/SYS.h
82
mov.l 912f, r3; \
lib/libc/arch/sh3/SYS.h
83
jmp @r3; \
lib/libm/ld128/e_lgammal_r.c
149
r3 = 1.78691044735267497452847829579514367e+00L,
lib/libm/ld128/e_lgammal_r.c
302
q = one+y*(r1+y*(r2+y*(r3+y*(r4+y*(r5+y*(r6+y*(r7+y*(r8+
lib/libm/ld80/e_lgammal_r.c
329
q = 1+y*(r1+y*(r2+y*(r3+y*(r4+y*(r5+y*(r6+y*r7))))));
lib/libm/noieee_src/n_lgamma.c
228
p = r0+z*(r1+z*(r2+z*(r3+z*(r4+z*r5))));
lib/libm/src/e_lgamma_r.c
144
r3 = 1.71933865632803078993e-01, /* 0x3FC601ED, 0xCCFBDF27 */
lib/libm/src/e_lgamma_r.c
275
q = one+y*(r1+y*(r2+y*(r3+y*(r4+y*(r5+y*r6)))));
lib/libm/src/e_lgammaf_r.c
211
q = one+y*(r1+y*(r2+y*(r3+y*(r4+y*(r5+y*r6)))));
lib/libm/src/e_lgammaf_r.c
80
r3 = 1.7193385959e-01, /* 0x3e300f6e */
sys/arch/acorn32/stand/lib/riscoscalls.h
213
extern void os_readsysinfo(int what, int *r0, int *r1, int *r2, int *r3, int *r4);
sys/arch/acorn32/stand/nbfs/nbfs.c
180
int fh = r->r3;
sys/arch/acorn32/stand/nbfs/nbfs.c
205
r->r3 = st.st_size;
sys/arch/acorn32/stand/nbfs/nbfs.c
223
size_t size = r->r3;
sys/arch/acorn32/stand/nbfs/nbfs.c
298
r->r0 = r->r2 = r->r3 = r->r4 = r->r5 = 0;
sys/arch/acorn32/stand/nbfs/nbfs.c
305
r->r2 = r->r3 = 0;
sys/arch/acorn32/stand/nbfs/nbfs.c
352
size_t maxcount = r->r3;
sys/arch/acorn32/stand/nbfs/nbfs.c
430
r->r3 = count;
sys/arch/acorn32/stand/nbfs/nbfs.h
8
uint32_t r0, r1, r2, r3, r4, r5, r6, r7;
sys/arch/arm/arm/smccc.c
112
register register_t r3 asm ("r3");
sys/arch/arm/arm/smccc.c
124
r3 = args[3];
sys/arch/arm/arm/smccc.c
129
"=r" (r0), "=r" (r1), "=r" (r2), "=r" (r3) :
sys/arch/arm/arm/smccc.c
130
"r" (r0), "r" (r1), "r" (r2), "r" (r3), "r" (r4) :
sys/arch/arm/arm/smccc.c
134
"=r" (r0), "=r" (r1), "=r" (r2), "=r" (r3) :
sys/arch/arm/arm/smccc.c
135
"r" (r0), "r" (r1), "r" (r2), "r" (r3), "r" (r4) :
sys/arch/arm/arm/smccc.c
149
*res3 = r3;
sys/arch/arm/include/arm32/frame.h
434
stmdb sp, {r0-r3}; /* Save 4 registers */ \
sys/arch/arm/include/arm32/frame.h
437
mrs r3, spsr; /* Save xxx32 spsr */ \
sys/arch/arm/include/arm32/frame.h
442
and r2, r3, #(PSR_MODE); \
sys/arch/arm/include/arm32/frame.h
456
msr spsr_fsxc, r3; /* Restore correct spsr */ \
sys/arch/arm/include/arm32/frame.h
457
ldmdb r1, {r0-r3}; /* Restore 4 regs from xxx mode */ \
sys/arch/arm/sociox/if_scx.c
1616
rlen = le32toh(sc->sc_rxdescs[i].r3) >> 16;
sys/arch/arm/sociox/if_scx.c
536
__rxd->r3 = htole32(__z - 4); \
sys/arch/arm/sociox/if_scx.c
83
uint32_t r0, r1, r2, r3;
sys/arch/evbarm/gumstix/gumstix_machdep.c
417
process_kernel_args_liner((char *)uboot_args[r3]);
sys/arch/powerpc/fpu/fpu_add.c
194
FPU_SUBCS(r3, x->fp_mant[3], y->fp_mant[3]);
sys/arch/powerpc/fpu/fpu_add.c
200
if ((r0 | r1 | r2 | r3) == 0) {
sys/arch/powerpc/fpu/fpu_add.c
218
FPU_SUBS(r3, 0, r3);
sys/arch/powerpc/fpu/fpu_add.c
223
r->fp_mant[3] = r3;
sys/arch/powerpc/fpu/fpu_add.c
69
u_int r0, r1, r2, r3;
sys/arch/powerpc/fpu/fpu_div.c
161
u_int r0, r1, r2, r3, d0, d1, d2, d3, y0, y1, y2, y3;
sys/arch/powerpc/fpu/fpu_div.c
233
FPU_SUBS(d3, r3, y3); FPU_SUBCS(d2, r2, y2); \
sys/arch/powerpc/fpu/fpu_div.c
241
FPU_ADDS(r3, r3, r3); FPU_ADDCS(r2, r2, r2); \
sys/arch/powerpc/fpu/fpu_div.c
246
r2 = (r2 << 1) | (r3 >> 31), r3 <<= 1
sys/arch/powerpc/fpu/fpu_div.c
255
r0 = d0, r1 = d1, r2 = d2, r3 = d3; \
sys/arch/powerpc/fpu/fpu_div.c
269
r3 = x->fp_mant[3];
sys/arch/powerpc/fpu/fpu_div.c
279
r0 = d0, r1 = d1, r2 = d2, r3 = d3;
sys/arch/powerpc/fpu/fpu_div.c
291
x->fp_sticky = r0 | r1 | r2 | r3;
sys/arch/sandpoint/stand/altboot/vge.c
270
rxd[i].r3 = htole32(FRAMESIZE << 16);
sys/arch/sandpoint/stand/altboot/vge.c
68
uint32_t r0, r1, r2, r3;
sys/arch/sandpoint/stand/altboot/wm.c
182
rxd[0].r3 = 0;
sys/arch/sandpoint/stand/altboot/wm.c
185
rxd[0].r3 = 0;
sys/arch/sandpoint/stand/altboot/wm.c
264
rxstat = le32toh(rxd->r3);
sys/arch/sandpoint/stand/altboot/wm.c
275
rxd->r3 = 0;
sys/arch/sandpoint/stand/altboot/wm.c
288
rxd->r3 = 0;
sys/arch/sandpoint/stand/altboot/wm.c
68
uint32_t r3; /* 31:16 special, 15:8 errors, 7:0 status */
sys/arch/sh3/include/locore.h
113
shlr r3 /* r3 = PSL_RB */ ;\
sys/arch/sh3/include/locore.h
115
not r3, r3 ;\
sys/arch/sh3/include/locore.h
116
and r1, r3 ;\
sys/arch/sh3/include/locore.h
117
ldc r3, sr /* SR.RB = 0 */
sys/arch/sh3/include/locore.h
154
mov.l @r14+, r3 /* tf_r3 */ ;\
sys/arch/sh3/include/locore.h
75
mov #0x40, r3 ;\
sys/arch/sh3/include/locore.h
77
swap.b r3, r3 ;\
sys/arch/sh3/include/locore.h
79
swap.w r3, r3 /* r3 = PSL_MD */ ;\
sys/arch/sh3/include/locore.h
81
tst r3, r2 /* if (SSR.MD == 0) T = 1 */ ;\
sys/arch/sh3/sh3/db_interface.c
642
TF(r3);
sys/arch/sparc/fpu/fpu_add.c
177
FPU_SUBCS(r3, x->fp_mant[3], y->fp_mant[3]);
sys/arch/sparc/fpu/fpu_add.c
183
if ((r0 | r1 | r2 | r3) == 0) {
sys/arch/sparc/fpu/fpu_add.c
201
FPU_SUBS(r3, 0, r3);
sys/arch/sparc/fpu/fpu_add.c
206
r->fp_mant[3] = r3;
sys/arch/sparc/fpu/fpu_add.c
68
u_int r0, r1, r2, r3;
sys/arch/sparc/fpu/fpu_div.c
157
u_int r0, r1, r2, r3, d0, d1, d2, d3, y0, y1, y2, y3;
sys/arch/sparc/fpu/fpu_div.c
204
FPU_SUBS(d3, r3, y3); FPU_SUBCS(d2, r2, y2); \
sys/arch/sparc/fpu/fpu_div.c
212
FPU_ADDS(r3, r3, r3); FPU_ADDCS(r2, r2, r2); \
sys/arch/sparc/fpu/fpu_div.c
217
r2 = (r2 << 1) | (r3 >> 31), r3 <<= 1
sys/arch/sparc/fpu/fpu_div.c
226
r0 = d0, r1 = d1, r2 = d2, r3 = d3; \
sys/arch/sparc/fpu/fpu_div.c
240
r3 = x->fp_mant[3];
sys/arch/sparc/fpu/fpu_div.c
250
r0 = d0, r1 = d1, r2 = d2, r3 = d3;
sys/arch/sparc/fpu/fpu_div.c
262
x->fp_sticky = r0 | r1 | r2 | r3;
sys/arch/vax/include/asm.h
127
movab \tbladdr, %r3
sys/arch/vax/include/asm.h
129
movf (%r3)+, %r0
sys/arch/vax/include/asm.h
132
addf2 (%r3)+, %r0 /* result += c[n] */
sys/arch/vax/include/asm.h
140
movab \tbladdr, %r3
sys/arch/vax/include/asm.h
142
movd (%r3)+, %r0
sys/arch/vax/include/asm.h
145
addd2 (%r3)+, %r0 /* result += c[n] */
sys/arch/vax/include/reg.h
37
int r3;
sys/arch/vax/include/signal.h
101
unsigned r0, r1, r2, r3, r4, r5; /* Registers saved when interrupt */
sys/arch/vax/vax/compat_13_machdep.c
187
tramp.r0 = tramp.r1 = tramp.r2 = tramp.r3 = tramp.r4 = tramp.r5 = 0;
sys/crypto/adiantum/adiantum.c
215
uint32_t r3 = P->r[3];
sys/crypto/adiantum/adiantum.c
265
p0 = r0*k0 + 5*r4*k1 + 5*r3*k2 + 5*r2*k3 + 5*r1*k4;
sys/crypto/adiantum/adiantum.c
266
p1 = r1*k0 + r0*k1 + 5*r4*k2 + 5*r3*k3 + 5*r2*k4;
sys/crypto/adiantum/adiantum.c
267
p2 = r2*k0 + r1*k1 + r0*k2 + 5*r4*k3 + 5*r3*k4;
sys/crypto/adiantum/adiantum.c
268
p3 = r3*k0 + r2*k1 + r1*k2 + r0*k3 + 5*r4*k4;
sys/crypto/adiantum/adiantum.c
269
p4 = r4*k0 + r3*k1 + r2*k2 + r1*k3 + r0*k4;
sys/crypto/aes/aes_ct64_dec.c
120
uint64_t r0, r1, r2, r3, r4, r5, r6, r7;
sys/crypto/aes/aes_ct64_dec.c
133
r3 = (q3 >> 16) | (q3 << 48);
sys/crypto/aes/aes_ct64_dec.c
142
q[3] = q0 ^ q1 ^ q2 ^ q5 ^ q6 ^ r0 ^ r2 ^ r3 ^ r5 ^ rotr32(q0 ^ q1 ^ q3 ^ q5 ^ q6 ^ q7 ^ r0 ^ r3 ^ r5 ^ r7);
sys/crypto/aes/aes_ct64_dec.c
143
q[4] = q1 ^ q2 ^ q3 ^ q5 ^ r1 ^ r3 ^ r4 ^ r5 ^ r6 ^ r7 ^ rotr32(q1 ^ q2 ^ q4 ^ q5 ^ q7 ^ r1 ^ r4 ^ r5 ^ r6);
sys/crypto/aes/aes_ct64_dec.c
145
q[6] = q3 ^ q4 ^ q5 ^ q7 ^ r3 ^ r5 ^ r6 ^ r7 ^ rotr32(q3 ^ q4 ^ q6 ^ q7 ^ r3 ^ r6 ^ r7);
sys/crypto/aes/aes_ct64_enc.c
76
uint64_t r0, r1, r2, r3, r4, r5, r6, r7;
sys/crypto/aes/aes_ct64_enc.c
89
r3 = (q3 >> 16) | (q3 << 48);
sys/crypto/aes/aes_ct64_enc.c
98
q[3] = q2 ^ r2 ^ q7 ^ r7 ^ r3 ^ rotr32(q3 ^ r3);
sys/crypto/aes/aes_ct64_enc.c
99
q[4] = q3 ^ r3 ^ q7 ^ r7 ^ r4 ^ rotr32(q4 ^ r4);
sys/crypto/aes/aes_ct_dec.c
131
uint32_t r0, r1, r2, r3, r4, r5, r6, r7;
sys/crypto/aes/aes_ct_dec.c
144
r3 = (q3 >> 8) | (q3 << 24);
sys/crypto/aes/aes_ct_dec.c
153
q[3] = q0 ^ q1 ^ q2 ^ q5 ^ q6 ^ r0 ^ r2 ^ r3 ^ r5 ^ rotr16(q0 ^ q1 ^ q3 ^ q5 ^ q6 ^ q7 ^ r0 ^ r3 ^ r5 ^ r7);
sys/crypto/aes/aes_ct_dec.c
154
q[4] = q1 ^ q2 ^ q3 ^ q5 ^ r1 ^ r3 ^ r4 ^ r5 ^ r6 ^ r7 ^ rotr16(q1 ^ q2 ^ q4 ^ q5 ^ q7 ^ r1 ^ r4 ^ r5 ^ r6);
sys/crypto/aes/aes_ct_dec.c
156
q[6] = q3 ^ q4 ^ q5 ^ q7 ^ r3 ^ r5 ^ r6 ^ r7 ^ rotr16(q3 ^ q4 ^ q6 ^ q7 ^ r3 ^ r6 ^ r7);
sys/crypto/aes/aes_ct_enc.c
73
uint32_t r0, r1, r2, r3, r4, r5, r6, r7;
sys/crypto/aes/aes_ct_enc.c
86
r3 = (q3 >> 8) | (q3 << 24);
sys/crypto/aes/aes_ct_enc.c
95
q[3] = q2 ^ r2 ^ q7 ^ r7 ^ r3 ^ rotr16(q3 ^ r3);
sys/crypto/aes/aes_ct_enc.c
96
q[4] = q3 ^ r3 ^ q7 ^ r7 ^ r4 ^ rotr16(q4 ^ r4);
sys/crypto/aes/arch/x86/aes_sse2_4x32_dec.c
149
__m128i r0, r1, r2, r3, r4, r5, r6, r7;
sys/crypto/aes/arch/x86/aes_sse2_4x32_dec.c
162
r3 = _mm_srli_epi32(q3, 8) | _mm_slli_epi32(q3, 24);
sys/crypto/aes/arch/x86/aes_sse2_4x32_dec.c
171
q[3] = q0 ^ q1 ^ q2 ^ q5 ^ q6 ^ r0 ^ r2 ^ r3 ^ r5 ^ rotr16(q0 ^ q1 ^ q3 ^ q5 ^ q6 ^ q7 ^ r0 ^ r3 ^ r5 ^ r7);
sys/crypto/aes/arch/x86/aes_sse2_4x32_dec.c
172
q[4] = q1 ^ q2 ^ q3 ^ q5 ^ r1 ^ r3 ^ r4 ^ r5 ^ r6 ^ r7 ^ rotr16(q1 ^ q2 ^ q4 ^ q5 ^ q7 ^ r1 ^ r4 ^ r5 ^ r6);
sys/crypto/aes/arch/x86/aes_sse2_4x32_dec.c
174
q[6] = q3 ^ q4 ^ q5 ^ q7 ^ r3 ^ r5 ^ r6 ^ r7 ^ rotr16(q3 ^ q4 ^ q6 ^ q7 ^ r3 ^ r6 ^ r7);
sys/crypto/aes/arch/x86/aes_sse2_4x32_enc.c
101
r3 = _mm_srli_epi32(q3, 8) | _mm_slli_epi32(q3, 24);
sys/crypto/aes/arch/x86/aes_sse2_4x32_enc.c
110
q[3] = q2 ^ r2 ^ q7 ^ r7 ^ r3 ^ rotr16(q3 ^ r3);
sys/crypto/aes/arch/x86/aes_sse2_4x32_enc.c
111
q[4] = q3 ^ r3 ^ q7 ^ r7 ^ r4 ^ rotr16(q4 ^ r4);
sys/crypto/aes/arch/x86/aes_sse2_4x32_enc.c
88
__m128i r0, r1, r2, r3, r4, r5, r6, r7;
sys/crypto/aes/arch/x86/aes_sse2_4x32_subr.c
51
#define _MM_TRANSPOSE4_EPI32(r0, r1, r2, r3) do \
sys/crypto/aes/arch/x86/aes_sse2_4x32_subr.c
56
_mm_tmp2 = _mm_unpacklo_epi32(r2, r3); \
sys/crypto/aes/arch/x86/aes_sse2_4x32_subr.c
58
_mm_tmp3 = _mm_unpackhi_epi32(r2, r3); \
sys/crypto/aes/arch/x86/aes_sse2_4x32_subr.c
62
(r3) = (__m128i)_mm_movehl_ps((__m128)_mm_tmp3, (__m128)_mm_tmp1); \
sys/crypto/chacha/arch/arm/chacha_neon.c
113
uint32x4_t r0, r1, r2, r3;
sys/crypto/chacha/arch/arm/chacha_neon.c
119
r3 = *p3;
sys/crypto/chacha/arch/arm/chacha_neon.c
122
r0 = vaddq_u32(r0, r1); r3 ^= r0; r3 = rol16(r3);
sys/crypto/chacha/arch/arm/chacha_neon.c
123
r2 = vaddq_u32(r2, r3); r1 ^= r2; r1 = rol12(r1);
sys/crypto/chacha/arch/arm/chacha_neon.c
124
r0 = vaddq_u32(r0, r1); r3 ^= r0; r3 = rol8(r3);
sys/crypto/chacha/arch/arm/chacha_neon.c
125
r2 = vaddq_u32(r2, r3); r1 ^= r2; r1 = rol7(r1);
sys/crypto/chacha/arch/arm/chacha_neon.c
130
c3 = vextq_u32(r3, r3, 3);
sys/crypto/chacha/arch/arm/chacha_neon.c
140
r3 = vextq_u32(c3, c3, 1);
sys/crypto/chacha/arch/arm/chacha_neon.c
146
*p3 = r3;
sys/crypto/chacha/arch/arm/chacha_neon.c
157
uint32x4_t r0, r1, r2, r3;
sys/crypto/chacha/arch/arm/chacha_neon.c
162
r3 = in3 = vreinterpretq_u32_u8(vld1q_u8(in));
sys/crypto/chacha/arch/arm/chacha_neon.c
164
chacha_permute(&r0, &r1, &r2, &r3, nr);
sys/crypto/chacha/arch/arm/chacha_neon.c
169
vst1q_u8(out + 48, vreinterpretq_u8_u32(vaddq_u32(r3, in3)));
sys/crypto/chacha/arch/arm/chacha_neon.c
179
uint32x4_t r0, r1, r2, r3;
sys/crypto/chacha/arch/arm/chacha_neon.c
184
r3 = vreinterpretq_u32_u8(vld1q_u8(in));
sys/crypto/chacha/arch/arm/chacha_neon.c
186
chacha_permute(&r0, &r1, &r2, &r3, nr);
sys/crypto/chacha/arch/arm/chacha_neon.c
189
vst1q_u8(out + 16, vreinterpretq_u8_u32(r3));
sys/crypto/chacha/arch/arm/chacha_neon.c
207
uint32x4_t r0, r1, r2, r3;
sys/crypto/chacha/arch/arm/chacha_neon.c
223
r3 = in3;
sys/crypto/chacha/arch/arm/chacha_neon.c
224
chacha_permute(&r0, &r1, &r2, &r3, nr);
sys/crypto/chacha/arch/arm/chacha_neon.c
228
r3 = vaddq_u32(r3, in3);
sys/crypto/chacha/arch/arm/chacha_neon.c
236
vst1q_u8(buf + 48, vreinterpretq_u8_u32(r3));
sys/crypto/chacha/arch/arm/chacha_neon.c
245
vst1q_u8(s + 48, vreinterpretq_u8_u32(r3));
sys/crypto/chacha/arch/arm/chacha_neon.c
267
uint32x4_t r0, r1, r2, r3;
sys/crypto/chacha/arch/arm/chacha_neon.c
283
r3 = in3;
sys/crypto/chacha/arch/arm/chacha_neon.c
284
chacha_permute(&r0, &r1, &r2, &r3, nr);
sys/crypto/chacha/arch/arm/chacha_neon.c
288
r3 = vaddq_u32(r3, in3);
sys/crypto/chacha/arch/arm/chacha_neon.c
297
vst1q_u8(buf + 48, vreinterpretq_u8_u32(r3));
sys/crypto/chacha/arch/arm/chacha_neon.c
311
r3 ^= vreinterpretq_u32_u8(vld1q_u8(p + 48));
sys/crypto/chacha/arch/arm/chacha_neon.c
315
vst1q_u8(s + 48, vreinterpretq_u8_u32(r3));
sys/crypto/chacha/arch/x86/chacha_sse2.c
103
_mm_storeu_si128((__m128i *)out + 3, _mm_add_epi32(r3, in3));
sys/crypto/chacha/arch/x86/chacha_sse2.c
113
__m128i r0, r1, r2, r3;
sys/crypto/chacha/arch/x86/chacha_sse2.c
118
r3 = _mm_loadu_si128((const __m128i *)in);
sys/crypto/chacha/arch/x86/chacha_sse2.c
120
chacha_permute(&r0, &r1, &r2, &r3, nr);
sys/crypto/chacha/arch/x86/chacha_sse2.c
123
_mm_storeu_si128((__m128i *)out + 1, r3);
sys/crypto/chacha/arch/x86/chacha_sse2.c
308
__m128i r0, r1, r2, r3;
sys/crypto/chacha/arch/x86/chacha_sse2.c
320
r3 = in3;
sys/crypto/chacha/arch/x86/chacha_sse2.c
321
chacha_permute(&r0, &r1, &r2, &r3, nr);
sys/crypto/chacha/arch/x86/chacha_sse2.c
325
r3 = _mm_add_epi32(r3, in3);
sys/crypto/chacha/arch/x86/chacha_sse2.c
333
_mm_storeu_si128((__m128i *)buf + 3, r3);
sys/crypto/chacha/arch/x86/chacha_sse2.c
342
_mm_storeu_si128((__m128i *)s + 3, r3);
sys/crypto/chacha/arch/x86/chacha_sse2.c
464
__m128i r0, r1, r2, r3;
sys/crypto/chacha/arch/x86/chacha_sse2.c
47
__m128i r0, r1, r2, r3;
sys/crypto/chacha/arch/x86/chacha_sse2.c
476
r3 = in3;
sys/crypto/chacha/arch/x86/chacha_sse2.c
477
chacha_permute(&r0, &r1, &r2, &r3, nr);
sys/crypto/chacha/arch/x86/chacha_sse2.c
481
r3 = _mm_add_epi32(r3, in3);
sys/crypto/chacha/arch/x86/chacha_sse2.c
490
_mm_storeu_si128((__m128i *)buf + 3, r3);
sys/crypto/chacha/arch/x86/chacha_sse2.c
504
r3 ^= _mm_loadu_si128((const __m128i *)p + 3);
sys/crypto/chacha/arch/x86/chacha_sse2.c
508
_mm_storeu_si128((__m128i *)s + 3, r3);
sys/crypto/chacha/arch/x86/chacha_sse2.c
53
r3 = *p3;
sys/crypto/chacha/arch/x86/chacha_sse2.c
56
r0 = _mm_add_epi32(r0, r1); r3 ^= r0; r3 = rol32(r3, 16);
sys/crypto/chacha/arch/x86/chacha_sse2.c
57
r2 = _mm_add_epi32(r2, r3); r1 ^= r2; r1 = rol32(r1, 12);
sys/crypto/chacha/arch/x86/chacha_sse2.c
58
r0 = _mm_add_epi32(r0, r1); r3 ^= r0; r3 = rol32(r3, 8);
sys/crypto/chacha/arch/x86/chacha_sse2.c
59
r2 = _mm_add_epi32(r2, r3); r1 ^= r2; r1 = rol32(r1, 7);
sys/crypto/chacha/arch/x86/chacha_sse2.c
64
c3 = _mm_shuffle_epi32(r3, 0x93);
sys/crypto/chacha/arch/x86/chacha_sse2.c
74
r3 = _mm_shuffle_epi32(c3, 0x39);
sys/crypto/chacha/arch/x86/chacha_sse2.c
80
*p3 = r3;
sys/crypto/chacha/arch/x86/chacha_sse2.c
91
__m128i r0, r1, r2, r3;
sys/crypto/chacha/arch/x86/chacha_sse2.c
96
r3 = in3 = _mm_loadu_si128((const __m128i *)in);
sys/crypto/chacha/arch/x86/chacha_sse2.c
98
chacha_permute(&r0, &r1, &r2, &r3, nr);
sys/dev/ic/i82365.c
952
int r1, r2, r3, r4, r5, r6;
sys/dev/ic/i82365.c
956
r3 = pcic_read(h, mem_map_index[win].sysmem_stop_msb);
sys/dev/ic/i82365.c
962
"%02x%02x\n", win, r1, r2, r3, r4, r5, r6));
sys/dev/ic/rt2661.c
186
uint32_t r1, r2, r3, r4;
sys/dev/ic/rt2661.c
2256
rt2661_rf_write(sc, RAL_RF3, rfprog[i].r3 | power << 7);
sys/dev/ic/rt2661.c
2263
rt2661_rf_write(sc, RAL_RF3, rfprog[i].r3 | power << 7 | 1);
sys/dev/ic/rt2661.c
2270
rt2661_rf_write(sc, RAL_RF3, rfprog[i].r3 | power << 7);
sys/dev/ic/rt2860.c
194
uint32_t r1, r2, r3, r4;
sys/dev/ic/rt2860.c
2365
uint32_t r2, r3, r4;
sys/dev/ic/rt2860.c
2393
r3 = rfprog[i].r3 | txpow1 << 7;
sys/dev/ic/rt2860.c
2398
rt2860_rf_write(sc, RT2860_RF3, r3);
sys/dev/ic/rt2860.c
2405
rt2860_rf_write(sc, RT2860_RF3, r3 | 1);
sys/dev/ic/rt2860.c
2412
rt2860_rf_write(sc, RT2860_RF3, r3);
sys/dev/ic/tcic2.c
848
int r1, r2, r3;
sys/dev/ic/tcic2.c
852
r3 = tcic_read_ind_2(h, TCIC_WR_MCTL_N(hwwin));
sys/dev/ic/tcic2.c
855
win, hwwin, r1, r2, r3));
sys/dev/pci/if_iwn.c
3938
int32_t r1, r2, r3, r4, temp;
sys/dev/pci/if_iwn.c
3942
r3 = le32toh(uc->temp[2].chan20MHz);
sys/dev/pci/if_iwn.c
3945
if (r1 == r3) /* Prevents division by 0 (should not happen). */
sys/dev/pci/if_iwn.c
3951
temp = (259 * (r4 - r2)) / (r3 - r1);
sys/dev/pci/if_kse.c
158
uint32_t r0, r1, r2, r3;
sys/dev/pci/if_kse.c
743
sc->sc_rxdescs[i].r3 = paddr;
sys/dev/pci/if_kse.c
746
sc->sc_rxdescs[KSE_NRXDESC - 1].r3 = KSE_CDRXADDR(sc, 0);
sys/dev/pci/pccbb.c
2617
int r1, r2, r3, r4, r5, r6, r7 = 0;
sys/dev/pci/pccbb.c
2621
r3 = Pcic_read(sc, regbase_win + PCIC_SMM_STOP_LOW);
sys/dev/pci/pccbb.c
2630
"%02x%02x", win, r1, r2, r3, r4, r5, r6);
sys/dev/usb/if_rum.c
1711
rum_rf_write(sc, RT2573_RF3, rfprog[i].r3 | power << 7);
sys/dev/usb/if_rum.c
1716
rum_rf_write(sc, RT2573_RF3, rfprog[i].r3 | power << 7 | 1);
sys/dev/usb/if_rum.c
1721
rum_rf_write(sc, RT2573_RF3, rfprog[i].r3 | power << 7);
sys/dev/usb/if_rum.c
226
uint32_t r1, r2, r3, r4;
sys/dev/usb/if_run.c
2974
uint32_t r2, r3, r4;
sys/dev/usb/if_run.c
3002
r3 = rfprog[i].r3 | txpow1 << 7;
sys/dev/usb/if_run.c
3007
run_rt2870_rf_write(sc, RT2860_RF3, r3);
sys/dev/usb/if_run.c
3014
run_rt2870_rf_write(sc, RT2860_RF3, r3 | 1);
sys/dev/usb/if_run.c
3021
run_rt2870_rf_write(sc, RT2860_RF3, r3);
sys/dev/usb/if_run.c
482
uint32_t r1, r2, r3, r4;
sys/dev/usb/if_zyd.c
1071
uint32_t r1, r2, r3;
sys/dev/usb/if_zyd.c
1076
(void)zyd_rfwrite(sc, rfprog[chan - 1].r3);
tests/kernel/arch/vax/execregs.c
106
register long r3 __asm("r3") = nonnull(3);
tests/kernel/arch/vax/execregs.c
144
"+r"(r3),
tests/kernel/arch/vax/execregs.c
59
register long r3 __asm("r3") = nonnull(3);
tests/kernel/arch/vax/execregs.c
83
"+r"(r3),