Home
last modified time | relevance | path

Searched refs:ptype_tbl (Results 1 – 21 of 21) sorted by relevance

/dpdk/drivers/net/hns3/
H A Dhns3_rxtx.h293 struct hns3_ptype_table *ptype_tbl; member
637 const struct hns3_ptype_table * const ptype_tbl = rxq->ptype_tbl; in hns3_rx_calc_ptype() local
645 return ptype_tbl->ptype[ptype]; in hns3_rx_calc_ptype()
653 if (unlikely(ptype_tbl->ol4table[ol4id])) in hns3_rx_calc_ptype()
654 return ptype_tbl->inner_l3table[l3id] | in hns3_rx_calc_ptype()
655 ptype_tbl->inner_l4table[l4id] | in hns3_rx_calc_ptype()
656 ptype_tbl->ol3table[ol3id] | in hns3_rx_calc_ptype()
657 ptype_tbl->ol4table[ol4id]; in hns3_rx_calc_ptype()
659 return ptype_tbl->l3table[l3id] | ptype_tbl->l4table[l4id]; in hns3_rx_calc_ptype()
H A Dhns3_ethdev.h872 struct hns3_ptype_table ptype_tbl __rte_cache_aligned;
H A Dhns3_rxtx.c1862 rxq->ptype_tbl = &hns->ptype_tbl; in hns3_rx_queue_setup()
2286 struct hns3_ptype_table *tbl = &hns->ptype_tbl; in hns3_init_rx_ptype_tble()
/dpdk/drivers/net/i40e/
H A Di40e_rxtx_vec_altivec.c173 uint32_t *ptype_tbl) in desc_to_ptype_v() argument
182 ptype_tbl[(*(__vector unsigned char *)&ptype0)[0]]; in desc_to_ptype_v()
184 ptype_tbl[(*(__vector unsigned char *)&ptype0)[8]]; in desc_to_ptype_v()
186 ptype_tbl[(*(__vector unsigned char *)&ptype1)[0]]; in desc_to_ptype_v()
188 ptype_tbl[(*(__vector unsigned char *)&ptype1)[8]]; in desc_to_ptype_v()
208 uint32_t *ptype_tbl = rxq->vsi->adapter->ptype_tbl; in _recv_raw_pkts_vec() local
430 desc_to_ptype_v(descs, &rx_pkts[pos], ptype_tbl); in _recv_raw_pkts_vec()
H A Di40e_rxtx_vec_avx2.c117 const uint32_t *ptype_tbl = rxq->vsi->adapter->ptype_tbl; in _recv_raw_pkts_vec_avx2() local
348 mb6_7 = _mm256_insert_epi32(mb6_7, ptype_tbl[ptype7], 4); in _recv_raw_pkts_vec_avx2()
349 mb6_7 = _mm256_insert_epi32(mb6_7, ptype_tbl[ptype6], 0); in _recv_raw_pkts_vec_avx2()
350 mb4_5 = _mm256_insert_epi32(mb4_5, ptype_tbl[ptype5], 4); in _recv_raw_pkts_vec_avx2()
351 mb4_5 = _mm256_insert_epi32(mb4_5, ptype_tbl[ptype4], 0); in _recv_raw_pkts_vec_avx2()
375 mb2_3 = _mm256_insert_epi32(mb2_3, ptype_tbl[ptype3], 4); in _recv_raw_pkts_vec_avx2()
376 mb2_3 = _mm256_insert_epi32(mb2_3, ptype_tbl[ptype2], 0); in _recv_raw_pkts_vec_avx2()
377 mb0_1 = _mm256_insert_epi32(mb0_1, ptype_tbl[ptype1], 4); in _recv_raw_pkts_vec_avx2()
378 mb0_1 = _mm256_insert_epi32(mb0_1, ptype_tbl[ptype0], 0); in _recv_raw_pkts_vec_avx2()
H A Di40e_rxtx_vec_sse.c333 uint32_t *ptype_tbl) in desc_to_ptype_v() argument
341 rx_pkts[0]->packet_type = ptype_tbl[_mm_extract_epi8(ptype0, 0)]; in desc_to_ptype_v()
342 rx_pkts[1]->packet_type = ptype_tbl[_mm_extract_epi8(ptype0, 8)]; in desc_to_ptype_v()
343 rx_pkts[2]->packet_type = ptype_tbl[_mm_extract_epi8(ptype1, 0)]; in desc_to_ptype_v()
344 rx_pkts[3]->packet_type = ptype_tbl[_mm_extract_epi8(ptype1, 8)]; in desc_to_ptype_v()
364 uint32_t *ptype_tbl = rxq->vsi->adapter->ptype_tbl; in _recv_raw_pkts_vec() local
579 desc_to_ptype_v(descs, &rx_pkts[pos], ptype_tbl); in _recv_raw_pkts_vec()
H A Di40e_rxtx_vec_avx512.c241 const uint32_t *ptype_tbl = rxq->vsi->adapter->ptype_tbl; in _recv_raw_pkts_vec_avx512() local
486 (0, 0, 0, ptype_tbl[ptype7], in _recv_raw_pkts_vec_avx512()
487 0, 0, 0, ptype_tbl[ptype6], in _recv_raw_pkts_vec_avx512()
488 0, 0, 0, ptype_tbl[ptype5], in _recv_raw_pkts_vec_avx512()
489 0, 0, 0, ptype_tbl[ptype4]); in _recv_raw_pkts_vec_avx512()
491 (0, 0, 0, ptype_tbl[ptype3], in _recv_raw_pkts_vec_avx512()
492 0, 0, 0, ptype_tbl[ptype2], in _recv_raw_pkts_vec_avx512()
493 0, 0, 0, ptype_tbl[ptype1], in _recv_raw_pkts_vec_avx512()
494 0, 0, 0, ptype_tbl[ptype0]); in _recv_raw_pkts_vec_avx512()
H A Di40e_rxtx_vec_neon.c313 uint32_t *__rte_restrict ptype_tbl) in desc_to_ptype_v() argument
322 rx_pkts[i]->packet_type = ptype_tbl[ptype]; in desc_to_ptype_v()
343 uint32_t *ptype_tbl = rxq->vsi->adapter->ptype_tbl; in _recv_raw_pkts_vec() local
503 desc_to_ptype_v(descs, &rx_pkts[pos], ptype_tbl); in _recv_raw_pkts_vec()
H A Di40e_rxtx.c464 uint32_t *ptype_tbl = rxq->vsi->adapter->ptype_tbl; in i40e_rx_scan_hw_ring() local
524 ptype_tbl[(uint8_t)((qword1 & in i40e_rx_scan_hw_ring()
720 uint32_t *ptype_tbl; in i40e_recv_pkts() local
728 ptype_tbl = rxq->vsi->adapter->ptype_tbl; in i40e_recv_pkts()
794 ptype_tbl[(uint8_t)((qword1 & in i40e_recv_pkts()
850 uint32_t *ptype_tbl = rxq->vsi->adapter->ptype_tbl; in i40e_recv_scattered_pkts() local
968 ptype_tbl[(uint8_t)((qword1 & in i40e_recv_scattered_pkts()
3547 ad->ptype_tbl[i] = i40e_get_default_pkt_type(i); in i40e_set_default_ptype_table()
H A Drte_pmd_i40e.c2259 ad->ptype_tbl[i] = RTE_PTYPE_UNKNOWN; in rte_pmd_i40e_ptype_mapping_update()
2263 ad->ptype_tbl[mapping_items[i].hw_ptype] in rte_pmd_i40e_ptype_mapping_update()
2309 if (valid_only && ad->ptype_tbl[i] == RTE_PTYPE_UNKNOWN) in rte_pmd_i40e_ptype_mapping_get()
2312 mapping_items[n].sw_ptype = ad->ptype_tbl[i]; in rte_pmd_i40e_ptype_mapping_get()
2346 if ((target | ad->ptype_tbl[i]) == target && in rte_pmd_i40e_ptype_mapping_replace()
2347 (target & ad->ptype_tbl[i])) in rte_pmd_i40e_ptype_mapping_replace()
2348 ad->ptype_tbl[i] = pkt_type; in rte_pmd_i40e_ptype_mapping_replace()
2350 if (ad->ptype_tbl[i] == target) in rte_pmd_i40e_ptype_mapping_replace()
2351 ad->ptype_tbl[i] = pkt_type; in rte_pmd_i40e_ptype_mapping_replace()
H A Di40e_ethdev.h1243 uint32_t ptype_tbl[I40E_MAX_PKT_TYPE] __rte_cache_min_aligned; member
/dpdk/drivers/net/ice/
H A Dice_rxtx_vec_avx2.c46 const uint32_t *ptype_tbl = rxq->vsi->adapter->ptype_tbl; in _ice_recv_raw_pkts_vec_avx2() local
345 mb6_7 = _mm256_insert_epi32(mb6_7, ptype_tbl[ptype7], 4); in _ice_recv_raw_pkts_vec_avx2()
346 mb6_7 = _mm256_insert_epi32(mb6_7, ptype_tbl[ptype6], 0); in _ice_recv_raw_pkts_vec_avx2()
347 mb4_5 = _mm256_insert_epi32(mb4_5, ptype_tbl[ptype5], 4); in _ice_recv_raw_pkts_vec_avx2()
348 mb4_5 = _mm256_insert_epi32(mb4_5, ptype_tbl[ptype4], 0); in _ice_recv_raw_pkts_vec_avx2()
375 mb2_3 = _mm256_insert_epi32(mb2_3, ptype_tbl[ptype3], 4); in _ice_recv_raw_pkts_vec_avx2()
376 mb2_3 = _mm256_insert_epi32(mb2_3, ptype_tbl[ptype2], 0); in _ice_recv_raw_pkts_vec_avx2()
377 mb0_1 = _mm256_insert_epi32(mb0_1, ptype_tbl[ptype1], 4); in _ice_recv_raw_pkts_vec_avx2()
378 mb0_1 = _mm256_insert_epi32(mb0_1, ptype_tbl[ptype0], 0); in _ice_recv_raw_pkts_vec_avx2()
H A Dice_rxtx_vec_sse.c274 uint32_t *ptype_tbl) in ice_rx_desc_to_ptype_v() argument
286 rx_pkts[0]->packet_type = ptype_tbl[_mm_extract_epi16(ptype_all, 1)]; in ice_rx_desc_to_ptype_v()
287 rx_pkts[1]->packet_type = ptype_tbl[_mm_extract_epi16(ptype_all, 3)]; in ice_rx_desc_to_ptype_v()
288 rx_pkts[2]->packet_type = ptype_tbl[_mm_extract_epi16(ptype_all, 5)]; in ice_rx_desc_to_ptype_v()
289 rx_pkts[3]->packet_type = ptype_tbl[_mm_extract_epi16(ptype_all, 7)]; in ice_rx_desc_to_ptype_v()
308 uint32_t *ptype_tbl = rxq->vsi->adapter->ptype_tbl; in _ice_recv_raw_pkts_vec() local
568 ice_rx_desc_to_ptype_v(descs, &rx_pkts[pos], ptype_tbl); in _ice_recv_raw_pkts_vec()
H A Dice_rxtx_vec_avx512.c161 const uint32_t *ptype_tbl = rxq->vsi->adapter->ptype_tbl; in _ice_recv_raw_pkts_vec_avx512() local
460 (0, 0, 0, ptype_tbl[ptype7], in _ice_recv_raw_pkts_vec_avx512()
461 0, 0, 0, ptype_tbl[ptype6], in _ice_recv_raw_pkts_vec_avx512()
462 0, 0, 0, ptype_tbl[ptype5], in _ice_recv_raw_pkts_vec_avx512()
463 0, 0, 0, ptype_tbl[ptype4]); in _ice_recv_raw_pkts_vec_avx512()
465 (0, 0, 0, ptype_tbl[ptype3], in _ice_recv_raw_pkts_vec_avx512()
466 0, 0, 0, ptype_tbl[ptype2], in _ice_recv_raw_pkts_vec_avx512()
467 0, 0, 0, ptype_tbl[ptype1], in _ice_recv_raw_pkts_vec_avx512()
468 0, 0, 0, ptype_tbl[ptype0]); in _ice_recv_raw_pkts_vec_avx512()
H A Dice_rxtx.c1575 uint32_t *ptype_tbl = rxq->vsi->adapter->ptype_tbl; in ice_rx_scan_hw_ring() local
1629 mb->packet_type = ptype_tbl[ICE_RX_FLEX_DESC_PTYPE_M & in ice_rx_scan_hw_ring()
1851 uint32_t *ptype_tbl = rxq->vsi->adapter->ptype_tbl; in ice_recv_scattered_pkts() local
1971 first_seg->packet_type = ptype_tbl[ICE_RX_FLEX_DESC_PTYPE_M & in ice_recv_scattered_pkts()
2361 uint32_t *ptype_tbl = rxq->vsi->adapter->ptype_tbl; in ice_recv_pkts() local
2422 rxm->packet_type = ptype_tbl[ICE_RX_FLEX_DESC_PTYPE_M & in ice_recv_pkts()
4228 ad->ptype_tbl[i] = ice_get_default_pkt_type(i); in ice_set_default_ptype_table()
H A Dice_ethdev.h546 uint32_t ptype_tbl[ICE_MAX_PKT_TYPE] __rte_cache_min_aligned; member
/dpdk/drivers/net/iavf/
H A Diavf_rxtx.c1316 const uint32_t *ptype_tbl; in iavf_recv_pkts() local
1323 ptype_tbl = rxq->vsi->adapter->ptype_tbl; in iavf_recv_pkts()
1384 ptype_tbl[(uint8_t)((qword1 & in iavf_recv_pkts()
1424 const uint32_t *ptype_tbl; in iavf_recv_pkts_flex_rxd() local
1431 ptype_tbl = rxq->vsi->adapter->ptype_tbl; in iavf_recv_pkts_flex_rxd()
1553 const uint32_t *ptype_tbl = rxq->vsi->adapter->ptype_tbl; in iavf_recv_scattered_pkts_flex_rxd() local
1729 const uint32_t *ptype_tbl = rxq->vsi->adapter->ptype_tbl; in iavf_recv_scattered_pkts() local
1839 ptype_tbl[(uint8_t)((qword1 & in iavf_recv_scattered_pkts()
1883 const uint32_t *ptype_tbl = rxq->vsi->adapter->ptype_tbl; in iavf_rx_scan_hw_ring_flex_rxd() local
2014 const uint32_t *ptype_tbl = rxq->vsi->adapter->ptype_tbl; in iavf_rx_scan_hw_ring() local
[all …]
H A Diavf_rxtx_vec_sse.c401 const uint32_t *ptype_tbl = rxq->vsi->adapter->ptype_tbl; in _recv_raw_pkts_vec() local
615 desc_to_ptype_v(descs, &rx_pkts[pos], ptype_tbl); in _recv_raw_pkts_vec()
651 const uint32_t *ptype_tbl = adapter->ptype_tbl; in _recv_raw_pkts_vec_flex_rxd() local
910 flex_desc_to_ptype_v(descs, &rx_pkts[pos], ptype_tbl); in _recv_raw_pkts_vec_flex_rxd()
H A Diavf.h313 uint32_t ptype_tbl[IAVF_MAX_PKT_TYPE] __rte_cache_min_aligned; member
H A Diavf_rxtx_vec_avx2.c29 const uint32_t *type_table = rxq->vsi->adapter->ptype_tbl; in _iavf_recv_raw_pkts_vec_avx2()
530 const uint32_t *type_table = adapter->ptype_tbl; in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
H A Diavf_rxtx_vec_avx512.c170 const uint32_t *type_table = rxq->vsi->adapter->ptype_tbl; in _iavf_recv_raw_pkts_vec_avx512()
718 const uint32_t *type_table = adapter->ptype_tbl; in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()