| /f-stack/dpdk/lib/librte_net/ |
| H A D | net_crc_sse.c | 50 __m128i tmp0 = _mm_clmulepi64_si128(fold, precomp, 0x01); in crcr32_folding_round() local
53 return _mm_xor_si128(tmp1, _mm_xor_si128(data_block, tmp0)); in crcr32_folding_round()
71 __m128i tmp0, tmp1, tmp2; in crcr32_reduce_128_to_64() local
74 tmp0 = _mm_clmulepi64_si128(data128, precomp, 0x00); in crcr32_reduce_128_to_64()
76 tmp0 = _mm_xor_si128(tmp0, tmp1); in crcr32_reduce_128_to_64()
79 tmp2 = _mm_slli_si128(tmp0, 4); in crcr32_reduce_128_to_64()
82 return _mm_xor_si128(tmp1, tmp0); in crcr32_reduce_128_to_64()
107 __m128i tmp0, tmp1, tmp2; in crcr32_reduce_64_to_32() local
111 tmp1 = _mm_clmulepi64_si128(tmp0, precomp, 0x00); in crcr32_reduce_64_to_32()
112 tmp1 = _mm_xor_si128(tmp1, tmp0); in crcr32_reduce_64_to_32()
[all …]
|
| H A D | net_crc_neon.c | 46 uint64x2_t tmp0 = vreinterpretq_u64_p128(vmull_p64( in crcr32_folding_round() local
54 return veorq_u64(tmp1, veorq_u64(data_block, tmp0)); in crcr32_folding_round()
69 uint64x2_t tmp0, tmp1, tmp2; in crcr32_reduce_128_to_64() local
72 tmp0 = vreinterpretq_u64_p128(vmull_p64( in crcr32_reduce_128_to_64()
76 tmp0 = veorq_u64(tmp0, tmp1); in crcr32_reduce_128_to_64()
79 tmp2 = vshift_bytes_left(tmp0, 4); in crcr32_reduce_128_to_64()
84 return veorq_u64(tmp1, tmp0); in crcr32_reduce_128_to_64()
105 uint64x2_t tmp0, tmp1, tmp2; in crcr32_reduce_64_to_32() local
110 vgetq_lane_p64(vreinterpretq_p64_u64(tmp0), 0), in crcr32_reduce_64_to_32()
112 tmp1 = veorq_u64(tmp1, tmp0); in crcr32_reduce_64_to_32()
[all …]
|
| H A D | net_crc_avx512.c | 54 __m512i tmp0, tmp1; in crcr32_folding_round() local
56 tmp0 = _mm512_clmulepi64_epi128(fold, precomp, 0x01); in crcr32_folding_round()
68 __m512i tmp0, tmp1, tmp2, tmp3; in crc32_fold_128() local
80 tmp0 = _mm512_ternarylogic_epi64(tmp0, tmp1, tmp2, 0x96); in crc32_fold_128()
81 tmp0 = _mm512_ternarylogic_epi64(tmp0, tmp3, tmp4, 0x96); in crc32_fold_128()
83 tmp1 = _mm512_shuffle_i64x2(tmp0, tmp0, 0x4e); in crc32_fold_128()
85 a = _mm256_xor_si256(*(__m256i *)&tmp1, *(__m256i *)&tmp0); in crc32_fold_128()
146 __m128i tmp0, tmp1; in barrett_reduction() local
149 tmp0 = data64; in barrett_reduction()
152 data64 = _mm_clmulepi64_si128(tmp0, params->rk7_rk8, 0x0); in barrett_reduction()
[all …]
|
| /f-stack/freebsd/contrib/libsodium/src/libsodium/crypto_scalarmult/curve25519/ref10/ |
| H A D | x25519_ref10.c | 63 fe25519 tmp0; in crypto_scalarmult_curve25519_ref10() local
92 fe25519_sub(tmp0, x3, z3); in crypto_scalarmult_curve25519_ref10()
96 fe25519_mul(z3, tmp0, x2); in crypto_scalarmult_curve25519_ref10()
98 fe25519_sq(tmp0, tmp1); in crypto_scalarmult_curve25519_ref10()
102 fe25519_mul(x2, tmp1, tmp0); in crypto_scalarmult_curve25519_ref10()
103 fe25519_sub(tmp1, tmp1, tmp0); in crypto_scalarmult_curve25519_ref10()
107 fe25519_add(tmp0, tmp0, z3); in crypto_scalarmult_curve25519_ref10()
109 fe25519_mul(z2, tmp1, tmp0); in crypto_scalarmult_curve25519_ref10()
|
| /f-stack/freebsd/crypto/aesni/ |
| H A D | aesni_ghash.c | 169 __m128i tmp0, tmp1, tmp2, tmp3; in reduce4() local
193 tmp0 = _mm_xor_si128(tmp0, H1); in reduce4()
208 tmp0 = _mm_clmulepi64_si128(tmp0, tmp4, 0x00); in reduce4()
213 tmp0 = _mm_xor_si128(tmp0, lo); in reduce4()
214 tmp0 = _mm_xor_si128(tmp0, hi); in reduce4()
215 tmp0 = _mm_xor_si128(tmp1, tmp0); in reduce4()
216 tmp0 = _mm_xor_si128(tmp2, tmp0); in reduce4()
217 tmp0 = _mm_xor_si128(tmp3, tmp0); in reduce4()
219 tmp4 = _mm_slli_si128(tmp0, 8); in reduce4()
220 tmp0 = _mm_srli_si128(tmp0, 8); in reduce4()
[all …]
|
| /f-stack/freebsd/contrib/ncsw/Peripherals/FM/MAC/ |
| H A D | fman_tgec.c | 39 uint32_t tmp0, tmp1; in fman_tgec_set_mac_address() local
41 tmp0 = (uint32_t)(adr[0] | in fman_tgec_set_mac_address()
46 iowrite32be(tmp0, ®s->mac_addr_0); in fman_tgec_set_mac_address()
257 uint32_t tmp0, tmp1; in fman_tgec_add_addr_in_paddr() local
259 tmp0 = (uint32_t)(adr[0] | in fman_tgec_add_addr_in_paddr()
264 iowrite32be(tmp0, ®s->mac_addr_2); in fman_tgec_add_addr_in_paddr()
|
| H A D | fman_memac.c | 82 uint32_t tmp0, tmp1; in fman_memac_add_addr_in_paddr() local
84 tmp0 = (uint32_t)(adr[0] | in fman_memac_add_addr_in_paddr()
91 iowrite32be(tmp0, ®s->mac_addr0.mac_addr_l); in fman_memac_add_addr_in_paddr()
94 iowrite32be(tmp0, ®s->mac_addr[paddr_num-1].mac_addr_l); in fman_memac_add_addr_in_paddr()
|
| /f-stack/freebsd/contrib/libsodium/src/libsodium/crypto_aead/aes256gcm/aesni/ |
| H A D | aead_aes256gcm_aesni.c | 369 tmp0 = _mm_xor_si128(tmp0, lo); \
370 tmp0 = _mm_xor_si128(tmp0, hi); \
371 tmp0 = _mm_xor_si128(tmp1, tmp0); \
372 tmp0 = _mm_xor_si128(tmp2, tmp0); \
373 tmp0 = _mm_xor_si128(tmp3, tmp0);\
376 tmp0B = _mm_slli_si128(tmp0, 8); \
377 tmp0 = _mm_srli_si128(tmp0, 8); \
379 hi = _mm_xor_si128(tmp0, hi); \
|
| /f-stack/dpdk/drivers/net/bnxt/ |
| H A D | bnxt_rxtx_vec_sse.c | 198 __m128i tmp0, tmp1, info3_v; in bnxt_recv_pkts_vec() local
202 tmp0 = _mm_loadu_si128((void *)&rxr->rx_buf_ring[mbcons]); in bnxt_recv_pkts_vec()
206 _mm_storeu_si128((void *)&rx_pkts[i], tmp0); in bnxt_recv_pkts_vec()
239 tmp0 = _mm_unpackhi_epi32(rxcmp1[0], rxcmp1[1]); in bnxt_recv_pkts_vec()
242 info3_v = _mm_and_si128(_mm_unpacklo_epi64(tmp0, tmp1), in bnxt_recv_pkts_vec()
|
| /f-stack/freebsd/crypto/openssl/arm/ |
| H A D | ecp_nistz256-armv4.S | 3664 bl __ecp_nistz256_mul_mont @ p256_mul_mont(tmp0, in_z, in_y);
3668 bl __ecp_nistz256_add_self @ p256_mul_by_2(res_z, tmp0);
3683 bl __ecp_nistz256_mul_mont @ p256_sqr_mont(tmp0, S);
3693 bl __ecp_nistz256_div_by_2 @ p256_div_by_2(res_y, tmp0);
3705 bl __ecp_nistz256_add_self @ p256_mul_by_2(tmp0, S);
3713 bl __ecp_nistz256_sub_from @ p256_sub(res_x, res_x, tmp0);
|