Home
last modified time | relevance | path

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

1234

/f-stack/freebsd/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 …]
H A Dblake2b-compress-sse41.h61 t1 = _mm_alignr_epi8(row2l, row2h, 8); \
63 row2h = t1; \
70 t1 = _mm_alignr_epi8(row4l, row4h, 8); \
71 row4l = t1; \
76 t1 = _mm_alignr_epi8(row2h, row2l, 8); \
78 row2h = t1; \
85 t1 = _mm_alignr_epi8(row4h, row4l, 8); \
86 row4l = t1; \
H A Dblake2b-compress-ssse3.h61 t1 = _mm_alignr_epi8(row2l, row2h, 8); \
63 row2h = t1; \
70 t1 = _mm_alignr_epi8(row4l, row4h, 8); \
71 row4l = t1; \
76 t1 = _mm_alignr_epi8(row2h, row2l, 8); \
78 row2h = t1; \
85 t1 = _mm_alignr_epi8(row4h, row4l, 8); \
86 row4l = t1; \
/f-stack/freebsd/contrib/libb2/
H A Dblake2s-load-sse41.h31 t1 = _mm_slli_si128(m3, 4); \
49 t1 = _mm_slli_si128(m3, 4); \
67 t1 = _mm_srli_si128(m1, 12); \
97 buf = _mm_unpacklo_epi64(t1,t0);
117 t1 = _mm_slli_si128(t0, 8); \
124 buf = _mm_unpacklo_epi64(t0,t1);
133 t1 = _mm_srli_si128(m3, 4); \
149 t1 = _mm_srli_si128(m1, 4); \
155 t1 = _mm_srli_si128(m1, 4); \
170 t1 = _mm_srli_si128(m0,4); \
[all …]
H A Dblake2s-load-xop.h47 t1 = _mm_perm_epi8(m1, m2, _mm_set_epi32(TOB(2),TOB(0),TOB(4),TOB(6)) ); \
48 buf = _mm_perm_epi8(t1, m3, _mm_set_epi32(TOB(3),TOB(7),TOB(1),TOB(0)) );
55 t1 = _mm_perm_epi8(m0, m1, _mm_set_epi32(TOB(3),TOB(7),TOB(2),TOB(0)) ); \
56 buf = _mm_perm_epi8(t1, m3, _mm_set_epi32(TOB(3),TOB(2),TOB(1),TOB(4)) );
63 t1 = _mm_perm_epi8(m0, m2, _mm_set_epi32(TOB(0),TOB(2),TOB(0),TOB(4)) ); \
64 buf = _mm_perm_epi8(t1, m3, _mm_set_epi32(TOB(5),TOB(2),TOB(1),TOB(0)) );
71 t1 = _mm_perm_epi8(m0, m1, _mm_set_epi32(TOB(4),TOB(1),TOB(6),TOB(0)) ); \
72 buf = _mm_perm_epi8(t1, m3, _mm_set_epi32(TOB(3),TOB(2),TOB(1),TOB(6)) );
81 buf = _mm_perm_epi8(t1, m3, _mm_set_epi32(TOB(6),TOB(4),TOB(1),TOB(0)) );
89 buf = _mm_perm_epi8(t1, m2, _mm_set_epi32(TOB(4),TOB(2),TOB(6),TOB(0)) );
[all …]
H A Dblake2b-round.h88 t1 = _mm_alignr_epi8(row2l, row2h, 8); \
90 row2h = t1; \
97 t1 = _mm_alignr_epi8(row4l, row4h, 8); \
98 row4l = t1; \
103 t1 = _mm_alignr_epi8(row2h, row2l, 8); \
105 row2h = t1; \
113 row4l = t1; \
119 t1 = row2l;\
126 row2h = _mm_unpackhi_epi64(row2h, _mm_unpacklo_epi64(t1, t1))
133 t1 = row4l;\
[all …]
/f-stack/freebsd/crypto/rijndael/
H A Drijndael-alg-fst.c864 u32 s0, s1, s2, s3, t0, t1, t2, t3; in rijndaelEncrypt() local
960 t1 = in rijndaelEncrypt()
986 Te1[(t1 >> 16) & 0xff] ^ in rijndaelEncrypt()
991 Te0[(t1 >> 24) ] ^ in rijndaelEncrypt()
1000 Te3[(t1 ) & 0xff] ^ in rijndaelEncrypt()
1005 Te2[(t1 >> 8) & 0xff] ^ in rijndaelEncrypt()
1045 u32 s0, s1, s2, s3, t0, t1, t2, t3; in rijndaelDecrypt() local
1141 t1 = in rijndaelDecrypt()
1169 Td3[(t1 ) & 0xff] ^ in rijndaelDecrypt()
1172 Td0[(t1 >> 24) ] ^ in rijndaelDecrypt()
[all …]
/f-stack/freebsd/mips/nlm/
H A Dmpreset.S86 li t1, 0x80000
87 and t1, t0, t1
88 bnez t1, nmi_handler
96 li t1, 1
97 sll t0, t1, t0
102 lw t1, 0(t2)
103 and t1, t1, t0
104 sw t1, 0(t2)
147 sd t1, 72(sp)
163 jr t1
[all …]
/f-stack/freebsd/crypto/camellia/
H A Dcamellia.c137 t1 = klr; \
139 t1 |= lr; \
140 ll ^= t1; \
1005 t1 = io[1]; in camellia_encrypt128()
1009 io[3] = t1; in camellia_encrypt128()
1072 t1 = io[1]; in camellia_decrypt128()
1076 io[3] = t1; in camellia_decrypt128()
1158 t1 = io[1]; in camellia_encrypt256()
1162 io[3] = t1; in camellia_encrypt256()
1241 t1 = io[1]; in camellia_decrypt256()
[all …]
/f-stack/freebsd/contrib/openzfs/module/icp/algs/aes/
H A Daes_impl_generic.c1008 t1 = Te0[s1 >> 24] ^ in aes_generic_encrypt()
1033 Te1[(t1 >> 16) & 0xff] ^ in aes_generic_encrypt()
1038 s1 = Te0[t1 >> 24] ^ in aes_generic_encrypt()
1047 Te3[t1 & 0xff] ^ in aes_generic_encrypt()
1052 Te2[(t1 >> 8) & 0xff] ^ in aes_generic_encrypt()
1079 (Te4[t1 & 0xff] & 0x000000ff) ^ in aes_generic_encrypt()
1135 t1 = Td0[s1 >> 24] ^ in aes_generic_decrypt()
1162 Td3[t1 & 0xff] ^ in aes_generic_decrypt()
1165 s1 = Td0[t1 >> 24] ^ in aes_generic_decrypt()
1172 Td1[(t1 >> 16) & 0xff] ^ in aes_generic_decrypt()
[all …]
/f-stack/freebsd/mips/mips/
H A Dsupport.S652 xor t1, t0, t1
653 and t1, t1, t2
685 xor t1, t0, t1
686 and t1, t1, t2
717 xor t1, t0, t1
718 and t1, t1, t2
750 xor t1, t0, t1
751 and t1, t1, t2
768 PTR_L t1, PC_CURPCB(t1)
787 PTR_L t1, PC_CURPCB(t1)
[all …]
H A Dfp.S1015 addu t1, t1, 12 # ???
1585 or t1, t1, t2
1615 or t1, t1, t2
1623 addu t1, t1, v0
1744 addu t1, t1, 1 # adjust exponent
1754 addu t1, t1, 1 # adjust exponent
2540 and t1, t1, 0xFF
2775 and t1, t1, 0x7FF
2877 and t1, t1, 0xFF
3071 and t1, t1, 0x7FF
[all …]
H A Dlocore.S98 li t1, (MIPS_SR_COP_0_BIT | MIPS_SR_PX | MIPS_SR_KX | MIPS_SR_UX | MIPS_SR_SX | MIPS_SR_BEV)
104 li t1, (MIPS_SR_COP_2_BIT | MIPS_SR_COP_0_BIT | MIPS_SR_KX | MIPS_SR_UX)
119 li t1, MIPS_SR_COP_1_BIT
121 or t1, MIPS_SR_FR
124 or t1, MIPS_SR_KX | MIPS_SR_SX | MIPS_SR_UX
134 or t2, t1
H A Dbcopy.S98 andi t1,DSTREG,(SZREG-1) # get last bits of dest
99 bne t1,zero,3f # dest unaligned
121 REG_L t1,(3*SZREG)(SRCREG)
126 REG_S t1,(3*SZREG)(DSTREG)
127 REG_L t1,(-1*SZREG)(SRCREG)
132 REG_S t1,(-1*SZREG)(DSTREG)
195 bne t1,zero,3f
215 REG_L t1,(-1*SZREG)(SRCREG)
220 REG_S t1,(-1*SZREG)(DSTREG)
221 REG_L t1,(3*SZREG)(SRCREG)
[all …]
H A Docteon_cop2_swtch.S38 dmfc2 t1, reg; sd t1, reg##_OFFSET(a0)
42 ld t1, reg##_OFFSET(a0); dmtc2 t1, reg##_SET
91 li t1, 0x000d0000 /* Octeon Pass1 */
92 beq t0, t1, save_pass1
192 li t1, 0x000d0000 /* Octeon Pass1 */
193 beq t0, t1, restore_pass1
/f-stack/app/redis-5.0.5/deps/jemalloc/test/src/
H A Dtimer.c11 nstime_copy(&timer->t1, &timer->t0); in timer_stop()
12 nstime_update(&timer->t1); in timer_stop()
19 nstime_copy(&delta, &timer->t1); in timer_usec()
27 uint64_t t1 = timer_usec(b); in timer_ratio() local
33 n = malloc_snprintf(&buf[i], buflen-i, "%"FMTu64, t0 / t1); in timer_ratio()
49 uint64_t round = (i+1 == buflen-1 && ((t0 * mult * 10 / t1) % 10 in timer_ratio()
52 "%"FMTu64, (t0 * mult / t1) % 10 + round); in timer_ratio()
/f-stack/freebsd/contrib/octeon-sdk/
H A Dcvmx-compactflash.c274 t1 = 10; in cvmx_compactflash_set_piomode()
285 t1 = 15; in cvmx_compactflash_set_piomode()
294 t1 = 25; in cvmx_compactflash_set_piomode()
303 t1 = 30; in cvmx_compactflash_set_piomode()
312 t1 = 30; in cvmx_compactflash_set_piomode()
321 t1 = 50; in cvmx_compactflash_set_piomode()
330 t1 = 70; in cvmx_compactflash_set_piomode()
344 t1 = FLASH_RoundUP(t1 * clocks_us, 1000); in cvmx_compactflash_set_piomode()
345 if (t1) in cvmx_compactflash_set_piomode()
346 t1--; in cvmx_compactflash_set_piomode()
[all …]
/f-stack/freebsd/contrib/libsodium/src/libsodium/crypto_onetimeauth/poly1305/donna/
H A Dpoly1305_donna64.h37 unsigned long long t0, t1; in poly1305_init() local
41 t1 = LOAD64_LE(&key[8]); in poly1305_init()
45 st->r[1] = ((t0 >> 44) | (t1 << 20)) & 0xfffffc0ffff; in poly1305_init()
46 st->r[2] = ((t1 >> 24)) & 0x00ffffffc0f; in poly1305_init()
85 unsigned long long t0, t1; in poly1305_blocks() local
89 t1 = LOAD64_LE(&m[8]); in poly1305_blocks()
92 h1 += (((t0 >> 44) | (t1 << 20)) & 0xfffffffffff); in poly1305_blocks()
93 h2 += (((t1 >> 24)) & 0x3ffffffffff) | hibit; in poly1305_blocks()
140 unsigned long long t0, t1; in poly1305_finish() local
200 t1 = st->pad[1]; in poly1305_finish()
[all …]
/f-stack/freebsd/contrib/libsodium/src/libsodium/crypto_core/ed25519/ref10/
H A Ded25519_ref10.c64 fe25519_sq(t1, t1); in fe25519_invert()
65 fe25519_mul(t1, z, t1); in fe25519_invert()
68 fe25519_mul(t1, t1, t2); in fe25519_invert()
73 fe25519_mul(t1, t2, t1); in fe25519_invert()
88 fe25519_mul(t1, t2, t1); in fe25519_invert()
104 fe25519_sq(t1, t1); in fe25519_invert()
106 fe25519_sq(t1, t1); in fe25519_invert()
121 fe25519_sq(t1, t1); in fe25519_pow22523()
122 fe25519_mul(t1, z, t1); in fe25519_pow22523()
141 fe25519_sq(t1, t1); in fe25519_pow22523()
[all …]
/f-stack/app/redis-5.0.5/deps/lua/src/
H A Dlobject.c72 int luaO_rawequalObj (const TValue *t1, const TValue *t2) { in luaO_rawequalObj() argument
73 if (ttype(t1) != ttype(t2)) return 0; in luaO_rawequalObj()
74 else switch (ttype(t1)) { in luaO_rawequalObj()
78 return luai_numeq(nvalue(t1), nvalue(t2)); in luaO_rawequalObj()
80 return bvalue(t1) == bvalue(t2); /* boolean true must be 1 !! */ in luaO_rawequalObj()
82 return pvalue(t1) == pvalue(t2); in luaO_rawequalObj()
84 lua_assert(iscollectable(t1)); in luaO_rawequalObj()
85 return gcvalue(t1) == gcvalue(t2); in luaO_rawequalObj()
/f-stack/freebsd/contrib/libsodium/src/libsodium/crypto_pwhash/argon2/
H A Dblamka-round-ssse3.h76 __m128i t1 = _mm_alignr_epi8(B0, B1, 8); \
78 B1 = t1; \
85 t1 = _mm_alignr_epi8(D0, D1, 8); \
86 D0 = t1; \
93 __m128i t1 = _mm_alignr_epi8(B1, B0, 8); \
95 B1 = t1; \
102 t1 = _mm_alignr_epi8(D1, D0, 8); \
103 D0 = t1; \
/f-stack/freebsd/contrib/openzfs/include/os/linux/spl/sys/
H A Dtrace.h68 #define DTRACE_PROBE1(name, t1, arg1) \ argument
71 #define DTRACE_PROBE2(name, t1, arg1, t2, arg2) \ argument
74 #define DTRACE_PROBE3(name, t1, arg1, t2, arg2, t3, arg3) \ argument
77 #define DTRACE_PROBE4(name, t1, arg1, t2, arg2, t3, arg3, t4, arg4) \ argument
93 #define DTRACE_PROBE1(name, t1, arg1) \ argument
96 #define DTRACE_PROBE2(name, t1, arg1, t2, arg2) \ argument
99 #define DTRACE_PROBE3(name, t1, arg1, t2, arg2, t3, arg3) \ argument
103 #define DTRACE_PROBE4(name, t1, arg1, t2, arg2, t3, arg3, t4, arg4) \ argument
/f-stack/freebsd/mips/cavium/
H A Docteon_cop2.S37 dmfc2 t1, reg; sd t1, reg##_OFFSET(a0)
41 ld t1, reg##_OFFSET(a0); dmtc2 t1, reg##_SET
83 li t1, 0x000d0000 /* Octeon Pass1 */
84 beq t0, t1, save_pass1
175 li t1, 0x000d0000 /* Octeon Pass1 */
176 beq t0, t1, restore_pass1
/f-stack/dpdk/drivers/net/bnxt/
H A Dbnxt_rxtx_vec_neon.c83 uint64x2_t t0, t1; in descs_to_mbufs() local
88 t1 = vreinterpretq_u64_u32(vzip1q_u32(mm_rxcmp[2], mm_rxcmp[3])); in descs_to_mbufs()
91 vget_low_u64(t1))); in descs_to_mbufs()
96 t1 = vreinterpretq_u64_u32(vzip1q_u32(mm_rxcmp1[2], mm_rxcmp1[3])); in descs_to_mbufs()
99 vget_low_u64(t1))); in descs_to_mbufs()
116 vget_low_u64(t1))); in descs_to_mbufs()
207 uint64x2_t t0, t1; in bnxt_recv_pkts_vec() local
213 t1 = vld1q_u64((void *)&rxr->rx_buf_ring[mbcons + 2]); in bnxt_recv_pkts_vec()
217 vst1q_u64((void *)&rx_pkts[i + 2], t1); in bnxt_recv_pkts_vec()
238 t1 = vreinterpretq_u64_u32(vzip2q_u32(rxcmp1[2], rxcmp1[3])); in bnxt_recv_pkts_vec()
[all …]
/f-stack/dpdk/lib/librte_acl/
H A Dacl_run_avx2.h94 ymm_t t0, t1; in acl_process_matches_avx2x8() local
123 t1 = _mm256_set_epi64x(tr[7], tr[6], tr[3], tr[2]); in acl_process_matches_avx2x8()
126 ACL_TR_HILO(mm256, __m256, t0, t1, lo, hi); in acl_process_matches_avx2x8()
169 ymm_t t0, t1; in search_avx2x16() local
181 t1 = _mm256_set_epi64x(index_array[7], index_array[6], in search_avx2x16()
184 ACL_TR_HILO(mm256, __m256, t0, t1, tr_lo[0], tr_hi[0]); in search_avx2x16()
188 t1 = _mm256_set_epi64x(index_array[15], index_array[14], in search_avx2x16()
191 ACL_TR_HILO(mm256, __m256, t0, t1, tr_lo[1], tr_hi[1]); in search_avx2x16()

1234