Searched refs:tmp0 (Results 1 – 5 of 5) sorted by relevance
| /dpdk/lib/net/ |
| 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_sse.c | 49 __m128i tmp0 = _mm_clmulepi64_si128(fold, precomp, 0x01); in crcr32_folding_round() local
52 return _mm_xor_si128(tmp1, _mm_xor_si128(data_block, tmp0)); in crcr32_folding_round()
70 __m128i tmp0, tmp1, tmp2; in crcr32_reduce_128_to_64() local
73 tmp0 = _mm_clmulepi64_si128(data128, precomp, 0x00); in crcr32_reduce_128_to_64()
75 tmp0 = _mm_xor_si128(tmp0, tmp1); in crcr32_reduce_128_to_64()
78 tmp2 = _mm_slli_si128(tmp0, 4); in crcr32_reduce_128_to_64()
81 return _mm_xor_si128(tmp1, tmp0); in crcr32_reduce_128_to_64()
106 __m128i tmp0, tmp1, tmp2; in crcr32_reduce_64_to_32() local
110 tmp1 = _mm_clmulepi64_si128(tmp0, precomp, 0x00); in crcr32_reduce_64_to_32()
111 tmp1 = _mm_xor_si128(tmp1, tmp0); in crcr32_reduce_64_to_32()
[all …]
|
| H A D | net_crc_avx512.c | 51 __m512i tmp0, tmp1; in crcr32_folding_round() local
53 tmp0 = _mm512_clmulepi64_epi128(fold, precomp, 0x01); in crcr32_folding_round()
65 __m512i tmp0, tmp1, tmp2, tmp3; in crc32_fold_128() local
77 tmp0 = _mm512_ternarylogic_epi64(tmp0, tmp1, tmp2, 0x96); in crc32_fold_128()
78 tmp0 = _mm512_ternarylogic_epi64(tmp0, tmp3, tmp4, 0x96); in crc32_fold_128()
80 tmp1 = _mm512_shuffle_i64x2(tmp0, tmp0, 0x4e); in crc32_fold_128()
82 a = _mm256_xor_si256(*(__m256i *)&tmp1, *(__m256i *)&tmp0); in crc32_fold_128()
143 __m128i tmp0, tmp1; in barrett_reduction() local
146 tmp0 = data64; in barrett_reduction()
149 data64 = _mm_clmulepi64_si128(tmp0, params->rk7_rk8, 0x0); in barrett_reduction()
[all …]
|
| /dpdk/drivers/net/bnxt/ |
| H A D | bnxt_rxtx_vec_sse.c | 208 __m128i tmp0, tmp1, info3_v; in recv_burst_vec_sse() local
212 tmp0 = _mm_loadu_si128((void *)&rxr->rx_buf_ring[mbcons]); in recv_burst_vec_sse()
216 _mm_storeu_si128((void *)&rx_pkts[i], tmp0); in recv_burst_vec_sse()
249 tmp0 = _mm_unpackhi_epi32(rxcmp1[0], rxcmp1[1]); in recv_burst_vec_sse()
252 info3_v = _mm_and_si128(_mm_unpacklo_epi64(tmp0, tmp1), in recv_burst_vec_sse()
|
| /dpdk/lib/eal/arm/include/ |
| H A D | rte_pause_64.h | 101 : [tmp0] "=&r" (dst_128->val[0]), \
107 : [tmp0] "=&r" (dst_128->val[0]), \
|