Searched refs:mb4_5 (Results 1 – 5 of 5) sorted by relevance
| /f-stack/dpdk/drivers/net/iavf/ |
| H A D | iavf_rxtx_vec_avx2.c | 388 __m256i mb4_5 = _mm256_shuffle_epi8(desc4_5, shuf_msk); in _iavf_recv_raw_pkts_vec_avx2() local 391 mb4_5 = _mm256_add_epi16(mb4_5, crc_adjust); in _iavf_recv_raw_pkts_vec_avx2() 405 mb4_5 = _mm256_insert_epi32(mb4_5, type_table[ptype5], 4); in _iavf_recv_raw_pkts_vec_avx2() 406 mb4_5 = _mm256_insert_epi32(mb4_5, type_table[ptype4], 0); in _iavf_recv_raw_pkts_vec_avx2() 508 rearm4 = _mm256_permute2f128_si256(rearm4, mb4_5, 0x20); in _iavf_recv_raw_pkts_vec_avx2() 537 rearm5 = _mm256_blend_epi32(rearm5, mb4_5, 0xF0); in _iavf_recv_raw_pkts_vec_avx2() 866 mb4_5 = _mm256_add_epi16(mb4_5, crc_adjust); in _iavf_recv_raw_pkts_vec_avx2_flex_rxd() 884 mb4_5 = _mm256_insert_epi32(mb4_5, type_table[ptype5], 4); in _iavf_recv_raw_pkts_vec_avx2_flex_rxd() 885 mb4_5 = _mm256_insert_epi32(mb4_5, type_table[ptype4], 0); in _iavf_recv_raw_pkts_vec_avx2_flex_rxd() 1078 mb4_5 = _mm256_or_si256(mb4_5, rss_hash4_5); in _iavf_recv_raw_pkts_vec_avx2_flex_rxd() [all …]
|
| H A D | iavf_rxtx_vec_avx512.c | 491 const __m256i mb4_5 = _mm512_extracti64x4_epi64(mb4_7, 0); in _iavf_recv_raw_pkts_vec_avx512() local 508 rearm4 = _mm256_permute2f128_si256(rearm4, mb4_5, 0x20); in _iavf_recv_raw_pkts_vec_avx512() 537 rearm5 = _mm256_blend_epi32(rearm5, mb4_5, 0xF0); in _iavf_recv_raw_pkts_vec_avx512() 1004 __m256i mb4_5 = _mm512_extracti64x4_epi64(mb4_7, 0); in _iavf_recv_raw_pkts_vec_avx512_flex_rxd() local 1093 mb4_5 = _mm256_or_si256(mb4_5, rss_hash4_5); in _iavf_recv_raw_pkts_vec_avx512_flex_rxd() 1132 rearm4 = _mm256_permute2f128_si256(rearm4, mb4_5, 0x20); in _iavf_recv_raw_pkts_vec_avx512_flex_rxd() 1161 rearm5 = _mm256_blend_epi32(rearm5, mb4_5, 0xF0); in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
|
| /f-stack/dpdk/drivers/net/i40e/ |
| H A D | i40e_rxtx_vec_avx2.c | 439 __m256i mb4_5 = _mm256_shuffle_epi8(desc4_5, shuf_msk); in _recv_raw_pkts_vec_avx2() local 441 mb4_5 = _mm256_add_epi16(mb4_5, crc_adjust); in _recv_raw_pkts_vec_avx2() 454 mb4_5 = _mm256_insert_epi32(mb4_5, ptype_tbl[ptype5], 4); in _recv_raw_pkts_vec_avx2() 455 mb4_5 = _mm256_insert_epi32(mb4_5, ptype_tbl[ptype4], 0); in _recv_raw_pkts_vec_avx2() 584 __m256i fdir_mb4_5 = _mm256_and_si256(mb4_5, tmp4_5); in _recv_raw_pkts_vec_avx2() 587 mb4_5 = _mm256_andnot_si256(tmp4_5, mb4_5); in _recv_raw_pkts_vec_avx2() 646 rearm4 = _mm256_permute2f128_si256(rearm4, mb4_5, 0x20); in _recv_raw_pkts_vec_avx2() 664 rearm5 = _mm256_blend_epi32(rearm5, mb4_5, 0xF0); in _recv_raw_pkts_vec_avx2()
|
| /f-stack/dpdk/drivers/net/ice/ |
| H A D | ice_rxtx_vec_avx2.c | 395 __m256i mb4_5 = _mm256_shuffle_epi8(raw_desc4_5, shuf_msk); in _ice_recv_raw_pkts_vec_avx2() local 398 mb4_5 = _mm256_add_epi16(mb4_5, crc_adjust); in _ice_recv_raw_pkts_vec_avx2() 416 mb4_5 = _mm256_insert_epi32(mb4_5, ptype_tbl[ptype5], 4); in _ice_recv_raw_pkts_vec_avx2() 417 mb4_5 = _mm256_insert_epi32(mb4_5, ptype_tbl[ptype4], 0); in _ice_recv_raw_pkts_vec_avx2() 610 mb4_5 = _mm256_or_si256(mb4_5, rss_hash4_5); in _ice_recv_raw_pkts_vec_avx2() 649 rearm4 = _mm256_permute2f128_si256(rearm4, mb4_5, 0x20); in _ice_recv_raw_pkts_vec_avx2() 678 rearm5 = _mm256_blend_epi32(rearm5, mb4_5, 0xF0); in _ice_recv_raw_pkts_vec_avx2()
|
| H A D | ice_rxtx_vec_avx512.c | 421 __m256i mb4_5 = _mm512_extracti64x4_epi64(mb4_7, 0); in _ice_recv_raw_pkts_vec_avx512() local 593 mb4_5 = _mm256_or_si256(mb4_5, rss_hash4_5); in _ice_recv_raw_pkts_vec_avx512() 634 rearm4 = _mm256_permute2f128_si256(rearm4, mb4_5, 0x20); in _ice_recv_raw_pkts_vec_avx512() 665 rearm5 = _mm256_blend_epi32(rearm5, mb4_5, 0xF0); in _ice_recv_raw_pkts_vec_avx512()
|