/src/sys/arch/m68k/fpe/ |
fpu_add.c | 64 uint32_t r0, r1, r2; local in function:fpu_add 142 FPU_ADDC(r0, x->fp_mant[0], y->fp_mant[0]); 143 if ((r->fp_mant[0] = r0) >= FP_2) { 174 FPU_SUBC(r0, x->fp_mant[0], y->fp_mant[0]); 175 if (r0 < FP_2) { 177 if ((r0 | r1 | r2) == 0) { 197 FPU_SUBC(r0, 0, r0); 201 r->fp_mant[0] = r0; 202 if (r0 < FP_1 [all...] |
fpu_div.c | 157 uint32_t r0, r1, r2, d0, d1, d2, y0, y1, y2; local in function:fpu_div 209 FPU_SUBCS(d1, r1, y1); FPU_SUBC(d0, r0, y0) 217 FPU_ADDCS(r1, r1, r1); FPU_ADDC(r0, r0, r0) 220 r0 = (r0 << 1) | (r1 >> 31), r1 = (r1 << 1) | (r2 >> 31), \ 230 r0 = d0, r1 = d1, r2 = d2; \ 241 r0 = x->fp_mant[0]; 252 r0 = d0, r1 = d1, r2 = d2 [all...] |
/src/sys/arch/powerpc/fpu/ |
fpu_add.c | 69 u_int r0, r1, r2, r3; local in function:fpu_add 164 FPU_ADDC(r0, x->fp_mant[0], y->fp_mant[0]); 165 if ((r->fp_mant[0] = r0) >= FP_2) { 197 FPU_SUBC(r0, x->fp_mant[0], y->fp_mant[0]); 198 if (r0 < FP_2) { 200 if ((r0 | r1 | r2 | r3) == 0) { 221 FPU_SUBC(r0, 0, r0); 226 r->fp_mant[0] = r0; 227 if (r0 < FP_1 [all...] |
fpu_div.c | 161 u_int r0, r1, r2, r3, d0, d1, d2, d3, y0, y1, y2, y3; local in function:fpu_div 234 FPU_SUBCS(d1, r1, y1); FPU_SUBC(d0, r0, y0) 242 FPU_ADDCS(r1, r1, r1); FPU_ADDC(r0, r0, r0) 245 r0 = (r0 << 1) | (r1 >> 31), r1 = (r1 << 1) | (r2 >> 31), \ 255 r0 = d0, r1 = d1, r2 = d2, r3 = d3; \ 266 r0 = x->fp_mant[0]; 279 r0 = d0, r1 = d1, r2 = d2, r3 = d3 [all...] |
/src/sys/arch/sparc/fpu/ |
fpu_add.c | 68 u_int r0, r1, r2, r3; local in function:fpu_add 147 FPU_ADDC(r0, x->fp_mant[0], y->fp_mant[0]); 148 if ((r->fp_mant[0] = r0) >= FP_2) { 180 FPU_SUBC(r0, x->fp_mant[0], y->fp_mant[0]); 181 if (r0 < FP_2) { 183 if ((r0 | r1 | r2 | r3) == 0) { 204 FPU_SUBC(r0, 0, r0); 209 r->fp_mant[0] = r0; 210 if (r0 < FP_1 [all...] |
fpu_div.c | 157 u_int r0, r1, r2, r3, d0, d1, d2, d3, y0, y1, y2, y3; local in function:fpu_div 205 FPU_SUBCS(d1, r1, y1); FPU_SUBC(d0, r0, y0) 213 FPU_ADDCS(r1, r1, r1); FPU_ADDC(r0, r0, r0) 216 r0 = (r0 << 1) | (r1 >> 31), r1 = (r1 << 1) | (r2 >> 31), \ 226 r0 = d0, r1 = d1, r2 = d2, r3 = d3; \ 237 r0 = x->fp_mant[0]; 250 r0 = d0, r1 = d1, r2 = d2, r3 = d3 [all...] |
/src/sys/arch/acorn32/stand/nbfs/ |
nbfs.h | 8 uint32_t r0, r1, r2, r3, r4, r5, r6, r7; member in struct:nbfs_reg
|
/src/sys/arch/hpc/stand/hpcboot/mips/ |
mips_arch.cpp | 53 uint32_t r0, r1; local in function:MIPSArchitecture::systemInfo 55 r0 = r1 = 0; 62 GET_SR(r0); 63 DPRINTF((TEXT("current value: 0x%08x\n"), r0)); 67 SET_SR(r0); 92 uint32_t r0; local in function:MIPSArchitecture::setupLoader 98 r0 = VOLATILE_REF(v); 100 r0 == TEST_MAGIC ? "OK" : "NG"));
|
/src/sys/arch/vax/include/ |
reg.h | 34 int r0; /* General registers saved upon trap/syscall */ member in struct:reg
|
signal.h | 101 unsigned r0, r1, r2, r3, r4, r5; /* Registers saved when interrupt */ member in struct:otrampframe
|
/src/libexec/httpd/ |
daemon-bozo.c | 128 struct addrinfo h, *r, *r0; local in function:bozo_daemon_init 144 e = getaddrinfo(httpd->bindaddress, portnum, &h, &r0); 149 for (r = r0; r != NULL; r = r->ai_next) 153 for (i = 0, r = r0; r != NULL; r = r->ai_next) { 173 freeaddrinfo(r0);
|
/src/sys/crypto/aes/ |
aes_ct_dec.c | 131 uint32_t r0, r1, r2, r3, r4, r5, r6, r7; local in function:inv_mix_columns 141 r0 = (q0 >> 8) | (q0 << 24); 150 q[0] = q5 ^ q6 ^ q7 ^ r0 ^ r5 ^ r7 ^ rotr16(q0 ^ q5 ^ q6 ^ r0 ^ r5); 151 q[1] = q0 ^ q5 ^ r0 ^ r1 ^ r5 ^ r6 ^ r7 ^ rotr16(q1 ^ q5 ^ q7 ^ r1 ^ r5 ^ r6); 153 q[3] = q0 ^ q1 ^ q2 ^ q5 ^ q6 ^ r0 ^ r2 ^ r3 ^ r5 ^ rotr16(q0 ^ q1 ^ q3 ^ q5 ^ q6 ^ q7 ^ r0 ^ r3 ^ r5 ^ r7);
|
aes_ct_enc.c | 73 uint32_t r0, r1, r2, r3, r4, r5, r6, r7; local in function:mix_columns 83 r0 = (q0 >> 8) | (q0 << 24); 92 q[0] = q7 ^ r7 ^ r0 ^ rotr16(q0 ^ r0); 93 q[1] = q0 ^ r0 ^ q7 ^ r7 ^ r1 ^ rotr16(q1 ^ r1);
|
/src/sys/arch/cesfic/cesfic/ |
dp8570a.h | 10 } r0; member in union:dp8570reg::__anon23a44c9f010a
|
/src/sys/crypto/aes/arch/x86/ |
aes_sse2_dec.c | 124 __m128i r0, r1, r2, r3, r4, r5, r6, r7; local in function:inv_mix_columns 131 r0 = _mm_srli_epi64(q0, 16) | _mm_slli_epi64(q0, 48); 144 r4 = _mm_shuffle_epi32(r0, 0x0e); 146 s0 = q5 ^ q6 ^ q7 ^ r0 ^ r5 ^ r7 ^ rotr32(q0 ^ q5 ^ q6 ^ r0 ^ r5); 147 s1 = q0 ^ q5 ^ r0 ^ r1 ^ r5 ^ r6 ^ r7 ^ rotr32(q1 ^ q5 ^ q7 ^ r1 ^ r5 ^ r6); 149 s3 = q0 ^ q1 ^ q2 ^ q5 ^ q6 ^ r0 ^ r2 ^ r3 ^ r5 ^ rotr32(q0 ^ q1 ^ q3 ^ q5 ^ q6 ^ q7 ^ r0 ^ r3 ^ r5 ^ r7);
|
aes_sse2_enc.c | 83 __m128i r0, r1, r2, r3, r4, r5, r6, r7; local in function:mix_columns 90 r0 = _mm_srli_epi64(q0, 16) | _mm_slli_epi64(q0, 48); 103 r4 = _mm_shuffle_epi32(r0, 0x0e); 105 s0 = q7 ^ r7 ^ r0 ^ rotr32(q0 ^ r0); 106 s1 = q0 ^ r0 ^ q7 ^ r7 ^ r1 ^ rotr32(q1 ^ r1);
|
/src/sys/external/isc/libsodium/dist/src/libsodium/crypto_onetimeauth/poly1305/donna/ |
poly1305_donna64.h | 67 unsigned long long r0, r1, r2; local in function:poly1305_blocks 73 r0 = st->r[0]; 96 MUL(d0, h0, r0); 102 MUL(d, h1, r0); 109 MUL(d, h2, r0);
|
poly1305_donna32.h | 60 unsigned long r0, r1, r2, r3, r4; local in function:poly1305_blocks 66 r0 = st->r[0]; 92 d0 = ((unsigned long long) h0 * r0) + ((unsigned long long) h1 * s4) + 95 d1 = ((unsigned long long) h0 * r1) + ((unsigned long long) h1 * r0) + 99 ((unsigned long long) h2 * r0) + ((unsigned long long) h3 * s4) + 102 ((unsigned long long) h2 * r1) + ((unsigned long long) h3 * r0) + 106 ((unsigned long long) h4 * r0);
|
/src/sys/crypto/chacha/arch/arm/ |
chacha_neon.c | 115 uint32x4_t r0, r1, r2, r3; 118 r0 = *p0; 124 r0 = vaddq_u32(r0, r1); r3 ^= r0; r3 = rol16(r3); 126 r0 = vaddq_u32(r0, r1); r3 ^= r0; r3 = rol8(r3); 129 c0 = r0; 139 r0 = c0 113 uint32x4_t r0, r1, r2, r3; local in function:chacha_permute 157 uint32x4_t r0, r1, r2, r3; local in function:chacha_core_neon 179 uint32x4_t r0, r1, r2, r3; local in function:hchacha_neon 207 uint32x4_t r0, r1, r2, r3; local in function:chacha_stream_neon 267 uint32x4_t r0, r1, r2, r3; local in function:chacha_stream_xor_neon [all...] |
/src/sys/arch/hppa/hppa/ |
fpu.c | 97 #define FRAME_REG(f, reg, r0) \ 98 ((reg) == 0 ? (&r0) : ((&(f)->tf_t1) + _frame_reg_positions[reg])) 102 -1, /* r0 */ 229 u_int r0 = 0; local in function:hppa_fpu_ls 263 base = FRAME_REG(frame, inst_b, r0); 269 index = *FRAME_REG(frame, inst_x, r0);
|
/src/sys/arch/newsmips/apbus/ |
xafb.c | 55 volatile uint32_t r0; member in struct:xafb_reg
|
/src/sys/dev/nor/ |
cfi_0002.c | 517 uint8_t r0 = bus_space_read_1(bst, bsh, 0) & __BIT(7); local in function:cfi_0002_busy_dq7 519 busy = (r0 != r1); 523 uint16_t r0 = bus_space_read_2(bst, bsh, 0); local in function:cfi_0002_busy_dq7 525 busy = (r0 != r1); 529 uint32_t r0 = bus_space_read_4(bst, bsh, 0); local in function:cfi_0002_busy_dq7 531 busy = (r0 != r1);
|
/src/sys/external/isc/libsodium/dist/src/libsodium/include/sodium/private/ |
ed25519_ref10_fe_51.h | 246 uint128_t r0, r1, r2, r3, r4, carry; local in function:fe25519_mul 269 r0 = ((uint128_t) f0 ) * ((uint128_t) g0); 270 r0 += ((uint128_t) f1_19) * ((uint128_t) g4); 271 r0 += ((uint128_t) f2_19) * ((uint128_t) g3); 272 r0 += ((uint128_t) f3_19) * ((uint128_t) g2); 273 r0 += ((uint128_t) f4_19) * ((uint128_t) g1); 299 r00 = ((uint64_t) r0) & mask; 300 carry = r0 >> 51; 337 uint128_t r0, r1, r2, r3, r4, carry; local in function:fe25519_sq 358 r0 = ((uint128_t) f0 ) * ((uint128_t) f0) 416 uint128_t r0, r1, r2, r3, r4, carry; local in function:fe25519_sq2 [all...] |
/src/sys/external/isc/libsodium/dist/src/libsodium/crypto_stream/salsa20/xmm6int/ |
u4.h | 102 __m128i r0, r1, r2, r3, r4, r5, r6, r7, r8, r9, r10, r11, r12, r13, variable in typeref:typename:__m128i 155 r0 = y0; 158 r0 = _mm_srli_epi32(r0, 14); 159 z0 = _mm_xor_si128(z0, r0); 283 r0 = y0; 286 r0 = _mm_srli_epi32(r0, 14); 287 z0 = _mm_xor_si128(z0, r0);
|
u8.h | 102 __m256i r0, r1, r2, r3, r4, r5, r6, r7, r8, r9, r10, r11, r12, r13, variable in typeref:typename:__m256i 155 r0 = y0; 158 r0 = _mm256_srli_epi32(r0, 14); 159 z0 = _mm256_xor_si256(z0, r0); 283 r0 = y0; 286 r0 = _mm256_srli_epi32(r0, 14); 287 z0 = _mm256_xor_si256(z0, r0);
|