Home
last modified time | relevance | path

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

123

/f-stack/freebsd/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 …]
H A Dblake2b-compress-sse41.h60 t0 = _mm_alignr_epi8(row2h, row2l, 8); \
62 row2l = t0; \
65 t0 = row3l; \
67 row3h = t0; \
69 t0 = _mm_alignr_epi8(row4h, row4l, 8); \
72 row4h = t0;
75 t0 = _mm_alignr_epi8(row2l, row2h, 8); \
77 row2l = t0; \
80 t0 = row3l; \
82 row3h = t0; \
[all …]
H A Dblake2b-compress-ssse3.h60 t0 = _mm_alignr_epi8(row2h, row2l, 8); \
62 row2l = t0; \
65 t0 = row3l; \
67 row3h = t0; \
69 t0 = _mm_alignr_epi8(row4h, row4l, 8); \
72 row4h = t0;
75 t0 = _mm_alignr_epi8(row2l, row2h, 8); \
77 row2l = t0; \
80 t0 = row3l; \
82 row3h = t0; \
[all …]
/f-stack/freebsd/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 …]
H A Dblake2b-round.h89 row2l = t0; \
92 t0 = row3l; \
99 row4h = t0;
104 row2l = t0; \
107 t0 = row3l; \
109 row3h = t0; \
114 row4h = t0;
118 t0 = row4l;\
129 t0 = row3l;\
131 row3h = t0;\
[all …]
/f-stack/freebsd/mips/mips/
H A Dsupport.S414 and t0, t0, 3
586 xori t0, t0, 2
592 or t0, t0, a1
613 xori t0, t0, 2
620 and t0, t0, a1
642 xori t0, t0, 2 # flip order for big-endian
654 xor t0, t0, t1
675 xori t0, t0, 2 # flip order for big-endian
687 xor t0, t0, t1
719 xor t0, t0, t1
[all …]
H A Dbcopy.S81 sltu t0,SRCREG,DSTREG # t0 == SRCREG < DSTREG
101 bne t0,zero,5f
112 PTR_SUBU SIZEREG,t0
145 PTR_ADDU t0,SRCREG,t2 # stop at t0
151 bne SRCREG,t0,1b
173 andi t0,SIZEREG,(SZREG-1) # t0 = bytecount mod SZREG
197 bne t0,zero,5f
205 PTR_SUBU SIZEREG,t0
239 PTR_SUBU t0,SRCREG,t2 # stop at t0
245 bne SRCREG,t0,1b
[all …]
H A Docteon_cop2_swtch.S49 and t0, t0, ~MIPS_SR_INT_IE
50 mtc0 t0, MIPS_COP_0_STATUS
53 dmfc0 t0, $9, 7
61 bbit1 t0, 28, save_nodfa
70 bbit1 t0, 26, save_done
90 dmfc0 t0, $15
92 beq t0, t1, save_pass1
151 and t0, t0, ~MIPS_SR_INT_IE
154 dmfc0 t0, $9, 7
191 dmfc0 t0, $15
[all …]
H A Dlocore.S101 … li t0, ~(MIPS_SR_DE | MIPS_SR_SR | MIPS_SR_ERL | MIPS_SR_EXL | MIPS_SR_INT_IE | MIPS_SR_COP_2_BIT)
107 li t0, ~(MIPS_SR_BEV | MIPS_SR_SR | MIPS_SR_INT_IE)
114 li t0, (MIPS_SR_BEV | MIPS_SR_SR)
133 and t2, t0
139 li t0, MIPS_CCA_CACHED
140 mtc0 t0, MIPS_COP_0_CONFIG
196 REG_LI t0, ~7
197 and a0, a0, t0
H A Dfp.S672 or t0, t0, ta0 # compute result sign
1254 xor t0, t0, 1 # reverse sign
1262 xor t0, t0, 1 # reverse sign
2542 srl t0, t0, 31 # get sign
2777 srl t0, t0, 31 # get sign
2879 srl t0, t0, 31 # get sign
3073 srl t0, t0, 31 # get sign
3195 sll t0, t0, 31 # position sign
3291 sll t0, t0, 31 # set sign
3293 or t0, t0, t1
[all …]
H A Dinckern.S29 PTR_LA t0, kernel_end
30 move sp, t0
33 PTR_LA t0, _startC
34 j t0
/f-stack/freebsd/crypto/rijndael/
H A Drijndael-alg-fst.c864 u32 s0, s1, s2, s3, t0, t1, t2, t3; in rijndaelEncrypt() local
954 t0 = in rijndaelEncrypt()
985 Te0[(t0 >> 24) ] ^ in rijndaelEncrypt()
994 Te3[(t0 ) & 0xff] ^ in rijndaelEncrypt()
999 Te2[(t0 >> 8) & 0xff] ^ in rijndaelEncrypt()
1004 Te1[(t0 >> 16) & 0xff] ^ in rijndaelEncrypt()
1045 u32 s0, s1, s2, s3, t0, t1, t2, t3; in rijndaelDecrypt() local
1135 t0 = in rijndaelDecrypt()
1166 Td0[(t0 >> 24) ] ^ in rijndaelDecrypt()
1173 Td1[(t0 >> 16) & 0xff] ^ in rijndaelDecrypt()
[all …]
/f-stack/freebsd/mips/nlm/
H A Dmpreset.S85 mfc0 t0, MIPS_COP_0_STATUS
87 and t1, t0, t1
93 mfc0 t0, MIPS_COP_0_PRID, 1
94 srl t0, t0, 2 /* discard thread id */
95 andi t0, t0, 0x7 /* core id */
97 sll t0, t1, t0
98 nor t0, t0, zero /* mask with core id bit clear */
103 and t1, t1, t0
159 andi t0, 0x3
160 beqz t0, 2f
[all …]
/f-stack/freebsd/crypto/camellia/
H A Dcamellia.c130 t0 = kll; \
132 t0 &= ll; \
969 t0,t1,il,ir); in camellia_encrypt128()
1004 t0 = io[0]; in camellia_encrypt128()
1008 io[2] = t0; in camellia_encrypt128()
1071 t0 = io[0]; in camellia_decrypt128()
1075 io[2] = t0; in camellia_decrypt128()
1157 t0 = io[0]; in camellia_encrypt256()
1161 io[2] = t0; in camellia_encrypt256()
1240 t0 = io[0]; in camellia_decrypt256()
[all …]
/f-stack/dpdk/drivers/net/softnic/
H A Drte_eth_softnic_cli.c1595 t0 = 5; in cmd_port_in_action_profile()
1808 t0 = 8; in cmd_table_action_profile()
1851 t0 += 7; in cmd_table_action_profile()
1907 t0 += 6; in cmd_table_action_profile()
1943 t0 += 5; in cmd_table_action_profile()
2061 t0 += 4; in cmd_table_action_profile()
2098 t0 += 4; in cmd_table_action_profile()
2298 t0 = 6; in cmd_pipeline_port_in()
2714 t0 = 4; in cmd_pipeline_table()
5096 t0 = 6; in cmd_softnic_pipeline_table_rule_add()
[all …]
/f-stack/app/redis-5.0.5/deps/jemalloc/test/src/
H A Dtimer.c5 nstime_init(&timer->t0, 0); in timer_start()
6 nstime_update(&timer->t0); in timer_start()
11 nstime_copy(&timer->t1, &timer->t0); in timer_stop()
20 nstime_subtract(&delta, &timer->t0); in timer_usec()
26 uint64_t t0 = timer_usec(a); 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/dpdk/examples/ip_pipeline/
H A Dcli.c906 t0 = 5; in cmd_port_in_action_profile()
1109 t0 = 8; in cmd_table_action_profile()
1148 t0 += 7; in cmd_table_action_profile()
1202 t0 += 6; in cmd_table_action_profile()
1237 t0 += 5; in cmd_table_action_profile()
1352 t0 += 4; in cmd_table_action_profile()
1388 t0 += 4; in cmd_table_action_profile()
1590 t0 = 6; in cmd_pipeline_port_in()
2022 t0 = 4; in cmd_pipeline_table()
4388 t0 = 6; in cmd_pipeline_table_rule_add()
[all …]
/f-stack/freebsd/contrib/libsodium/src/libsodium/crypto_pwhash/argon2/
H A Dblamka-round-ssse3.h75 __m128i t0 = _mm_alignr_epi8(B1, B0, 8); \
77 B0 = t0; \
80 t0 = C0; \
82 C1 = t0; \
84 t0 = _mm_alignr_epi8(D1, D0, 8); \
87 D1 = t0; \
92 __m128i t0 = _mm_alignr_epi8(B0, B1, 8); \
94 B0 = t0; \
97 t0 = C0; \
99 C1 = t0; \
[all …]
/f-stack/freebsd/contrib/openzfs/module/icp/algs/aes/
H A Daes_impl_generic.c1002 t0 = Te0[s0 >> 24] ^ in aes_generic_encrypt()
1032 s0 = Te0[t0 >> 24] ^ in aes_generic_encrypt()
1041 Te3[t0 & 0xff] ^ in aes_generic_encrypt()
1046 Te2[(t0 >> 8) & 0xff] ^ in aes_generic_encrypt()
1051 Te1[(t0 >> 16) & 0xff] ^ in aes_generic_encrypt()
1072 (Te4[t0 & 0xff] & 0x000000ff) ^ in aes_generic_encrypt()
1129 t0 = Td0[s0 >> 24] ^ in aes_generic_decrypt()
1159 s0 = Td0[t0 >> 24] ^ in aes_generic_decrypt()
1166 Td1[(t0 >> 16) & 0xff] ^ in aes_generic_decrypt()
1173 Td2[(t0 >> 8) & 0xff] ^ in aes_generic_decrypt()
[all …]
/f-stack/freebsd/mips/include/
H A Dpcb.h72 mfc0 t0, MIPS_COP_0_STATUS ;\
73 and a0, t0, MIPS_SR_INT_IE ;\
74 xor t0, a0, t0 ;\
75 mtc0 t0, MIPS_COP_0_STATUS ;\
83 mfc0 t0, MIPS_COP_0_STATUS ;\
84 or t0, a0, t0 ;\
85 mtc0 t0, MIPS_COP_0_STATUS ;\
/f-stack/freebsd/mips/cavium/
H A Dasm_octeon.S53 1: ll t0, octeon_ap_boot
54 bne v0, t0, 1b
57 move t0, zero
58 sc t0, octeon_ap_boot
60 beqz t0, 1b
H A Docteon_cop2.S45 dmfc0 t0, $9, 7
53 bbit1 t0, 28, save_nodfa
62 bbit1 t0, 26, save_done
82 dmfc0 t0, $15
84 beq t0, t1, save_pass1
137 dmfc0 t0, $9, 7
145 bbit1 t0, 28, restore_nodfa
154 bbit1 t0, 26, restore_done
174 dmfc0 t0, $15
176 beq t0, t1, restore_pass1
/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
40 t0 = LOAD64_LE(&key[0]); in poly1305_init()
44 st->r[0] = (t0) &0xffc0fffffff; in poly1305_init()
45 st->r[1] = ((t0 >> 44) | (t1 << 20)) & 0xfffffc0ffff; in poly1305_init()
85 unsigned long long t0, t1; in poly1305_blocks() local
88 t0 = LOAD64_LE(&m[0]); in poly1305_blocks()
91 h0 += ((t0) &0xfffffffffff); in poly1305_blocks()
92 h1 += (((t0 >> 44) | (t1 << 20)) & 0xfffffffffff); in poly1305_blocks()
140 unsigned long long t0, t1; in poly1305_finish() local
199 t0 = st->pad[0]; in poly1305_finish()
[all …]
/f-stack/freebsd/mips/malta/
H A Dasm_malta.S79 ll t0, 0(t1)
80 bne v0, t0, 1b
83 move t0, zero
84 sc t0, 0(t1)
86 beqz t0, 1b

123