Home
last modified time | relevance | path

Searched refs:t1 (Results 1 – 25 of 519) sorted by relevance

12345678910>>...21

/freebsd/sys/contrib/libsodium/src/libsodium/crypto_generichash/blake2b/ref/
H A Dblake2b-load-avx2.h7 t1 = _mm256_unpacklo_epi64(m2, m3); \
8 b0 = _mm256_blend_epi32(t0, t1, 0xF0); \
14 t1 = _mm256_unpackhi_epi64(m2, m3); \
15 b0 = _mm256_blend_epi32(t0, t1, 0xF0); \
21 t1 = _mm256_unpacklo_epi64(m6, m7); \
22 b0 = _mm256_blend_epi32(t0, t1, 0xF0); \
28 t1 = _mm256_unpackhi_epi64(m6, m7); \
29 b0 = _mm256_blend_epi32(t0, t1, 0xF0); \
35 t1 = _mm256_unpackhi_epi64(m4, m6); \
36 b0 = _mm256_blend_epi32(t0, t1, 0xF0); \
[all …]
/freebsd/sys/contrib/libb2/
H A Dblake2s-load-sse41.h31 t1 = _mm_slli_si128(m3, 4); \
32 t2 = _mm_blend_epi16(t0, t1, 0xF0); \
37 t1 = _mm_blend_epi16(m1,m3,0xC0); \
38 t2 = _mm_blend_epi16(t0, t1, 0xF0); \
43 t1 = _mm_blend_epi16(m2, t0, 0x30); \
44 t2 = _mm_blend_epi16(m0, t1, 0xF0); \
49 t1 = _mm_slli_si128(m3, 4); \
50 t2 = _mm_blend_epi16(t0, t1, 0x0C); \
55 t1 = _mm_blend_epi16(m3,m1,0x0C); \
56 t2 = _mm_blend_epi16(t0, t1, 0x0F); \
[all …]
/freebsd/crypto/openssl/crypto/seed/
H A Dseed.c439 seed_word t0, t1; in SEED_set_key() local
447 t1 = (x2 - x4 + KC0) & 0xffffffff; in SEED_set_key()
448 KEYUPDATE_TEMP(t0, t1, &ks->data[0]); in SEED_set_key()
449 KEYSCHEDULE_UPDATE1(t0, t1, x1, x2, x3, x4, KC1); in SEED_set_key()
450 KEYUPDATE_TEMP(t0, t1, &ks->data[2]); in SEED_set_key()
453 KEYSCHEDULE_UPDATE0(t0, t1, x1, x2, x3, x4, KC2); in SEED_set_key()
454 KEYUPDATE_TEMP(t0, t1, &ks->data[4]); in SEED_set_key()
455 KEYSCHEDULE_UPDATE1(t0, t1, x1, x2, x3, x4, KC3); in SEED_set_key()
456 KEYUPDATE_TEMP(t0, t1, &ks->data[6]); in SEED_set_key()
457 KEYSCHEDULE_UPDATE0(t0, t1, x1, x2, x3, x4, KC4); in SEED_set_key()
[all …]
/freebsd/crypto/openssl/crypto/sha/asm/
H A Dsha512-armv4.pl88 $t1="r10";
113 mov $t1,$Ehi,lsr#14
117 eor $t1,$t1,$Elo,lsl#18
120 eor $t1,$t1,$Ehi,lsr#18
122 eor $t1,$t1,$Elo,lsl#14
124 eor $t1,$t1,$Elo,lsr#9
126 eor $t1,$t1,$Ehi,lsl#23 @ Sigma1(e)
129 adc $Thi,$Thi,$t1 @ T += Sigma1(e)
130 ldr $t1,[sp,#$Foff+4] @ f.hi
138 eor $t1,$t1,$t3
[all …]
H A Dsha1-thumb.pl35 $t1="r1";
51 ldr $t1,[$t0]
57 add $t2,$t1 @ E+=X[i]
68 add $a,$t2,$t1 @ A=E+F_xx_xx(B,C,D)
75 mov $t1,$c
76 eor $t1,$d
77 and $t1,$b
78 eor $t1,$d @ F_00_19(B,C,D)
86 mov $t1,$b
87 eor $t1,$c
[all …]
H A Dsha256-armv4.pl66 $len="r2"; $t1="r2";
90 @ ldr $t1,[$inp],#4 @ $i
98 rev $t1,$t1
101 @ ldrb $t1,[$inp,#3] @ $i
105 orr $t1,$t1,$t2,lsl#8
107 orr $t1,$t1,$t0,lsl#16
112 orr $t1,$t1,$t2,lsl#24
118 add $h,$h,$t1 @ h+=X[i]
119 str $t1,[sp,#`$i%16`*4]
120 eor $t1,$f,$g
[all …]
/freebsd/contrib/bearssl/src/symcipher/
H A Daes_x86ni.c62 expand_step192(__m128i *t1, __m128i *t2, __m128i *t3) in expand_step192() argument
67 t4 = _mm_slli_si128(*t1, 0x4); in expand_step192()
68 *t1 = _mm_xor_si128(*t1, t4); in expand_step192()
70 *t1 = _mm_xor_si128(*t1, t4); in expand_step192()
72 *t1 = _mm_xor_si128(*t1, t4); in expand_step192()
73 *t1 = _mm_xor_si128(*t1, *t2); in expand_step192()
74 *t2 = _mm_shuffle_epi32(*t1, 0xFF); in expand_step192()
82 expand_step256_1(__m128i *t1, __m128i *t2) in expand_step256_1() argument
87 t4 = _mm_slli_si128(*t1, 0x4); in expand_step256_1()
88 *t1 = _mm_xor_si128(*t1, t4); in expand_step256_1()
[all …]
/freebsd/crypto/openssl/include/openssl/
H A Dsafestack.h.in39 #define SKM_DEFINE_STACK_OF_INTERNAL(t1, t2, t3) … argument
40 …STACK_OF(t1); …
41 …typedef int (*sk_##t1##_compfunc)(const t3 *const *a, const t3 *const *b); …
42 …typedef void (*sk_##t1##_freefunc)(t3 * a); …
43 …typedef t3 *(*sk_##t1##_copyfunc)(const t3 *a); …
44 …static ossl_unused ossl_inline t2 *ossl_check_##t1##_type(t2 *ptr) …
48 …l_unused ossl_inline const OPENSSL_STACK *ossl_check_const_##t1##_sk_type(const STACK_OF(t1) *sk) \
52 …static ossl_unused ossl_inline OPENSSL_STACK *ossl_check_##t1##_sk_type(STACK_OF(t1) *sk) …
56 …static ossl_unused ossl_inline OPENSSL_sk_compfunc ossl_check_##t1##_compfunc_type(sk_##t1##_compf…
60 …static ossl_unused ossl_inline OPENSSL_sk_copyfunc ossl_check_##t1##_copyfunc_type(sk_##t1##_copyf…
[all …]
H A Dsafestack.h36 #define SKM_DEFINE_STACK_OF_INTERNAL(t1, t2, t3) … argument
37 …STACK_OF(t1); …
38 …typedef int (*sk_##t1##_compfunc)(const t3 *const *a, const t3 *const *b); …
39 …typedef void (*sk_##t1##_freefunc)(t3 * a); …
40 …typedef t3 *(*sk_##t1##_copyfunc)(const t3 *a); …
41 …static ossl_unused ossl_inline t2 *ossl_check_##t1##_type(t2 *ptr) …
45 …l_unused ossl_inline const OPENSSL_STACK *ossl_check_const_##t1##_sk_type(const STACK_OF(t1) *sk) \
49 …static ossl_unused ossl_inline OPENSSL_STACK *ossl_check_##t1##_sk_type(STACK_OF(t1) *sk) …
53 …static ossl_unused ossl_inline OPENSSL_sk_compfunc ossl_check_##t1##_compfunc_type(sk_##t1##_compf…
57 …static ossl_unused ossl_inline OPENSSL_sk_copyfunc ossl_check_##t1##_copyfunc_type(sk_##t1##_copyf…
[all …]
/freebsd/share/misc/
H A Dscsi_modes57 {TMF_ONLY} t1
58 {DPICZ} t1
59 {D_SENSE} t1
60 {GLTSD} t1
61 {RLEC} t1
63 {NUAR} t1
65 {DQue} t1
66 {EECA} t1
67 {RAC} t1
69 {SWP} t1
[all …]
/freebsd/crypto/openssl/crypto/ec/asm/
H A Dx25519-ppc64.pl49 my ($bi,$a0,$a1,$a2,$a3,$t0,$t1, $t2,$t3,
84 mulhdu $t1,$a1,$bi
98 adde @acc[2],@acc[2],$t1
99 mulld $t1,$a1,$bi
106 adde @acc[2],@acc[2],$t1
107 mulhdu $t1,$a1,$bi
119 adde $acc5,$acc5,$t1
120 mulld $t1,$acc5,$bi
128 adde $acc1,$acc1,$t1
129 mulhdu $t1,$acc5,$bi
[all …]
H A Decp_nistp521-ppc64.pl150 my ($t1, $t2, $t3, $t4) = ("v33", "v34", "v44", "v54");
178 xxpermdi $t1,$in1[0],$in1[1],0b00
180 vmsumudm $out[1],$t1,$t2,$vzero
183 vmsumudm $out[2],$t1,$t2,$vzero
187 vmsumudm $out[3],$t1,$t2,$vzero
193 vmsumudm $out[4],$t1,$t2,$vzero
199 vmsumudm $out[5],$t1,$t2,$vzero
204 vmsumudm $out[6],$t1,$t2,$vzero
209 vmsumudm $out[7],$t1,$t2,$vzero
214 vmsumudm $out[8],$t1,$t2,$vzero
[all …]
H A Decp_sm2p256-armv8.pl25 my ($t0,$t1,$t2,$t3)=map("x$_",(3..6));
52 mov $t1,$s1
58 sbcs $t1,$t1,$s5
65 csel $s1,$s1,$t1,cc
99 mov $t1,$s1
105 adcs $t1,$t1,$s5
112 csel $s1,$s1,$t1,eq
275 mov $t1,$s1
291 csel $s1,$s1,$t1,cs
306 mov $t1,$s1
[all …]
H A Decp_nistz256-x86_64.pl119 my ($t0,$t1,$t2,$t3,$t4)=("%rax","%rdx","%rcx","%r12","%r13");
146 mov $a1, $t1
158 cmovc $t1, $a1
197 mov $a1, $t1
210 cmovz $t1, $a1
218 mov $a2, $t1
221 shl \$63, $t1
224 or $t1, $a1
270 mov $a1, $t1
282 cmovc $t1, $a1
[all …]
/freebsd/crypto/openssl/crypto/aes/asm/
H A Daes-armv4.pl63 $t1="r4";
218 ldrb $t1,[$rounds,#2] @ manner...
221 orr $s0,$s0,$t1,lsl#8
224 ldrb $t1,[$rounds,#6]
228 orr $s1,$s1,$t1,lsl#8
231 ldrb $t1,[$rounds,#10]
235 orr $s2,$s2,$t1,lsl#8
238 ldrb $t1,[$rounds,#14]
242 orr $s3,$s3,$t1,lsl#8
272 mov $t1,$s0,lsr#24 @ write output in endian-neutral
[all …]
/freebsd/crypto/openssl/crypto/modes/asm/
H A Dghash-riscv64.pl148 my ($z0,$z1,$z2,$z3,$t0,$t1,$polymod) = ("t0","t1","t2","t3","t4","t5","t6");
172 @{[clmulh $t1, $x0, $y1]}
174 xor $z2, $z2, $t1
175 @{[clmulh $t1, $x1, $y0]}
177 xor $z2, $z2, $t1
179 @{[clmulh $t1, $x0, $y0]}
181 xor $z1, $z1, $t1
184 @{[clmulh $t1, $z3, $polymod]}
186 xor $z2, $z2, $t1
188 @{[clmulh $t1, $z2, $polymod]}
[all …]
H A Dghashv8-armx.pl72 my ($t0,$t1,$t2,$xC2,$H,$Hhl,$H2)=map("q$_",(8..14));
115 vld1.64 {$t1},[x1] @ load input H
118 vext.8 $IN,$t1,$t1,#8
120 vdup.32 $t1,${t1}[1]
123 vshr.s32 $t1,$t1,#31 @ broadcast carry bit
127 vand $t0,$t0,$t1
139 vext.8 $t1,$Xl,$Xh,#8 @ Karatsuba post-processing
141 veor $Xm,$Xm,$t1
154 vext.8 $t1,$H2,$H2,#8 @ Karatsuba pre-processing
155 veor $t1,$t1,$H2
[all …]
H A Dghashp8-ppc.pl72 my ($zero,$t0,$t1,$t2,$xC2,$H,$Hh,$Hl,$lemask)=map("v$_",(4..12));
98 vsldoi $t1,$zero,$t0,1 # ...1
101 vor $xC2,$xC2,$t1 # 0xc2....01
102 vspltb $t1,$H,0 # most significant byte
104 vsrab $t1,$t1,$t2 # broadcast carry bit
105 vand $t1,$t1,$xC2
106 vxor $IN,$H,$t1 # twisted H
128 vsldoi $t1,$zero,$Xm,8
130 vxor $Xh,$Xh,$t1
135 vsldoi $t1,$Xl,$Xl,8 # 2nd reduction phase
[all …]
/freebsd/crypto/openssl/crypto/bn/asm/
H A Darmv4-gf2m.pl78 ($hi,$lo,$t0,$t1, $i0,$i1 )=map("r$_",(4..9),12);
107 ldr $t1,[sp,$i1] @ tab[b >> 3 & 0x7]
110 eor $lo,$lo,$t1,lsl#3 @ stall
111 mov $hi,$t1,lsr#29
112 ldr $t1,[sp,$i1] @ tab[b >> 9 & 0x7]
120 eor $lo,$lo,$t1,lsl#9
121 eor $hi,$hi,$t1,lsr#23
122 ldr $t1,[sp,$i1] @ tab[b >> 15 & 0x7]
130 eor $lo,$lo,$t1,lsl#15
131 eor $hi,$hi,$t1,lsr#17
[all …]
/freebsd/crypto/heimdal/lib/roken/
H A Dtimeval.c47 timevalfix(struct timeval *t1) in timevalfix() argument
49 if (t1->tv_usec < 0) { in timevalfix()
50 t1->tv_sec--; in timevalfix()
51 t1->tv_usec += 1000000; in timevalfix()
53 if (t1->tv_usec >= 1000000) { in timevalfix()
54 t1->tv_sec++; in timevalfix()
55 t1->tv_usec -= 1000000; in timevalfix()
64 timevaladd(struct timeval *t1, const struct timeval *t2) in timevaladd() argument
66 t1->tv_sec += t2->tv_sec; in timevaladd()
67 t1->tv_usec += t2->tv_usec; in timevaladd()
[all …]
/freebsd/lib/libc/riscv/string/
H A Dmemcpy.S21 sltiu t1, a2, 8
27 bnez t1, .Lend
30 neg t1, a0
31 andi t1, t1, 0b111
33 sub a2, a2, t1
36 slli t3, t1, 3
55 add a1, a1, t1
56 add a3, a3, t1
87 slli t1, a6, 3
88 add a1, a1, t1
[all …]
/freebsd/crypto/openssh/
H A Dsmult_curve25519_ref.c191 unsigned int t1[32]; in recip() local
195 /* 4 */ square(t1,z2); in recip()
196 /* 8 */ square(t0,t1); in recip()
203 /* 2^7 - 2^2 */ square(t1,t0); in recip()
204 /* 2^8 - 2^3 */ square(t0,t1); in recip()
205 /* 2^9 - 2^4 */ square(t1,t0); in recip()
206 /* 2^10 - 2^5 */ square(t0,t1); in recip()
210 /* 2^12 - 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()
212 /* 2^20 - 2^0 */ mult(z2_20_0,t1,z2_10_0); in recip()
[all …]
H A Drijndael.c765 u32 s0, s1, s2, s3, t0, t1, t2, t3; in rijndaelEncrypt() local
781 t1 = Te0[s1 >> 24] ^ Te1[(s2 >> 16) & 0xff] ^ Te2[(s3 >> 8) & 0xff] ^ Te3[s0 & 0xff] ^ rk[ 5]; in rijndaelEncrypt()
785 s0 = Te0[t0 >> 24] ^ Te1[(t1 >> 16) & 0xff] ^ Te2[(t2 >> 8) & 0xff] ^ Te3[t3 & 0xff] ^ rk[ 8]; in rijndaelEncrypt()
786 s1 = Te0[t1 >> 24] ^ Te1[(t2 >> 16) & 0xff] ^ Te2[(t3 >> 8) & 0xff] ^ Te3[t0 & 0xff] ^ rk[ 9]; in rijndaelEncrypt()
787 s2 = Te0[t2 >> 24] ^ Te1[(t3 >> 16) & 0xff] ^ Te2[(t0 >> 8) & 0xff] ^ Te3[t1 & 0xff] ^ rk[10]; in rijndaelEncrypt()
788 s3 = Te0[t3 >> 24] ^ Te1[(t0 >> 16) & 0xff] ^ Te2[(t1 >> 8) & 0xff] ^ Te3[t2 & 0xff] ^ rk[11]; in rijndaelEncrypt()
791 t1 = Te0[s1 >> 24] ^ Te1[(s2 >> 16) & 0xff] ^ Te2[(s3 >> 8) & 0xff] ^ Te3[s0 & 0xff] ^ rk[13]; in rijndaelEncrypt()
795 s0 = Te0[t0 >> 24] ^ Te1[(t1 >> 16) & 0xff] ^ Te2[(t2 >> 8) & 0xff] ^ Te3[t3 & 0xff] ^ rk[16]; in rijndaelEncrypt()
796 s1 = Te0[t1 >> 24] ^ Te1[(t2 >> 16) & 0xff] ^ Te2[(t3 >> 8) & 0xff] ^ Te3[t0 & 0xff] ^ rk[17]; in rijndaelEncrypt()
797 s2 = Te0[t2 >> 24] ^ Te1[(t3 >> 16) & 0xff] ^ Te2[(t0 >> 8) & 0xff] ^ Te3[t1 & 0xff] ^ rk[18]; in rijndaelEncrypt()
[all …]
/freebsd/lib/msun/src/
H A De_hypot.c53 double a,b,t1,t2,y1,y2,w; in hypot() local
86 t1=0; in hypot()
87 SET_HIGH_WORD(t1,0x7fd00000); /* t1=2^1022 */ in hypot()
88 b *= t1; in hypot()
89 a *= t1; in hypot()
102 t1 = 0; in hypot()
103 SET_HIGH_WORD(t1,ha); in hypot()
104 t2 = a-t1; in hypot()
105 w = sqrt(t1*t1-(b*(-b)-t2*(a+t1))); in hypot()
111 t1 = 0; in hypot()
[all …]
/freebsd/sys/crypto/rijndael/
H A Drijndael-alg-fst.c862 u32 s0, s1, s2, s3, t0, t1, t2, t3; in rijndaelEncrypt() local
878 t1 = Te0[s1 >> 24] ^ Te1[(s2 >> 16) & 0xff] ^ Te2[(s3 >> 8) & 0xff] ^ Te3[s0 & 0xff] ^ rk[ 5]; in rijndaelEncrypt()
882 s0 = Te0[t0 >> 24] ^ Te1[(t1 >> 16) & 0xff] ^ Te2[(t2 >> 8) & 0xff] ^ Te3[t3 & 0xff] ^ rk[ 8]; in rijndaelEncrypt()
883 s1 = Te0[t1 >> 24] ^ Te1[(t2 >> 16) & 0xff] ^ Te2[(t3 >> 8) & 0xff] ^ Te3[t0 & 0xff] ^ rk[ 9]; in rijndaelEncrypt()
884 s2 = Te0[t2 >> 24] ^ Te1[(t3 >> 16) & 0xff] ^ Te2[(t0 >> 8) & 0xff] ^ Te3[t1 & 0xff] ^ rk[10]; in rijndaelEncrypt()
885 s3 = Te0[t3 >> 24] ^ Te1[(t0 >> 16) & 0xff] ^ Te2[(t1 >> 8) & 0xff] ^ Te3[t2 & 0xff] ^ rk[11]; in rijndaelEncrypt()
888 t1 = Te0[s1 >> 24] ^ Te1[(s2 >> 16) & 0xff] ^ Te2[(s3 >> 8) & 0xff] ^ Te3[s0 & 0xff] ^ rk[13]; in rijndaelEncrypt()
892 s0 = Te0[t0 >> 24] ^ Te1[(t1 >> 16) & 0xff] ^ Te2[(t2 >> 8) & 0xff] ^ Te3[t3 & 0xff] ^ rk[16]; in rijndaelEncrypt()
893 s1 = Te0[t1 >> 24] ^ Te1[(t2 >> 16) & 0xff] ^ Te2[(t3 >> 8) & 0xff] ^ Te3[t0 & 0xff] ^ rk[17]; in rijndaelEncrypt()
894 s2 = Te0[t2 >> 24] ^ Te1[(t3 >> 16) & 0xff] ^ Te2[(t0 >> 8) & 0xff] ^ Te3[t1 & 0xff] ^ rk[18]; in rijndaelEncrypt()
[all …]

12345678910>>...21