Home
last modified time | relevance | path

Searched refs:t0 (Results 1 – 25 of 243) sorted by relevance

12345678910

/freebsd-14.2/sys/contrib/libsodium/src/libsodium/crypto_generichash/blake2b/ref/
H A Dblake2b-load-avx2.h6 t0 = _mm256_unpacklo_epi64(m0, m1); \
8 b0 = _mm256_blend_epi32(t0, t1, 0xF0); \
13 t0 = _mm256_unpackhi_epi64(m0, m1); \
15 b0 = _mm256_blend_epi32(t0, t1, 0xF0); \
20 t0 = _mm256_unpacklo_epi64(m4, m5); \
22 b0 = _mm256_blend_epi32(t0, t1, 0xF0); \
27 t0 = _mm256_unpackhi_epi64(m4, m5); \
29 b0 = _mm256_blend_epi32(t0, t1, 0xF0); \
34 t0 = _mm256_unpacklo_epi64(m7, m2); \
36 b0 = _mm256_blend_epi32(t0, t1, 0xF0); \
[all …]
/freebsd-14.2/sys/contrib/libb2/
H A Dblake2s-load-sse41.h42 t0 = _mm_slli_si128(m1, 4); \
48 t0 = _mm_unpackhi_epi32(m0,m1); \
54 t0 = _mm_unpackhi_epi32(m2,m3); \
60 t0 = _mm_unpacklo_epi32(m2,m0); \
72 t0 = _mm_slli_si128(m3, 4); \
84 t0 = _mm_slli_si128(m2, 8); \
117 t1 = _mm_slli_si128(t0, 8); \
127 t0 = _mm_srli_si128(m2, 4); \
143 t0 = _mm_slli_si128(m1, 12); \
198 t1 = _mm_slli_si128(t0,4); \
[all …]
H A Dblake2s-load-xop.h43 t0 = _mm_perm_epi8(m1, m2, _mm_set_epi32(TOB(0),TOB(5),TOB(0),TOB(0)) ); \
44 buf = _mm_perm_epi8(t0, m3, _mm_set_epi32(TOB(5),TOB(2),TOB(1),TOB(6)) );
51 t0 = _mm_perm_epi8(m0, m1, _mm_set_epi32(TOB(5),TOB(0),TOB(0),TOB(1)) ); \
52 buf = _mm_perm_epi8(t0, m2, _mm_set_epi32(TOB(3),TOB(7),TOB(1),TOB(0)) );
60 buf = _mm_perm_epi8(t0, m3, _mm_set_epi32(TOB(7),TOB(2),TOB(4),TOB(0)) );
68 buf = _mm_perm_epi8(t0, m2, _mm_set_epi32(TOB(5),TOB(2),TOB(1),TOB(6)) );
76 t0 = _mm_perm_epi8(t0, m2, _mm_set_epi32(TOB(7),TOB(2),TOB(1),TOB(0)) ); \
77 buf = _mm_perm_epi8(t0, m3, _mm_set_epi32(TOB(3),TOB(5),TOB(1),TOB(0)) );
101 t0 = _mm_perm_epi8(t0, m2, _mm_set_epi32(TOB(3),TOB(2),TOB(7),TOB(0)) ); \
150 t0 = _mm_perm_epi8(t0, m2, _mm_set_epi32(TOB(3),TOB(4),TOB(1),TOB(0)) ); \
[all …]
/freebsd-14.2/crypto/openssl/crypto/seed/
H A Dseed.c450 seed_word t0, t1; in SEED_set_key() local
457 t0 = (x1 + x3 - KC0) & 0xffffffff; in SEED_set_key()
510 seed_word t0, t1; in SEED_encrypt() local
518 E_SEED(t0, t1, x1, x2, x3, x4, 0); in SEED_encrypt()
519 E_SEED(t0, t1, x3, x4, x1, x2, 2); in SEED_encrypt()
520 E_SEED(t0, t1, x1, x2, x3, x4, 4); in SEED_encrypt()
521 E_SEED(t0, t1, x3, x4, x1, x2, 6); in SEED_encrypt()
522 E_SEED(t0, t1, x1, x2, x3, x4, 8); in SEED_encrypt()
555 seed_word t0, t1; in SEED_decrypt() local
574 E_SEED(t0, t1, x3, x4, x1, x2, 8); in SEED_decrypt()
[all …]
/freebsd-14.2/sys/riscv/riscv/
H A Dlocore.S68 amoadd.w t0, t1, 0(t0)
188 or t0, t0, t2
204 sub t0, t0, s9
206 add t0, t0, t1
230 li t0, 0
247 addi t0, t0, 8
262 add t0, t0, t1
356 add t0, t0, t1
372 sub t0, t0, s9
374 add t0, t0, t1
[all …]
H A Dexception.S92 add t0, sp, t1
99 li t0, 0
101 csrr t0, sepc
103 csrr t0, sstatus
108 csrc sstatus, t0
110 csrr t0, stval
112 csrr t0, scause
121 or t0, t0, t1
129 and t0, t0, t1
131 csrw sstatus, t0
[all …]
/freebsd-14.2/crypto/openssl/crypto/sha/asm/
H A Dsha512-armv4.pl115 eor $t0,$t0,$Ehi,lsl#18
119 eor $t0,$t0,$Elo,lsr#18
123 eor $t0,$t0,$Ehi,lsr#9
136 eor $t0,$t0,$t2
140 and $t0,$t0,$Elo
144 eor $t0,$t0,$t2
171 eor $t0,$t0,$Ahi,lsl#4
173 eor $t0,$t0,$Ahi,lsr#2
440 adds $t0,$Alo,$t0
457 adds $t0,$Alo,$t0
[all …]
H A Dsha1-mips.pl103 $t0="\$25";
132 and $t0,$b
140 xor $t0,$d
154 and $t0,$b
156 xor $t0,$d
191 and $t0,$b
194 xor $t0,$d
210 and $t0,$b
214 xor $t0,$d
235 xor $t0,$b
[all …]
H A Dsha1-thumb.pl34 $t0="r0";
50 sub $t0,#4
175 ldmia $t0!,{$a,$b,$c,$d,$e} @ $t0 is r0 and holds ctx
176 mov $t0,$Xi
179 mov $t1,$t0
187 cmp $Xi,$t0
191 mov $t1,$t0
199 cmp $Xi,$t0
201 cmp sp,$t0
205 mov $t1,$t0
[all …]
H A Dsha1-parisc.pl62 $t0="%r28";
78 and $c,$b,$t0
82 or $t1,$t0,$t0
95 or $t1,$t0,$t0
115 xor $d,$t0,$t0
129 xor $d,$t0,$t0
146 and $b,$t0,$t0
190 sh3addl $t0,%r0,$t0 ; t0*=8;
191 subi 32,$t0,$t0 ; t0=32-t0;
195 ldi 3,$t0
[all …]
/freebsd-14.2/lib/libmp/tests/
H A Dlegacy_test.c54 mp_madd(c42, c1, t0); in testsimpel()
56 mp_madd(t0, c1, t0); in testsimpel()
58 mp_msub(t0, c1, t0); in testsimpel()
60 mp_msub(t0, c1, t0); in testsimpel()
62 mp_move(c42, t0); in testsimpel()
79 mp_gcd(c10, c15, t0); in testgcd()
126 mp_mult(c5, c2, t0); in testmult()
128 mp_mult(c3, c14, t0); in testmult()
140 mp_rpow(c2, 3, t0); in testpow()
178 t0 = mp_itom(0); in main()
[all …]
/freebsd-14.2/crypto/openssl/crypto/ec/asm/
H A Dx25519-ppc64.pl320 ld $t0,0($ap)
326 mulhdu $t0,$t0,$bi
348 andc $t0,$t0,$t1
378 li $t0,38
389 andc $t0,$t0,$t1
419 li $t0,38
431 and $t0,$t0,$t1
454 and $t0,$t0,$t1
456 add $t0,$t0,$t1 # compare to modulus in the same go
467 andc $t0,$t1,$t0
[all …]
H A Decp_nistz256-x86_64.pl141 mov $a0, $t0
155 cmovc $t0, $a0
191 mov $a0, $t0
205 test \$1, $t0
215 shl \$63, $t0
218 or $t0, $a0
265 mov $a0, $t0
287 mov $a0, $t0
343 mov $a0, $t0
399 mov $a0, $t0
[all …]
H A Decp_nistz256-armv8.pl276 mov $t0,$acc0
301 mov $t0,$acc0
312 mov $t0,$a0
682 subs $t0,$acc0,#1 // adds $t0,$a0,#-1 // tmp = a+modulus
740 mov $t0,$acc0
1079 csel $t0,$a0,$t0,ne
1100 csel $t0,$a0,$t0,ne
1171 orr $t0,$t0,$t1
1174 orr $t0,$t0,$t2
1289 csel $t0,$a0,$t0,ne
[all …]
H A Decp_nistz256-ppc64.pl708 subfe $t0,$t2,$t0
739 subfe $t0,$t0,$t0 # t0 = borrow ? -1 : 0
772 subfe $t0,$t0,$t0 # t0 = borrow ? -1 : 0
799 neg $t0,$t0
801 not $t0,$t0
1326 or $t0,$t0,$a0
1370 or $t0,$t0,$a0
1484 or $t0,$t0,$t1
1486 or $t0,$t0,$t2
1633 or $t0,$t0,$a0
[all …]
/freebsd-14.2/crypto/openssl/crypto/modes/asm/
H A Dghash-alpha.pl32 $t0="t0";
288 zapnot $t0,0x11,$t0
292 or $t0,$t1,$t0
306 zapnot $t0,0x11,$t0
311 or $t0,$t1,$t0
377 zapnot $t0,0x11,$t0
381 or $t0,$t1,$t0
396 zapnot $t0,0x11,$t0
402 or $t0,$t1,$t0
418 zapnot $t0,0x11,$t0
[all …]
H A Dghashv8-armx.pl127 vand $t0,$t0,$t1
135 veor $t0,$t0,$H
137 vpmull.p64 $Xm,$t0,$t0
200 veor $t0,$t0,$H
313 vrev64.8 $t0,$t0
360 vrev64.8 $t0,$t0
501 veor $t0,$t0,$IN
556 veor $t0,$t0,$IN
612 veor $t0,$t0,$IN
655 veor $t0,$t0,$IN
[all …]
/freebsd-14.2/crypto/openssl/crypto/bn/asm/
H A Darmv4-gf2m.pl115 eor $lo,$lo,$t0,lsl#6
147 eor $hi,$hi,$t0,lsr#8
164 eor $hi,$hi,$t0,lsr#2
271 vmull.p8 $t0, $t0#lo, $b @ F = A1*B
279 veor $t0, $t0, $r @ L = E + F
284 veor $t0#lo, $t0#lo, $t0#hi @ t0 = (L) (P0 + P1) << 8
285 vand $t0#hi, $t0#hi, $k48
291 veor $t0#lo, $t0#lo, $t0#hi
295 vext.8 $t0, $t0, $t0, #15
303 veor $t0, $t0, $t1
[all …]
H A Dppc64-mont.pl814 addc $t0,$t0,$carry
1154 adde $t0,$t0,$t1
1232 addc $t0,$t0,$t2
1283 adde $t0,$t0,$t7
1344 adde $t0,$t0,$t1
1406 addc $t0,$t0,$t2
1448 adde $t0,$t0,$t7
1524 and $t0,$t0,$ovf
1528 or $t0,$t0,$t2
1595 and $t0,$t0,$ovf
[all …]
H A Darmv8-mont.pl768 mul $t0,$a5,$a0
794 mul $t0,$a4,$a1
942 mul $t0,$a0,$n0
949 mul $t0,$a4,$n0
1015 sub $t1,$tp,$t0
1033 ldp $a1,$a3,[$t0,#8*0] // recall that $t0 is &a[0]
1066 extr $t0,$t1,$t0,#63
1085 extr $t0,$t1,$t0,#63
1107 extr $t0,$t1,$t0,#63
1198 mul $t0,$a0,$n0
[all …]
/freebsd-14.2/crypto/openssh/
H A Dsmult_curve25519_ref.c190 unsigned int t0[32]; in recip() local
196 /* 8 */ square(t0,t1); in recip()
197 /* 9 */ mult(z9,t0,z); in recip()
199 /* 22 */ square(t0,z11); in recip()
203 /* 2^7 - 2^2 */ square(t1,t0); in recip()
211 /* 2^20 - 2^10 */ for (i = 2;i < 10;i += 2) { square(t0,t1); square(t1,t0); } in recip()
216 /* 2^40 - 2^20 */ for (i = 2;i < 20;i += 2) { square(t0,t1); square(t1,t0); } in recip()
221 /* 2^50 - 2^10 */ for (i = 2;i < 10;i += 2) { square(t1,t0); square(t0,t1); } in recip()
226 /* 2^100 - 2^50 */ for (i = 2;i < 50;i += 2) { square(t0,t1); square(t1,t0); } in recip()
231 /* 2^200 - 2^100 */ for (i = 2;i < 100;i += 2) { square(t1,t0); square(t0,t1); } in recip()
[all …]
H A Drijndael.c765 u32 s0, s1, s2, s3, t0, t1, t2, t3; in rijndaelEncrypt() local
855 t0 = in rijndaelEncrypt()
886 Te0[(t0 >> 24) ] ^ in rijndaelEncrypt()
895 Te3[(t0 ) & 0xff] ^ in rijndaelEncrypt()
900 Te2[(t0 >> 8) & 0xff] ^ in rijndaelEncrypt()
905 Te1[(t0 >> 16) & 0xff] ^ in rijndaelEncrypt()
1040 t0 =
1071 Td0[(t0 >> 24) ] ^
1078 Td1[(t0 >> 16) & 0xff] ^
1085 Td2[(t0 >> 8) & 0xff] ^
[all …]
/freebsd-14.2/sys/crypto/rijndael/
H A Drijndael-alg-fst.c862 u32 s0, s1, s2, s3, t0, t1, t2, t3; in rijndaelEncrypt() local
952 t0 = in rijndaelEncrypt()
983 Te0[(t0 >> 24) ] ^ in rijndaelEncrypt()
992 Te3[(t0 ) & 0xff] ^ in rijndaelEncrypt()
997 Te2[(t0 >> 8) & 0xff] ^ in rijndaelEncrypt()
1002 Te1[(t0 >> 16) & 0xff] ^ in rijndaelEncrypt()
1043 u32 s0, s1, s2, s3, t0, t1, t2, t3; in rijndaelDecrypt() local
1133 t0 = in rijndaelDecrypt()
1164 Td0[(t0 >> 24) ] ^ in rijndaelDecrypt()
1171 Td1[(t0 >> 16) & 0xff] ^ in rijndaelDecrypt()
[all …]
/freebsd-14.2/crypto/openssl/crypto/aes/asm/
H A Daes-parisc.pl110 and $inp,$t0,$t0
118 sh3addl $t0,%r0,$t0
119 subi 32,$t0,$t0
249 xor $acc0,$t0,$t0
252 xor $acc1,$t0,$t0
255 xor $acc2,$t0,$t0
258 xor $acc3,$t0,$t0
362 xor $acc0,$t0,$t0
365 xor $acc1,$t0,$t0
579 and $inp,$t0,$t0
[all …]
/freebsd-14.2/sys/crypto/camellia/
H A Dcamellia.c128 t0 = kll; \
130 t0 &= ll; \
967 t0,t1,il,ir); in camellia_encrypt128()
1002 t0 = io[0]; in camellia_encrypt128()
1006 io[2] = t0; in camellia_encrypt128()
1069 t0 = io[0]; in camellia_decrypt128()
1073 io[2] = t0; in camellia_decrypt128()
1155 t0 = io[0]; in camellia_encrypt256()
1159 io[2] = t0; in camellia_encrypt256()
1238 t0 = io[0]; in camellia_decrypt256()
[all …]

12345678910