Home
last modified time | relevance | path

Searched refs:v0 (Results 1 – 25 of 109) sorted by relevance

12345

/f-stack/freebsd/crypto/openssl/aarch64/
H A Dghashv8-armx.S46 pmull v0.1q,v0.1d,v19.1d
131 rev64 v0.16b,v0.16b
133 ext v0.16b,v0.16b,v0.16b,#8
164 ext v0.16b,v0.16b,v0.16b,#8 //rotate Xi
169 rev64 v0.16b,v0.16b
265 ext v0.16b,v0.16b,v0.16b,#8
377 ext v0.16b,v0.16b,v0.16b,#8
432 ext v0.16b,v0.16b,v0.16b,#8
475 ext v0.16b,v0.16b,v0.16b,#8
516 ext v0.16b,v0.16b,v0.16b,#8
[all …]
H A Daesv8-armx.S36 eor v0.16b,v0.16b,v0.16b
209 aesimc v0.16b,v0.16b
217 aesimc v0.16b,v0.16b
324 aesmc v0.16b,v0.16b
332 aesmc v0.16b,v0.16b
336 aesmc v0.16b,v0.16b
338 aesmc v0.16b,v0.16b
342 aesmc v0.16b,v0.16b
347 aesmc v0.16b,v0.16b
350 aesmc v0.16b,v0.16b
[all …]
H A Dvpaes-armv8.S141 eor v0.16b, v0.16b, v2.16b // vpxor %xmm2, %xmm0, %xmm0
169 ushr v0.16b, v0.16b, #4 // vpsrlb $4, %xmm0, %xmm0 # 1 = i
233 eor v0.16b, v0.16b, v2.16b // vpxor %xmm2, %xmm0, %xmm0
359 eor v0.16b, v0.16b, v2.16b // vpxor %xmm2, %xmm0, %xmm0
724 dup v0.4s, v0.s[3] // vpshufd $0xFF, %xmm0, %xmm0
763 eor v0.16b, v0.16b, v0.16b // vpxor %xmm0, %xmm0, %xmm0
833 dup v0.4s, v0.s[3] // vpshufd $0xFF, %xmm0, %xmm0
834 ext v0.16b, v0.16b, v0.16b, #1 // vpalignr $1, %xmm0, %xmm0, %xmm0
883 ushr v0.16b, v0.16b, #4 // vpsrlb $4, %xmm0, %xmm0
1088 eor v0.16b, v0.16b, v6.16b // xor with ivec
[all …]
H A Darm64cpuid.S30 aese v0.16b, v0.16b
44 sha256su0 v0.4s, v0.4s
51 pmull v0.1q, v0.1d, v0.1d
H A Dsha512-armv8.S1131 orr v26.16b,v0.16b,v0.16b // offload
1152 ext v6.16b,v0.16b,v4.16b,#8
1189 add v0.2d,v0.2d,v24.2d // "T1 + H + K512[i]"
1249 add v0.2d,v0.2d,v25.2d // "T1 + H + K512[i]"
1309 add v0.2d,v0.2d,v24.2d // "T1 + H + K512[i]"
1369 add v0.2d,v0.2d,v25.2d // "T1 + H + K512[i]"
1429 add v0.2d,v0.2d,v24.2d // "T1 + H + K512[i]"
1489 add v0.2d,v0.2d,v25.2d // "T1 + H + K512[i]"
1548 add v0.2d,v0.2d,v24.2d // "T1 + H + K512[i]"
1603 add v0.2d,v0.2d,v25.2d // "T1 + H + K512[i]"
[all …]
/f-stack/freebsd/sys/
H A Dktr.h141 ident, edat, (v0), (v1))
144 ident, edat, (v0), (v1), (v2))
146 a0, v0, a1, v1, a2, v2, a3, v3) \ argument
148 ident, edat, (v0), (v1), (v2), (v3))
161 state, a0, (v0), a1, (v1), a2, (v2))
194 a0, (v0), a1, (v1), a2, (v2))
214 a0, (v0), a1, (v1))
217 a0, (v0), a1, (v1), a2, (v2))
219 a0, v0, a1, v1, a2, v2, a3, v3) \ argument
234 a0, (v0), a1, (v1))
[all …]
/f-stack/freebsd/mips/mips/
H A Dsupport.S228 li v0, 0
246 li v0, 0
260 li v0, 0
328 li v0, 1
351 li v0, 1
396 li v0, -1
458 move a1, v0
484 and v0, v0, 3
491 move v0, v1 # init v0,v1 so unmodified bytes match
552 li v0, 1
[all …]
H A Dfp.S106 and v0, v0, 0xF << 2 # mask FMT field
1025 sltu v0, v0, v1 # compute carry
1032 sltu v0, v0, v1
1043 sltu v0, v0, v1
1113 subu v0, v0, 1 # are we done?
1213 subu v0, v0, 1 # are we done?
1341 subu v0, v0, t9
1349 subu v0, v0, t9
1423 subu v0, v0, t9
1431 subu v0, v0, t9
[all …]
H A Dswtch.S81 mfc0 v0, MIPS_COP_0_STATUS
82 and v0, ~(MIPS_SR_INT_IE)
83 mtc0 v0, MIPS_COP_0_STATUS # disable interrupts
100 RESTORE_U_PCB_REG(v0, V0, k1)
155 mfc0 v0, MIPS_COP_0_STATUS
163 SAVE_U_PCB_CONTEXT(v0, PCB_REG_SR, a0)
166 move v0, ra /* save 'ra' before we trash it */
171 move ra, v0 /* restore 'ra' before returning */
174 move v0, zero
662 li v0, SYS_sigreturn
[all …]
/f-stack/dpdk/lib/librte_eal/arm/include/
H A Drte_vect.h132 case 0: return vextq_u8(v0, v1, 0); in vextract()
133 case 1: return vextq_u8(v0, v1, 1); in vextract()
134 case 2: return vextq_u8(v0, v1, 2); in vextract()
135 case 3: return vextq_u8(v0, v1, 3); in vextract()
136 case 4: return vextq_u8(v0, v1, 4); in vextract()
137 case 5: return vextq_u8(v0, v1, 5); in vextract()
138 case 6: return vextq_u8(v0, v1, 6); in vextract()
139 case 7: return vextq_u8(v0, v1, 7); in vextract()
140 case 8: return vextq_u8(v0, v1, 8); in vextract()
141 case 9: return vextq_u8(v0, v1, 9); in vextract()
[all …]
/f-stack/freebsd/libkern/arm/
H A Dmuldi3.c118 #define v0 v.ul[L] in __muldi3() macro
140 prod.q = __lmulq(u0, v0); in __muldi3()
148 low.q = __lmulq(u0, v0); in __muldi3()
154 if (v0 >= v1) in __muldi3()
155 vdiff = v0 - v1; in __muldi3()
173 #undef v0 in __muldi3()
204 v0 = LHALF(v); in __lmulq()
206 low = u0 * v0; in __lmulq()
216 if (v0 >= v1) in __lmulq()
217 vdiff = v0 - v1; in __lmulq()
[all …]
/f-stack/app/redis-5.0.5/src/
H A Dsiphash.c102 v0 = ROTL(v0, 32); \
120 uint64_t v0 = 0x736f6d6570736575ULL; in siphash() local
133 v0 ^= k0; in siphash()
141 v0 ^= m; in siphash()
159 v0 ^= b; in siphash()
165 b = v0 ^ v1 ^ v2 ^ v3; in siphash()
180 uint64_t v0 = 0x736f6d6570736575ULL; in siphash_nocase() local
193 v0 ^= k0; in siphash_nocase()
201 v0 ^= m; in siphash_nocase()
219 v0 ^= b; in siphash_nocase()
[all …]
/f-stack/freebsd/contrib/libsodium/src/libsodium/crypto_shorthash/siphash24/ref/
H A Dshorthash_siphash_ref.h8 v0 += v1; \
10 v1 ^= v0; \
11 v0 = ROTL64(v0, 32); \
15 v0 += v3; \
17 v3 ^= v0; \
H A Dshorthash_siphashx24_ref.c9 uint64_t v0 = 0x736f6d6570736575ULL; in crypto_shorthash_siphashx24() local
24 v0 ^= k0; in crypto_shorthash_siphashx24()
30 v0 ^= m; in crypto_shorthash_siphashx24()
60 v0 ^= b; in crypto_shorthash_siphashx24()
66 b = v0 ^ v1 ^ v2 ^ v3; in crypto_shorthash_siphashx24()
73 b = v0 ^ v1 ^ v2 ^ v3; in crypto_shorthash_siphashx24()
H A Dshorthash_siphash24_ref.c10 uint64_t v0 = 0x736f6d6570736575ULL; in crypto_shorthash_siphash24() local
25 v0 ^= k0; in crypto_shorthash_siphash24()
31 v0 ^= m; in crypto_shorthash_siphash24()
61 v0 ^= b; in crypto_shorthash_siphash24()
67 b = v0 ^ v1 ^ v2 ^ v3; in crypto_shorthash_siphash24()
/f-stack/freebsd/mips/include/
H A Dcpufunc.h128 uint64_t v0; \
130 : [v0] "=&r"(v0)); \
132 return (v0); \
150 uint64_t v0; \
152 : [v0] "=&r"(v0)); \
154 return (v0); \
193 uint32_t v0; \
195 : [v0] "=&r"(v0)); \
197 return (v0); \
215 uint32_t v0; \
[all …]
/f-stack/dpdk/app/test-pmd/
H A Dmacswap_neon.h24 uint8x16_t v0, v1, v2, v3; in do_macswap() local
60 v0 = vld1q_u8((uint8_t const *)eth_hdr[0]); in do_macswap()
65 v0 = vqtbl1q_u8(v0, idx_map); in do_macswap()
70 vst1q_u8((uint8_t *)eth_hdr[0], v0); in do_macswap()
89 v0 = vld1q_u8((uint8_t const *)eth_hdr[0]); in do_macswap()
90 v0 = vqtbl1q_u8(v0, idx_map); in do_macswap()
91 vst1q_u8((uint8_t *)eth_hdr[0], v0); in do_macswap()
/f-stack/freebsd/mips/nlm/dev/net/ucore/
H A Dcrt0_basic.S46 la v0, _fbss
49 sw zero, 0(v0)
50 bltu v0,v1,3b
51 addiu v0,v0,4 # executed in delay slot
/f-stack/freebsd/mips/broadcom/
H A Dbcm_bmips_exts.h74 int v0; \
76 : [v0] "=&r"(v0)); \
78 return (v0); \
/f-stack/dpdk/lib/librte_eal/include/
H A Drte_reciprocal.h56 uint64_t u0, u1, v0, v1, k, t; in mullhi_u64()
61 v1 = y >> 32; v0 = y & 0xFFFFFFFF; in mullhi_u64()
63 t = u0*v0; in mullhi_u64()
66 t = u1*v0 + k; in mullhi_u64()
/f-stack/freebsd/mips/malta/
H A Dasm_malta.S52 mfc0 v0, $15, 1
54 andi v0, 0x1f
80 bne v0, t0, 1b
/f-stack/freebsd/contrib/openzfs/lib/libzpool/
H A Dutil.c49 vdev_stat_t *v0 = { 0 }; in show_vdev_stats() local
57 v0 = umem_zalloc(sizeof (*v0), UMEM_NOFAIL); in show_vdev_stats()
75 vs = v0; in show_vdev_stats()
108 umem_free(v0, sizeof (*v0)); in show_vdev_stats()
/f-stack/freebsd/contrib/libsodium/src/libsodium/crypto_pwhash/argon2/
H A Dblamka-round-ref.h27 #define BLAKE2_ROUND_NOMSG(v0, v1, v2, v3, v4, v5, v6, v7, v8, v9, v10, v11, \ argument
30 G(v0, v4, v8, v12); \
34 G(v0, v5, v10, v15); \
/f-stack/freebsd/contrib/zstd/
H A DCHANGELOG448 v0.8.0 (Aug 2, 2016)
461 v0.7.5 (Aug 1, 2016)
471 v0.7.3 (Jul 9, 2016)
483 v0.7.2 (Jul 4, 2016)
530 v0.5.0 (Feb 5, 2016)
555 v0.4.3 (Dec 7, 2015)
559 v0.4.2 (Dec 2, 2015)
563 v0.4.1 (Dec 1, 2015)
576 v0.3.5 (Nov 9, 2015)
579 v0.3.4 (Nov 6, 2015)
[all …]
/f-stack/freebsd/contrib/openzfs/module/icp/asm-x86_64/aes/
H A Daestab.h125 d_1(uint32_t, t_dec(i, n), isb_data, v0);
128 d_4(uint32_t, t_dec(i, n), isb_data, v0, v1, v2, v3);
155 d_1(uint32_t, t_dec(i, m), mm_data, v0);
158 d_4(uint32_t, t_dec(i, m), mm_data, v0, v1, v2, v3);

12345