common/lib/libc/arch/arm/atomic/atomic_op_asm.h
60
#define NHI r2
common/lib/libc/arch/arm/atomic/atomic_op_asm.h
67
#define NLO r2
games/backgammon/common_source/odds.c
44
odds(int r1, int r2, int val)
games/backgammon/common_source/odds.c
55
if (r2-- == 0) {
games/backgammon/common_source/odds.c
61
table[r2][r1] += val;
games/backgammon/common_source/odds.c
62
table[r1][r2] += val;
games/gomoku/main.c
478
direction r1, r2;
games/gomoku/main.c
549
parse_direction(&str, &r2) &&
games/gomoku/main.c
552
+ board[s2].s_frame[r2];
games/gomoku/main.c
554
stoc(s1), pdir[r1], stoc(s2), pdir[r2],
games/monop/cards.c
209
int r1, r2;
games/monop/cards.c
226
r2 = roll(1, dp->num_cards) - 1;
games/monop/cards.c
227
temp = dp->cards[r2];
games/monop/cards.c
228
dp->cards[r2] = dp->cards[r1];
games/monop/execute.c
103
printf("roll is %d, %d\n", r1=roll(1, 6), r2=roll(1, 6));
games/monop/execute.c
106
if (!move_jail(r1, r2)) {
games/monop/execute.c
112
if (r1 == r2 && ++num_doub == 3) {
games/monop/execute.c
118
move(r1+r2);
games/monop/execute.c
120
if (r1 != r2 || was_jail)
games/monop/execute.c
99
int r1, r2;
games/monop/jail.c
83
move_jail(int r1, int r2)
games/monop/jail.c
85
if (r1 != r2) {
games/monop/jail.c
94
move(r1+r2);
games/monop/jail.c
95
r1 = r2 - 1; /* kludge: stop new roll w/doub */
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)) {
include/vis_proto.h
100
vis_fpsub32(vis_d64 r1, vis_d64 r2)
include/vis_proto.h
1004
vis_fxnors(vis_f32 r1, vis_f32 r2)
include/vis_proto.h
1009
: "f"(r1), "f"(r2));
include/vis_proto.h
1015
vis_fornots(vis_f32 r1, vis_f32 r2)
include/vis_proto.h
1020
: "f"(r1), "f"(r2));
include/vis_proto.h
1026
vis_fandnots(vis_f32 r1, vis_f32 r2)
include/vis_proto.h
1031
: "f"(r1), "f"(r2));
include/vis_proto.h
106
: "f"(r1), "f"(r2));
include/vis_proto.h
112
vis_fpadd16s(vis_f32 r1, vis_f32 r2)
include/vis_proto.h
118
: "f"(r1), "f"(r2));
include/vis_proto.h
124
vis_fpsub16s(vis_f32 r1, vis_f32 r2)
include/vis_proto.h
130
: "f"(r1), "f"(r2));
include/vis_proto.h
136
vis_fpadd32s(vis_f32 r1, vis_f32 r2)
include/vis_proto.h
142
: "f"(r1), "f"(r2));
include/vis_proto.h
148
vis_fpsub32s(vis_f32 r1, vis_f32 r2)
include/vis_proto.h
154
: "f"(r1), "f"(r2));
include/vis_proto.h
174
vis_fpack32(vis_d64 r1, vis_d64 r2)
include/vis_proto.h
180
: "f"(r1), "f"(r2));
include/vis_proto.h
210
vis_fpmerge(vis_f32 r1, vis_f32 r2)
include/vis_proto.h
216
: "f"(r1), "f"(r2));
include/vis_proto.h
497
vis_u32 r2 = *((vis_u32 *)&f2);
include/vis_proto.h
499
out = ((vis_u64)r1 << 32ULL) | r2;
include/vis_proto.h
64
vis_fpadd16(vis_d64 r1, vis_d64 r2)
include/vis_proto.h
70
: "f"(r1), "f"(r2));
include/vis_proto.h
76
vis_fpsub16(vis_d64 r1, vis_d64 r2)
include/vis_proto.h
82
: "f"(r1), "f"(r2));
include/vis_proto.h
861
vis_for(vis_d64 r1, vis_d64 r2)
include/vis_proto.h
866
: "f"(r1), "f"(r2));
include/vis_proto.h
872
vis_fand(vis_d64 r1, vis_d64 r2)
include/vis_proto.h
877
: "f"(r1), "f"(r2));
include/vis_proto.h
88
vis_fpadd32(vis_d64 r1, vis_d64 r2)
include/vis_proto.h
883
vis_fxor(vis_d64 r1, vis_d64 r2)
include/vis_proto.h
888
: "f"(r1), "f"(r2));
include/vis_proto.h
894
vis_fnor(vis_d64 r1, vis_d64 r2)
include/vis_proto.h
899
: "f"(r1), "f"(r2));
include/vis_proto.h
905
vis_fnand(vis_d64 r1, vis_d64 r2)
include/vis_proto.h
910
: "f"(r1), "f"(r2));
include/vis_proto.h
916
vis_fxnor(vis_d64 r1, vis_d64 r2)
include/vis_proto.h
921
: "f"(r1), "f"(r2));
include/vis_proto.h
927
vis_fornot(vis_d64 r1, vis_d64 r2)
include/vis_proto.h
932
: "f"(r1), "f"(r2));
include/vis_proto.h
938
vis_fandnot(vis_d64 r1, vis_d64 r2)
include/vis_proto.h
94
: "f"(r1), "f"(r2));
include/vis_proto.h
943
: "f"(r1), "f"(r2));
include/vis_proto.h
949
vis_fors(vis_f32 r1, vis_f32 r2)
include/vis_proto.h
954
: "f"(r1), "f"(r2));
include/vis_proto.h
960
vis_fands(vis_f32 r1, vis_f32 r2)
include/vis_proto.h
965
: "f"(r1), "f"(r2));
include/vis_proto.h
971
vis_fxors(vis_f32 r1, vis_f32 r2)
include/vis_proto.h
976
: "f"(r1), "f"(r2));
include/vis_proto.h
982
vis_fnors(vis_f32 r1, vis_f32 r2)
include/vis_proto.h
987
: "f"(r1), "f"(r2));
include/vis_proto.h
993
vis_fnands(vis_f32 r1, vis_f32 r2)
include/vis_proto.h
998
: "f"(r1), "f"(r2));
lib/libc/arch/powerpc64/SYS.h
28
#define _DO_CERROR() lwz %r4,_C_LABEL(errno)@got(%r2) ;\
lib/libc/arch/sh3/SYS.h
70
mov.l 913f, r2; \
lib/libc/arch/sh3/SYS.h
72
mov.l @(r0, r2), r3; \
lib/libc/citrus/citrus_csmapper.c
108
struct _region fr, r1, r2;
lib/libc/citrus/citrus_csmapper.c
131
ret = _db_get_entry(db2, i, &r1, &r2);
lib/libc/citrus/citrus_csmapper.c
135
ret = get32(&r2, &val32);
lib/libc/citrus/citrus_csmapper.c
145
if (_db_lookup_by_s(db3, dst, &r2, NULL) != 0)
lib/libc/citrus/citrus_csmapper.c
149
ret = get32(&r2, &val32);
lib/libc/time/zic.c
1909
struct rule const *r1 = cp1, *r2 = cp2;
lib/libc/time/zic.c
1910
return strcmp(r1->r_name, r2->r_name);
lib/libm/ld128/e_lgammal_r.c
148
r2 = 2.86289413392776399262513849911531180e+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/ld128/k_expl.h
241
double dr, fn, r2;
lib/libm/ld128/k_expl.h
251
r2 = fn * -L2;
lib/libm/ld128/k_expl.h
252
r = r1 + r2;
lib/libm/ld128/k_expl.h
256
q = r2 + r * r * (A2 + r * (A3 + r * (A4 + r * (A5 + r * (A6 +
lib/libm/ld128/s_expl.c
204
double dr, dx, fn, r2;
lib/libm/ld128/s_expl.c
272
r2 = fn * -L2;
lib/libm/ld128/s_expl.c
273
r = r1 + r2;
lib/libm/ld128/s_expl.c
285
q = r2 + r * r * (A2 + r * (A3 + r * (A4 + r * (A5 + r * (A6 +
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/ld80/k_expl.h
222
long double fn, q, r, r1, r2, t, z;
lib/libm/ld80/k_expl.h
233
r2 = fn * -L2;
lib/libm/ld80/k_expl.h
238
q = r2 + z * (A2 + r * A3) + z * z * (A4 + r * A5) + z * z * z * A6;
lib/libm/ld80/k_expl.h
240
q = r2 + z * A2 + z * r * (A3 + r * A4 + z * (A5 + r * A6));
lib/libm/ld80/s_expl.c
159
long double fn, hx2_hi, hx2_lo, q, r, r1, r2, t, twomk, twopk, x_hi;
lib/libm/ld80/s_expl.c
225
r2 = fn * -L2;
lib/libm/ld80/s_expl.c
226
r = r1 + r2;
lib/libm/ld80/s_expl.c
238
q = r2 + z * (A2 + r * A3) + z * z * (A4 + r * A5) + z * z * z * A6;
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
143
r2 = 7.21935547567138069525e-01, /* 0x3FE71A18, 0x93D3DCDC */
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
79
r2 = 7.2193557024e-01, /* 0x3f38d0c5 */
lib/libpam/modules/pam_unix/pam_unix.c
251
enum clnt_stat r2;
lib/libpam/modules/pam_unix/pam_unix.c
322
r2 = clnt_call(client, YPPASSWDPROC_UPDATE,
lib/libpam/modules/pam_unix/pam_unix.c
324
if (r2 != RPC_SUCCESS)
libexec/ftpd/ftpd.c
3599
const char *r1, *r2;
libexec/ftpd/ftpd.c
3607
r1 = r2 = NULL;
libexec/ftpd/ftpd.c
3611
if ((r2 = realpath(file2, realfile2)) == NULL)
libexec/ftpd/ftpd.c
3612
r2 = file2;
libexec/ftpd/ftpd.c
3622
else if (r2 != NULL)
libexec/ftpd/ftpd.c
3624
" %s", r2);
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
204
r->r2 = DEV_BSIZE;
sys/arch/acorn32/stand/nbfs/nbfs.c
222
void *buf = (void *)r->r2;
sys/arch/acorn32/stand/nbfs/nbfs.c
273
void *buf = (void *)r->r2;
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
358
char *outp = (char *)r->r2;
sys/arch/acorn32/stand/nbfs/nbfs.h
8
uint32_t r0, r1, r2, r3, r4, r5, r6, r7;
sys/arch/amiga/dev/efa.c
289
int r1, r2, ret;
sys/arch/amiga/dev/efa.c
300
r2 = wdcintr(&sc->sc_ports[1].chan);
sys/arch/amiga/dev/efa.c
301
ret = r1 | r2;
sys/arch/amiga/dev/wdc_xsurf.c
202
int r1, r2;
sys/arch/amiga/dev/wdc_xsurf.c
205
r1 = r2 = 0;
sys/arch/amiga/dev/wdc_xsurf.c
213
r2 = wdcintr(&sc->sc_ports[1].channel);
sys/arch/amiga/dev/wdc_xsurf.c
216
return r1 | r2;
sys/arch/arm/arm/smccc.c
111
register register_t r2 asm ("r2");
sys/arch/arm/arm/smccc.c
123
r2 = args[2];
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
146
*res2 = r2;
sys/arch/arm/include/arm32/frame.h
196
ldr r2, .Laflt_cpufuncs ;\
sys/arch/arm/include/arm32/frame.h
199
BL_CF_CONTROL(r2) /* Enable alignment faults */ ;\
sys/arch/arm/include/arm32/frame.h
220
ldr r2, .Laflt_cpufuncs ;\
sys/arch/arm/include/arm32/frame.h
223
BL_CF_CONTROL(r2) /* Set new CTRL reg value */ ;\
sys/arch/arm/include/arm32/frame.h
255
ldmia r0, {r1-r2} /* load ev_count */ ;\
sys/arch/arm/include/arm32/frame.h
256
adds r2, r2, #1 /* 64-bit incr (lo) */ ;\
sys/arch/arm/include/arm32/frame.h
258
stmia r0, {r1-r2} /* store ev_count */
sys/arch/arm/include/arm32/frame.h
263
ldmia r0, {r1-r2} /* load ev_count */ ;\
sys/arch/arm/include/arm32/frame.h
265
adc r2, r2, #0 /* 64-bit incr (hi) */ ;\
sys/arch/arm/include/arm32/frame.h
266
stmia r0, {r1-r2} /* store ev_count */
sys/arch/arm/include/arm32/frame.h
438
SET_CPSR_MODE(r2, PSR_SVC32_MODE)
sys/arch/arm/include/arm32/frame.h
442
and r2, r3, #(PSR_MODE); \
sys/arch/arm/include/arm32/frame.h
443
cmp r2, #(PSR_SVC32_MODE); /* were we in SVC mode? */ \
sys/arch/arm/include/arm32/frame.h
444
mov r2, sp; \
sys/arch/arm/include/arm32/frame.h
445
subeq r2, r2, #(4 * 16); /* if so, leave a gap for dtrace */
sys/arch/arm/include/arm32/frame.h
448
mov r2, sp
sys/arch/arm/include/arm32/frame.h
452
bic r2, rX, #7; /* Align new SVC sp */ \
sys/arch/arm/include/arm32/frame.h
453
str r0, [r2, #-4]!; /* Push return address */ \
sys/arch/arm/include/arm32/frame.h
454
stmdb r2!, {sp, lr}; /* Push SVC sp, lr */ \
sys/arch/arm/include/arm32/frame.h
455
mov sp, r2; /* Keep stack aligned */ \
sys/arch/arm/sociox/if_scx.c
537
__rxd->r2 = htole32(BUS_ADDR_LO32(__p)); \
sys/arch/arm/sociox/if_scx.c
83
uint32_t r0, r1, r2, r3;
sys/arch/atari/stand/tostools/aptck/disklbl.c
190
*r2 = x2;
sys/arch/atari/stand/tostools/aptck/disklbl.c
192
if (*r1 < *r2)
sys/arch/atari/stand/tostools/aptck/disklbl.c
194
if (*r1 > *r2)
sys/arch/hppa/dev/mongoose.c
676
R(r2); R(r4); R(w2); R(w4);
sys/arch/hppa/hppa/db_disasm.c
1878
u_int op2, r2, dfmt;
sys/arch/hppa/hppa/db_disasm.c
1898
r2 = (op1 >> 6) & 0x3e;
sys/arch/hppa/hppa/db_disasm.c
1900
r2++;
sys/arch/hppa/hppa/db_disasm.c
1914
condStrTbl[op2], ST(r1), ST(r2));
sys/arch/hppa/hppa/db_disasm.c
1933
db_printf("\t%%f%s, %%f%s, %%f%s",ST(r1),ST(r2),ST(t));
sys/arch/hppa/hppa/db_disasm.c
1982
u_int r1, r2, t, fmt, dfmt;
sys/arch/hppa/hppa/db_disasm.c
2031
r1 = (op1 >> 12) & 0x1f; r2 = (op1 >> 7) & 0x1f;
sys/arch/hppa/hppa/db_disasm.c
2038
p,fmtStrTbl[fmt],condStrTbl[op2],r1,r2);
sys/arch/hppa/hppa/db_disasm.c
2042
r1 = (op1 >> 12) & 0x1f; r2 = (op1 >> 7) & 0x1f; t = op2;
sys/arch/hppa/hppa/db_disasm.c
2053
p, fmtStrTbl[fmt], r1, r2, t);
sys/arch/hppa/spmath/fpudispatch.c
118
unsigned r1,r2,t; /* operand register offsets */
sys/arch/hppa/spmath/fpudispatch.c
274
r2 = extru(ir, fpr2pos, 5) * sizeof(double)/sizeof(unsigned);
sys/arch/hppa/spmath/fpudispatch.c
275
if (r2 == 0)
sys/arch/hppa/spmath/fpudispatch.c
276
r2 = fpzeroreg;
sys/arch/hppa/spmath/fpudispatch.c
288
return(sgl_fcmp(&fpregs[r1],&fpregs[r2],
sys/arch/hppa/spmath/fpudispatch.c
291
return(dbl_fcmp(&fpregs[r1],&fpregs[r2],
sys/arch/hppa/spmath/fpudispatch.c
319
r2 = extru(ir,fpr2pos,5) * sizeof(double)/sizeof(unsigned);
sys/arch/hppa/spmath/fpudispatch.c
320
if (r2 == 0)
sys/arch/hppa/spmath/fpudispatch.c
321
r2 = fpzeroreg;
sys/arch/hppa/spmath/fpudispatch.c
331
return(sgl_fadd(&fpregs[r1],&fpregs[r2],
sys/arch/hppa/spmath/fpudispatch.c
334
return(dbl_fadd(&fpregs[r1],&fpregs[r2],
sys/arch/hppa/spmath/fpudispatch.c
343
return(sgl_fsub(&fpregs[r1],&fpregs[r2],
sys/arch/hppa/spmath/fpudispatch.c
346
return(dbl_fsub(&fpregs[r1],&fpregs[r2],
sys/arch/hppa/spmath/fpudispatch.c
355
return(sgl_fmpy(&fpregs[r1],&fpregs[r2],
sys/arch/hppa/spmath/fpudispatch.c
358
return(dbl_fmpy(&fpregs[r1],&fpregs[r2],
sys/arch/hppa/spmath/fpudispatch.c
367
return(sgl_fdiv(&fpregs[r1],&fpregs[r2],
sys/arch/hppa/spmath/fpudispatch.c
370
return(dbl_fdiv(&fpregs[r1],&fpregs[r2],
sys/arch/hppa/spmath/fpudispatch.c
379
return(sgl_frem(&fpregs[r1],&fpregs[r2],
sys/arch/hppa/spmath/fpudispatch.c
382
return(dbl_frem(&fpregs[r1],&fpregs[r2],
sys/arch/hppa/spmath/fpudispatch.c
396
unsigned r1,r2,t; /* operand register offsets */
sys/arch/hppa/spmath/fpudispatch.c
536
r2 = ((extru(ir,fpr2pos,5)<<1)|(extru(ir,fpxr2pos,1)));
sys/arch/hppa/spmath/fpudispatch.c
537
if (r2 == 0)
sys/arch/hppa/spmath/fpudispatch.c
538
r2 = fpzeroreg;
sys/arch/hppa/spmath/fpudispatch.c
554
return(sgl_fcmp(&fpregs[r1],&fpregs[r2],
sys/arch/hppa/spmath/fpudispatch.c
557
return(dbl_fcmp(&fpregs[r1],&fpregs[r2],
sys/arch/hppa/spmath/fpudispatch.c
562
r2 = ((extru(ir,fpr2pos,5)<<1)|(extru(ir,fpxr2pos,1)));
sys/arch/hppa/spmath/fpudispatch.c
563
if (r2 == 0)
sys/arch/hppa/spmath/fpudispatch.c
564
r2 = fpzeroreg;
sys/arch/hppa/spmath/fpudispatch.c
576
return(sgl_fadd(&fpregs[r1],&fpregs[r2],
sys/arch/hppa/spmath/fpudispatch.c
579
return(dbl_fadd(&fpregs[r1],&fpregs[r2],
sys/arch/hppa/spmath/fpudispatch.c
585
return(sgl_fsub(&fpregs[r1],&fpregs[r2],
sys/arch/hppa/spmath/fpudispatch.c
588
return(dbl_fsub(&fpregs[r1],&fpregs[r2],
sys/arch/hppa/spmath/fpudispatch.c
609
impyu(&fpregs[r1],&fpregs[r2],
sys/arch/hppa/spmath/fpudispatch.c
623
&fpregs[r2],&fpregs[t],status));
sys/arch/hppa/spmath/fpudispatch.c
626
&fpregs[r2],&fpregs[t],status));
sys/arch/hppa/spmath/fpudispatch.c
632
return(sgl_fdiv(&fpregs[r1],&fpregs[r2],
sys/arch/hppa/spmath/fpudispatch.c
635
return(dbl_fdiv(&fpregs[r1],&fpregs[r2],
sys/arch/hppa/spmath/fpudispatch.c
641
return(sgl_frem(&fpregs[r1],&fpregs[r2],
sys/arch/hppa/spmath/fpudispatch.c
644
return(dbl_frem(&fpregs[r1],&fpregs[r2],
sys/arch/m68k/fpe/fpu_add.c
172
FPU_SUBCS(r2, x->fp_mant[2], y->fp_mant[2]);
sys/arch/m68k/fpe/fpu_add.c
177
if ((r0 | r1 | r2) == 0) {
sys/arch/m68k/fpe/fpu_add.c
195
FPU_SUBS(r2, 0, r2);
sys/arch/m68k/fpe/fpu_add.c
199
r->fp_mant[2] = r2;
sys/arch/m68k/fpe/fpu_add.c
64
uint32_t r0, r1, r2;
sys/arch/m68k/fpe/fpu_div.c
157
uint32_t r0, r1, r2, d0, d1, d2, y0, y1, y2;
sys/arch/m68k/fpe/fpu_div.c
208
FPU_SUBS(d2, r2, y2); \
sys/arch/m68k/fpe/fpu_div.c
216
FPU_ADDS(r2, r2, r2); \
sys/arch/m68k/fpe/fpu_div.c
220
r0 = (r0 << 1) | (r1 >> 31), r1 = (r1 << 1) | (r2 >> 31), \
sys/arch/m68k/fpe/fpu_div.c
221
r2 <<= 1
sys/arch/m68k/fpe/fpu_div.c
230
r0 = d0, r1 = d1, r2 = d2; \
sys/arch/m68k/fpe/fpu_div.c
243
r2 = x->fp_mant[2];
sys/arch/m68k/fpe/fpu_div.c
252
r0 = d0, r1 = d1, r2 = d2;
sys/arch/m68k/fpe/fpu_div.c
263
x->fp_sticky = r0 | r1 | r2;
sys/arch/newsmips/apbus/xafb.c
57
volatile uint32_t r2;
sys/arch/powerpc/fpu/fpu_add.c
195
FPU_SUBCS(r2, x->fp_mant[2], y->fp_mant[2]);
sys/arch/powerpc/fpu/fpu_add.c
200
if ((r0 | r1 | r2 | r3) == 0) {
sys/arch/powerpc/fpu/fpu_add.c
219
FPU_SUBCS(r2, 0, r2);
sys/arch/powerpc/fpu/fpu_add.c
224
r->fp_mant[2] = r2;
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
245
r0 = (r0 << 1) | (r1 >> 31), r1 = (r1 << 1) | (r2 >> 31), \
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
268
r2 = x->fp_mant[2];
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
269
rxd[i].r2 = htole32(VTOPHYS(l->rxstore[i]));
sys/arch/sandpoint/stand/altboot/vge.c
68
uint32_t r0, r1, r2, r3;
sys/arch/sandpoint/stand/altboot/wm.c
181
rxd[0].r2 = 0;
sys/arch/sandpoint/stand/altboot/wm.c
184
rxd[1].r2 = 0;
sys/arch/sandpoint/stand/altboot/wm.c
274
rxd->r2 = 0;
sys/arch/sandpoint/stand/altboot/wm.c
287
rxd->r2 = 0;
sys/arch/sandpoint/stand/altboot/wm.c
67
uint32_t r2; /* 31:16 checksum, 15:0 Rx frame length */
sys/arch/sh3/include/locore.h
108
mov.l r2, @-r14 /* tf_ssr */ ;\
sys/arch/sh3/include/locore.h
155
mov.l @r14+, r2 /* tf_r2 */ ;\
sys/arch/sh3/include/locore.h
76
stc ssr, r2 /* r2 = SSR */ ;\
sys/arch/sh3/include/locore.h
81
tst r3, r2 /* if (SSR.MD == 0) T = 1 */ ;\
sys/arch/sh3/sh3/db_interface.c
641
TF(r2);
sys/arch/sparc/fpu/fpu_add.c
178
FPU_SUBCS(r2, x->fp_mant[2], y->fp_mant[2]);
sys/arch/sparc/fpu/fpu_add.c
183
if ((r0 | r1 | r2 | r3) == 0) {
sys/arch/sparc/fpu/fpu_add.c
202
FPU_SUBCS(r2, 0, r2);
sys/arch/sparc/fpu/fpu_add.c
207
r->fp_mant[2] = r2;
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
216
r0 = (r0 << 1) | (r1 >> 31), r1 = (r1 << 1) | (r2 >> 31), \
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
239
r2 = x->fp_mant[2];
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/sparc/include/asm.h
231
#define INCR64X(what,r0,r1,r2) \
sys/arch/sparc/include/asm.h
232
sethi %hi(what), r2; \
sys/arch/sparc/include/asm.h
233
ldd [r2 + %lo(what)], r0; \
sys/arch/sparc/include/asm.h
236
std r0, [r2 + %lo(what)]
sys/arch/sparc64/include/asm.h
74
#define COMBINE(r1, r2, d) \
sys/arch/sparc64/include/asm.h
75
clruw r2; \
sys/arch/sparc64/include/asm.h
77
or d, r2, d
sys/arch/vax/include/asm.h
126
movzwl \degree, %r2
sys/arch/vax/include/asm.h
133
sobgtr %r2, 1b
sys/arch/vax/include/asm.h
139
movzwl \degree, %r2
sys/arch/vax/include/asm.h
146
sobgtr %r2, 1b
sys/arch/vax/include/reg.h
36
int r2;
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/arch/x68k/x68k/iodevice.h
51
char pad2[0x00fe]; unsigned short r2;
sys/crypto/adiantum/adiantum.c
214
uint32_t r2 = P->r[2];
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
132
r2 = (q2 >> 16) | (q2 << 48);
sys/crypto/aes/aes_ct64_dec.c
141
q[2] = q0 ^ q1 ^ q6 ^ r1 ^ r2 ^ r6 ^ r7 ^ rotr32(q0 ^ q2 ^ q6 ^ r2 ^ r6 ^ r7);
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
144
q[5] = q2 ^ q3 ^ q4 ^ q6 ^ r2 ^ r4 ^ r5 ^ r6 ^ r7 ^ rotr32(q2 ^ q3 ^ q5 ^ q6 ^ r2 ^ r5 ^ 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
88
r2 = (q2 >> 16) | (q2 << 48);
sys/crypto/aes/aes_ct64_enc.c
97
q[2] = q1 ^ r1 ^ r2 ^ rotr32(q2 ^ r2);
sys/crypto/aes/aes_ct64_enc.c
98
q[3] = q2 ^ r2 ^ q7 ^ r7 ^ r3 ^ rotr32(q3 ^ r3);
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
143
r2 = (q2 >> 8) | (q2 << 24);
sys/crypto/aes/aes_ct_dec.c
152
q[2] = q0 ^ q1 ^ q6 ^ r1 ^ r2 ^ r6 ^ r7 ^ rotr16(q0 ^ q2 ^ q6 ^ r2 ^ r6 ^ r7);
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
155
q[5] = q2 ^ q3 ^ q4 ^ q6 ^ r2 ^ r4 ^ r5 ^ r6 ^ r7 ^ rotr16(q2 ^ q3 ^ q5 ^ q6 ^ r2 ^ r5 ^ 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
85
r2 = (q2 >> 8) | (q2 << 24);
sys/crypto/aes/aes_ct_enc.c
94
q[2] = q1 ^ r1 ^ r2 ^ rotr16(q2 ^ r2);
sys/crypto/aes/aes_ct_enc.c
95
q[3] = q2 ^ r2 ^ q7 ^ r7 ^ r3 ^ rotr16(q3 ^ r3);
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
161
r2 = _mm_srli_epi32(q2, 8) | _mm_slli_epi32(q2, 24);
sys/crypto/aes/arch/x86/aes_sse2_4x32_dec.c
170
q[2] = q0 ^ q1 ^ q6 ^ r1 ^ r2 ^ r6 ^ r7 ^ rotr16(q0 ^ q2 ^ q6 ^ r2 ^ r6 ^ r7);
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
173
q[5] = q2 ^ q3 ^ q4 ^ q6 ^ r2 ^ r4 ^ r5 ^ r6 ^ r7 ^ rotr16(q2 ^ q3 ^ q5 ^ q6 ^ r2 ^ r5 ^ r6 ^ r7);
sys/crypto/aes/arch/x86/aes_sse2_4x32_enc.c
100
r2 = _mm_srli_epi32(q2, 8) | _mm_slli_epi32(q2, 24);
sys/crypto/aes/arch/x86/aes_sse2_4x32_enc.c
109
q[2] = q1 ^ r1 ^ r2 ^ rotr16(q2 ^ r2);
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
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
61
(r2) = (__m128i)_mm_movelh_ps((__m128)_mm_tmp1, (__m128)_mm_tmp3); \
sys/crypto/chacha/arch/arm/chacha_neon.c
113
uint32x4_t r0, r1, r2, r3;
sys/crypto/chacha/arch/arm/chacha_neon.c
118
r2 = *p2;
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
125
r2 = vaddq_u32(r2, r3); r1 ^= r2; r1 = rol7(r1);
sys/crypto/chacha/arch/arm/chacha_neon.c
129
c2 = vextq_u32(r2, r2, 2);
sys/crypto/chacha/arch/arm/chacha_neon.c
139
r2 = vextq_u32(c2, c2, 2);
sys/crypto/chacha/arch/arm/chacha_neon.c
145
*p2 = r2;
sys/crypto/chacha/arch/arm/chacha_neon.c
157
uint32x4_t r0, r1, r2, r3;
sys/crypto/chacha/arch/arm/chacha_neon.c
161
r2 = in2 = vreinterpretq_u32_u8(vld1q_u8(k + 16));
sys/crypto/chacha/arch/arm/chacha_neon.c
164
chacha_permute(&r0, &r1, &r2, &r3, nr);
sys/crypto/chacha/arch/arm/chacha_neon.c
168
vst1q_u8(out + 32, vreinterpretq_u8_u32(vaddq_u32(r2, in2)));
sys/crypto/chacha/arch/arm/chacha_neon.c
179
uint32x4_t r0, r1, r2, r3;
sys/crypto/chacha/arch/arm/chacha_neon.c
183
r2 = vreinterpretq_u32_u8(vld1q_u8(k + 16));
sys/crypto/chacha/arch/arm/chacha_neon.c
186
chacha_permute(&r0, &r1, &r2, &r3, nr);
sys/crypto/chacha/arch/arm/chacha_neon.c
207
uint32x4_t r0, r1, r2, r3;
sys/crypto/chacha/arch/arm/chacha_neon.c
222
r2 = in2;
sys/crypto/chacha/arch/arm/chacha_neon.c
224
chacha_permute(&r0, &r1, &r2, &r3, nr);
sys/crypto/chacha/arch/arm/chacha_neon.c
227
r2 = vaddq_u32(r2, in2);
sys/crypto/chacha/arch/arm/chacha_neon.c
235
vst1q_u8(buf + 32, vreinterpretq_u8_u32(r2));
sys/crypto/chacha/arch/arm/chacha_neon.c
244
vst1q_u8(s + 32, vreinterpretq_u8_u32(r2));
sys/crypto/chacha/arch/arm/chacha_neon.c
267
uint32x4_t r0, r1, r2, r3;
sys/crypto/chacha/arch/arm/chacha_neon.c
282
r2 = in2;
sys/crypto/chacha/arch/arm/chacha_neon.c
284
chacha_permute(&r0, &r1, &r2, &r3, nr);
sys/crypto/chacha/arch/arm/chacha_neon.c
287
r2 = vaddq_u32(r2, in2);
sys/crypto/chacha/arch/arm/chacha_neon.c
296
vst1q_u8(buf + 32, vreinterpretq_u8_u32(r2));
sys/crypto/chacha/arch/arm/chacha_neon.c
310
r2 ^= vreinterpretq_u32_u8(vld1q_u8(p + 32));
sys/crypto/chacha/arch/arm/chacha_neon.c
314
vst1q_u8(s + 32, vreinterpretq_u8_u32(r2));
sys/crypto/chacha/arch/x86/chacha_sse2.c
102
_mm_storeu_si128((__m128i *)out + 2, _mm_add_epi32(r2, in2));
sys/crypto/chacha/arch/x86/chacha_sse2.c
113
__m128i r0, r1, r2, r3;
sys/crypto/chacha/arch/x86/chacha_sse2.c
117
r2 = _mm_loadu_si128((const __m128i *)k + 1);
sys/crypto/chacha/arch/x86/chacha_sse2.c
120
chacha_permute(&r0, &r1, &r2, &r3, nr);
sys/crypto/chacha/arch/x86/chacha_sse2.c
308
__m128i r0, r1, r2, r3;
sys/crypto/chacha/arch/x86/chacha_sse2.c
319
r2 = in2;
sys/crypto/chacha/arch/x86/chacha_sse2.c
321
chacha_permute(&r0, &r1, &r2, &r3, nr);
sys/crypto/chacha/arch/x86/chacha_sse2.c
324
r2 = _mm_add_epi32(r2, in2);
sys/crypto/chacha/arch/x86/chacha_sse2.c
332
_mm_storeu_si128((__m128i *)buf + 2, r2);
sys/crypto/chacha/arch/x86/chacha_sse2.c
341
_mm_storeu_si128((__m128i *)s + 2, r2);
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
475
r2 = in2;
sys/crypto/chacha/arch/x86/chacha_sse2.c
477
chacha_permute(&r0, &r1, &r2, &r3, nr);
sys/crypto/chacha/arch/x86/chacha_sse2.c
480
r2 = _mm_add_epi32(r2, in2);
sys/crypto/chacha/arch/x86/chacha_sse2.c
489
_mm_storeu_si128((__m128i *)buf + 2, r2);
sys/crypto/chacha/arch/x86/chacha_sse2.c
503
r2 ^= _mm_loadu_si128((const __m128i *)p + 2);
sys/crypto/chacha/arch/x86/chacha_sse2.c
507
_mm_storeu_si128((__m128i *)s + 2, r2);
sys/crypto/chacha/arch/x86/chacha_sse2.c
52
r2 = *p2;
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
59
r2 = _mm_add_epi32(r2, r3); r1 ^= r2; r1 = rol32(r1, 7);
sys/crypto/chacha/arch/x86/chacha_sse2.c
63
c2 = _mm_shuffle_epi32(r2, 0x4e);
sys/crypto/chacha/arch/x86/chacha_sse2.c
73
r2 = _mm_shuffle_epi32(c2, 0x4e);
sys/crypto/chacha/arch/x86/chacha_sse2.c
79
*p2 = r2;
sys/crypto/chacha/arch/x86/chacha_sse2.c
91
__m128i r0, r1, r2, r3;
sys/crypto/chacha/arch/x86/chacha_sse2.c
95
r2 = in2 = _mm_loadu_si128((const __m128i *)k + 1);
sys/crypto/chacha/arch/x86/chacha_sse2.c
98
chacha_permute(&r0, &r1, &r2, &r3, nr);
sys/dev/i2c/mt2131.c
128
uint32_t r1, r2;
sys/dev/i2c/mt2131.c
150
r2 = d2/8192;
sys/dev/i2c/mt2131.c
157
b[6] = r2;
sys/dev/ic/clmpcc.c
931
u_char r2;
sys/dev/ic/clmpcc.c
935
r2 = clmpcc_rdreg(sc, CLMPCC_REG_TBPR);
sys/dev/ic/clmpcc.c
937
if ( ch->ch_tcor != r1 || ch->ch_tbpr != r2 ) {
sys/dev/ic/clmpcc.c
945
r2 = clmpcc_rdreg(sc, CLMPCC_REG_RBPR);
sys/dev/ic/clmpcc.c
947
if ( ch->ch_rcor != r1 || ch->ch_rbpr != r2 ) {
sys/dev/ic/i82365.c
952
int r1, r2, r3, r4, r5, r6;
sys/dev/ic/i82365.c
955
r2 = pcic_read(h, mem_map_index[win].sysmem_start_lsb);
sys/dev/ic/i82365.c
962
"%02x%02x\n", win, r1, r2, r3, r4, r5, r6));
sys/dev/ic/rt2560.c
2405
rt2560_rf_write(sc, RT2560_RF2, rt2560_rf5222[i].r2);
sys/dev/ic/rt2560.c
274
uint32_t r2;
sys/dev/ic/rt2661.c
1227
uint32_t r1, r2;
sys/dev/ic/rt2661.c
1238
r2 = RAL_READ(sc, RT2661_MCU_INT_SOURCE_CSR);
sys/dev/ic/rt2661.c
1240
if ((r1 & RT2661_INT_CSR_ALL) == 0 && (r2 & RT2661_MCU_INT_ALL) == 0)
sys/dev/ic/rt2661.c
1255
uint32_t r1, r2;
sys/dev/ic/rt2661.c
1259
r2 = RAL_READ(sc, RT2661_MCU_INT_SOURCE_CSR);
sys/dev/ic/rt2661.c
1262
(r2 & RT2661_MCU_INT_ALL) == 0)
sys/dev/ic/rt2661.c
1266
RAL_WRITE(sc, RT2661_MCU_INT_SOURCE_CSR, r2);
sys/dev/ic/rt2661.c
1289
if (r2 & RT2661_MCU_CMD_DONE)
sys/dev/ic/rt2661.c
1292
if (r2 & RT2661_MCU_BEACON_EXPIRE)
sys/dev/ic/rt2661.c
1295
if (r2 & RT2661_MCU_WAKEUP)
sys/dev/ic/rt2661.c
186
uint32_t r1, r2, r3, r4;
sys/dev/ic/rt2661.c
2255
rt2661_rf_write(sc, RAL_RF2, rfprog[i].r2);
sys/dev/ic/rt2661.c
2262
rt2661_rf_write(sc, RAL_RF2, rfprog[i].r2);
sys/dev/ic/rt2661.c
2269
rt2661_rf_write(sc, RAL_RF2, rfprog[i].r2);
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
2372
r2 = rfprog[i].r2;
sys/dev/ic/rt2860.c
2374
r2 |= 1 << 12; /* 1T: disable Tx chain 2 */
sys/dev/ic/rt2860.c
2376
r2 |= 1 << 15 | 1 << 4; /* 1R: disable Rx chains 2 & 3 */
sys/dev/ic/rt2860.c
2378
r2 |= 1 << 4; /* 2R: disable Rx chain 3 */
sys/dev/ic/rt2860.c
2397
rt2860_rf_write(sc, RT2860_RF2, r2);
sys/dev/ic/rt2860.c
2404
rt2860_rf_write(sc, RT2860_RF2, r2);
sys/dev/ic/rt2860.c
2411
rt2860_rf_write(sc, RT2860_RF2, r2);
sys/dev/ic/tcic2.c
1065
int r1, r2;
sys/dev/ic/tcic2.c
1068
r2 = tcic_read_ind_2(h, TCIC_WR_ICTL_N(hwwin));
sys/dev/ic/tcic2.c
1071
win, hwwin, r1, r2));
sys/dev/ic/tcic2.c
848
int r1, r2, r3;
sys/dev/ic/tcic2.c
851
r2 = tcic_read_ind_2(h, TCIC_WR_MMAP_N(hwwin));
sys/dev/ic/tcic2.c
855
win, hwwin, r1, r2, r3));
sys/dev/pci/eap.c
1303
int l1, r1, l2, r2, m, o1, o2;
sys/dev/pci/eap.c
1311
l1 = l2 = r1 = r2 = 0;
sys/dev/pci/eap.c
1313
l2 |= AK_M_VOICE, r2 |= AK_M_VOICE;
sys/dev/pci/eap.c
1321
l2 |= AK_M2_AUX_L, r2 |= AK_M2_AUX_R;
sys/dev/pci/eap.c
1323
l2 |= AK_M_TMIC, r2 |= AK_M_TMIC;
sys/dev/pci/eap.c
1327
eap1370_set_mixer(sc, AK_IN_MIXER2_R, r2);
sys/dev/pci/if_iwm.c
8723
uint32_t r1, r2;
sys/dev/pci/if_iwm.c
8739
r1 = r2 = 0;
sys/dev/pci/if_iwm.c
8764
r2 = IWM_READ(sc, IWM_CSR_FH_INT_STATUS);
sys/dev/pci/if_iwm.c
8766
if (r1 == 0 && r2 == 0) {
sys/dev/pci/if_iwn.c
2825
uint32_t r1, r2, tmp;
sys/dev/pci/if_iwn.c
2846
r2 = 0; /* Unused. */
sys/dev/pci/if_iwn.c
2851
r2 = IWN_READ(sc, IWN_FH_INT);
sys/dev/pci/if_iwn.c
2853
if (r1 == 0 && r2 == 0) {
sys/dev/pci/if_iwn.c
2860
IWN_WRITE(sc, IWN_FH_INT, r2);
sys/dev/pci/if_iwn.c
2884
(r2 & IWN_FH_INT_RX)) {
sys/dev/pci/if_iwn.c
2898
if ((r1 & IWN_INT_FH_TX) || (r2 & IWN_FH_INT_TX)) {
sys/dev/pci/if_iwn.c
3938
int32_t r1, r2, r3, r4, temp;
sys/dev/pci/if_iwn.c
3941
r2 = le32toh(uc->temp[1].chan20MHz);
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
312
__rxd->r2 = __rxs->rxs_dmamap->dm_segs[0].ds_addr; \
sys/dev/pci/pccbb.c
2617
int r1, r2, r3, r4, r5, r6, r7 = 0;
sys/dev/pci/pccbb.c
2620
r2 = Pcic_read(sc, regbase_win + PCIC_SMM_START_HIGH);
sys/dev/pci/pccbb.c
2630
"%02x%02x", win, r1, r2, r3, r4, r5, r6);
sys/dev/pci/radeonfb.c
4452
int r1, r2;
sys/dev/pci/radeonfb.c
4456
r2 = DIVIDE(DIVIDE(m2->dot_clock, m2->htotal), m2->vtotal);
sys/dev/pci/radeonfb.c
4458
return (r1 < r2 ? m2 : m1);
sys/dev/usb/if_rum.c
1710
rum_rf_write(sc, RT2573_RF2, rfprog[i].r2);
sys/dev/usb/if_rum.c
1715
rum_rf_write(sc, RT2573_RF2, rfprog[i].r2);
sys/dev/usb/if_rum.c
1720
rum_rf_write(sc, RT2573_RF2, rfprog[i].r2);
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
2981
r2 = rfprog[i].r2;
sys/dev/usb/if_run.c
2983
r2 |= 1 << 12; /* 1T: disable Tx chain 2 */
sys/dev/usb/if_run.c
2985
r2 |= 1 << 15 | 1 << 4; /* 1R: disable Rx chains 2 & 3 */
sys/dev/usb/if_run.c
2987
r2 |= 1 << 4; /* 2R: disable Rx chain 3 */
sys/dev/usb/if_run.c
3006
run_rt2870_rf_write(sc, RT2860_RF2, r2);
sys/dev/usb/if_run.c
3013
run_rt2870_rf_write(sc, RT2860_RF2, r2);
sys/dev/usb/if_run.c
3020
run_rt2870_rf_write(sc, RT2860_RF2, r2);
sys/dev/usb/if_run.c
482
uint32_t r1, r2, r3, r4;
sys/dev/usb/if_ural.c
1770
ural_rf_write(sc, RAL_RF2, ural_rf5222[i].r2);
sys/dev/usb/if_ural.c
293
uint32_t r2;
sys/dev/usb/if_zyd.c
1071
uint32_t r1, r2, r3;
sys/dev/usb/if_zyd.c
1075
(void)zyd_rfwrite(sc, rfprog[chan - 1].r2);
sys/dev/usb/if_zyd.c
1149
uint32_t r1, r2;
sys/dev/usb/if_zyd.c
1170
(void)zyd_rfwrite(sc, rfprog[chan - 1].r2);
sys/dev/usb/if_zyd.c
1346
uint32_t r1, r2;
sys/dev/usb/if_zyd.c
1368
(void)zyd_rfwrite(sc, rfprog[chan - 1].r2);
sys/dev/usb/if_zyd.c
1429
uint32_t r1, r2;
sys/dev/usb/if_zyd.c
1451
(void)zyd_rfwrite(sc, rfprog[chan - 1].r2);
sys/dev/usb/if_zyd.c
984
uint32_t r1, r2;
sys/dev/usb/if_zyd.c
988
(void)zyd_rfwrite(sc, rfprog[chan - 1].r2);
sys/kern/vfs_getcwd.c
457
struct vnode *r2 = l2->l_proc->p_cwdi->cwdi_rdir;
sys/kern/vfs_getcwd.c
460
return (r2 == NULL);
sys/kern/vfs_getcwd.c
461
else if (r2 == NULL)
sys/kern/vfs_getcwd.c
464
return vn_isunder(r1, r2, l2);
sys/net/zlib.c
3506
int r, r2;
sys/net/zlib.c
3511
r2 = f == Z_FINISH ? Z_BUF_ERROR : Z_OK;
sys/net/zlib.c
3588
r = r2;
sys/net/zlib.c
3591
r = r2;
sys/netipsec/key.c
1000
struct ipsecrequest *r1, *r2, *p;
sys/netipsec/key.c
1018
r1 = r2 = NULL;
sys/netipsec/key.c
1023
r1 = r2;
sys/netipsec/key.c
1024
r2 = p;
sys/netipsec/key.c
1042
if (!key_sockaddr_match(&r2->saidx.src.sa, osrc, PORT_NONE) ||
sys/netipsec/key.c
1043
!key_sockaddr_match(&r2->saidx.dst.sa, odst, PORT_NONE))
tests/fs/ffs/t_fifos.c
134
pthread_create(&ptr2, NULL, r2, NULL);
tests/kernel/arch/vax/execregs.c
105
register long r2 __asm("r2") = nonnull(2);
tests/kernel/arch/vax/execregs.c
143
"+r"(r2),
tests/kernel/arch/vax/execregs.c
58
register long r2 __asm("r2") = nonnull(2);
tests/kernel/arch/vax/execregs.c
82
"+r"(r2),
tests/kernel/kqueue/t_scan.c
103
r2 = (intptr_t)v2;
tests/kernel/kqueue/t_scan.c
106
ATF_REQUIRE(r2 >= 0);
tests/kernel/kqueue/t_scan.c
109
ATF_REQUIRE(r2 == NKEVENT_CALLS);
tests/kernel/kqueue/t_scan.c
85
intptr_t r1, r2;
tests/lib/libc/string/t_popcount.c
166
unsigned int i, j, r, r2, p;
tests/lib/libc/string/t_popcount.c
173
r2 = byte_count[p & 255] + byte_count[(p >> 8) & 255]
tests/lib/libc/string/t_popcount.c
180
+ byte_count[(i >> 24) & 255] + r2;
tests/lib/libc/sys/t_ptrace_x86_wait.h
133
struct dbreg r2;
tests/lib/libc/sys/t_ptrace_x86_wait.h
1640
struct dbreg r2;
tests/lib/libc/sys/t_ptrace_x86_wait.h
1711
SYSCALL_REQUIRE(ptrace(PT_GETDBREGS, child, &r2, lid) != -1);
tests/lib/libc/sys/t_ptrace_x86_wait.h
1714
for (i = 0; i < __arraycount(r2.dr); i++)
tests/lib/libc/sys/t_ptrace_x86_wait.h
1715
DPRINTF("r2[%zu]=%" PRIxREGISTER "\n", i, r2.dr[i]);
tests/lib/libc/sys/t_ptrace_x86_wait.h
1718
ATF_REQUIRE(memcmp(&r1, &r2, sizeof(r1)) != 0);
tests/lib/libc/sys/t_ptrace_x86_wait.h
1801
struct dbreg r2;
tests/lib/libc/sys/t_ptrace_x86_wait.h
1871
SYSCALL_REQUIRE(ptrace(PT_GETDBREGS, child, &r2, 0) != -1);
tests/lib/libc/sys/t_ptrace_x86_wait.h
1874
for (i = 0; i < __arraycount(r2.dr); i++)
tests/lib/libc/sys/t_ptrace_x86_wait.h
1875
DPRINTF("r2[%zu]=%" PRIxREGISTER "\n", i, r2.dr[i]);
tests/lib/libc/sys/t_ptrace_x86_wait.h
1878
ATF_REQUIRE(memcmp(&r1, &r2, sizeof(r1)) != 0);
tests/lib/libc/sys/t_ptrace_x86_wait.h
206
SYSCALL_REQUIRE(ptrace(PT_GETDBREGS, child, &r2, 0) != -1);
tests/lib/libc/sys/t_ptrace_x86_wait.h
209
SYSCALL_REQUIRE(memcmp(&r1, &r2, sizeof(r1)) == 0);
usr.bin/diff3/diff3.c
490
duplicate(struct range *r1, struct range *r2)
usr.bin/diff3/diff3.c
496
if (r1->to-r1->from != r2->to-r2->from)
usr.bin/diff3/diff3.c
499
skip(1, r2->from, NULL);
usr.bin/m4/look.c
192
struct macro_definition *r, *r2;
usr.bin/m4/look.c
194
for (r = n->d; r != NULL; r = r2) {
usr.bin/m4/look.c
195
r2 = r->next;
usr.bin/tcopy/tcopy.c
257
goto r2;
usr.bin/tcopy/tcopy.c
262
r2: if (inn != outn) {
usr.sbin/mrouted/route.c
711
const struct newrt *r2 = (const struct newrt *)rt2;
usr.sbin/mrouted/route.c
713
u_int32_t m2 = ntohl(r2->mask);
usr.sbin/mrouted/route.c
723
o2 = ntohl(r2->origin);