| /f-stack/dpdk/lib/librte_net/ |
| H A D | net_crc_avx512.c | 144 barrett_reduction(__m128i data64, const struct crc_vpclmulqdq_ctx *params) in barrett_reduction() argument
148 data64 = _mm_and_si128(data64, *(const __m128i *)mask2); in barrett_reduction()
149 tmp0 = data64; in barrett_reduction()
150 tmp1 = data64; in barrett_reduction()
152 data64 = _mm_clmulepi64_si128(tmp0, params->rk7_rk8, 0x0); in barrett_reduction()
153 data64 = _mm_ternarylogic_epi64(data64, tmp1, *(const __m128i *)mask, in barrett_reduction()
156 tmp1 = data64; in barrett_reduction()
157 data64 = _mm_clmulepi64_si128(data64, params->rk7_rk8, 0x10); in barrett_reduction()
158 data64 = _mm_ternarylogic_epi64(data64, tmp1, tmp0, 0x96); in barrett_reduction()
160 return _mm_extract_epi32(data64, 2); in barrett_reduction()
|
| H A D | net_crc_sse.c | 98 crcr32_reduce_64_to_32(__m128i data64, __m128i precomp) in crcr32_reduce_64_to_32() argument
109 tmp0 = _mm_and_si128(data64, _mm_load_si128((const __m128i *)mask2)); in crcr32_reduce_64_to_32()
|
| H A D | net_crc_neon.c | 96 crcr32_reduce_64_to_32(uint64x2_t data64, in crcr32_reduce_64_to_32() argument
107 tmp0 = vandq_u64(data64, vld1q_u64((uint64_t *)mask2)); in crcr32_reduce_64_to_32()
|
| /f-stack/freebsd/contrib/openzfs/module/icp/algs/edonr/ |
| H A D | edonr.c | 502 uint64_t *data64; in EdonRUpdate() local
560 data64 = (uint64_t *)data; in EdonRUpdate()
584 uint64_t *data64, num_bits; in EdonRFinal() local
609 st_swap64(num_bits, data64 + 7); in EdonRFinal()
611 data64[7] = num_bits; in EdonRFinal()
619 st_swap64(num_bits, data64 + 15); in EdonRFinal()
621 data64[15] = num_bits; in EdonRFinal()
648 st_swap64(num_bits, data64 + 15); in EdonRFinal()
650 data64[15] = num_bits; in EdonRFinal()
658 st_swap64(num_bits, data64 + 31); in EdonRFinal()
[all …]
|
| /f-stack/freebsd/mips/cavium/cryptocteon/ |
| H A D | cavium_crypto.c | 574 uint64_t data64[1]; in octo_aes_cbc_sha1_encrypt() member
576 uint64_t *pdata = &mydata[0].data64[0]; in octo_aes_cbc_sha1_encrypt()
577 uint64_t *data = &mydata[1].data64[0]; in octo_aes_cbc_sha1_encrypt()
765 uint64_t data64[1]; in octo_aes_cbc_sha1_decrypt() member
767 uint64_t *pdata = &mydata[0].data64[0]; in octo_aes_cbc_sha1_decrypt()
768 uint64_t *data = &mydata[1].data64[0]; in octo_aes_cbc_sha1_decrypt()
|
| /f-stack/freebsd/amd64/vmm/io/ |
| H A D | vioapic.c | 311 uint64_t data64, mask64; in vioapic_write() local
340 data64 = (uint64_t)data << lshift; in vioapic_write()
343 vioapic->rtbl[pin].reg |= data64 & ~RTBL_RO_BITS; in vioapic_write()
|
| /f-stack/dpdk/app/test/ |
| H A D | test_hash.c | 166 uint64_t data64[CRC32_DWORDS]; in test_crc32_hash_alg_equiv() local
173 data_len = (size_t) ((rte_rand() % sizeof(data64)) + 1); in test_crc32_hash_alg_equiv()
178 data64[j] = rte_rand(); in test_crc32_hash_alg_equiv()
182 hash_val = rte_hash_crc(data64, data_len, init_val); in test_crc32_hash_alg_equiv()
186 if (hash_val != rte_hash_crc(data64, data_len, init_val)) { in test_crc32_hash_alg_equiv()
193 if (hash_val != rte_hash_crc(data64, data_len, init_val)) { in test_crc32_hash_alg_equiv()
200 if (hash_val != rte_hash_crc(data64, data_len, init_val)) { in test_crc32_hash_alg_equiv()
214 printf("%02X%c", ((uint8_t *)data64)[j], in test_crc32_hash_alg_equiv()
|
| /f-stack/freebsd/contrib/octeon-sdk/ |
| H A D | cvmx-interrupt.c | 105 #define HI32(data64) ((uint32_t)(data64 >> 32)) argument
106 #define LO32(data64) ((uint32_t)(data64 & 0xFFFFFFFF)) argument
|
| /f-stack/dpdk/drivers/net/bnx2x/ |
| H A D | ecore_init_ops.h | 73 uint64_t data64 = 0; in ecore_init_wr_64() local
77 data64 = HILO_U64((*(data + 1)), (*data)); in ecore_init_wr_64()
83 *pdata = data64; in ecore_init_wr_64()
|