Home
last modified time | relevance | path

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

/f-stack/dpdk/drivers/net/hns3/
H A Dhns3_rxtx.h273 struct hns3_ptype_table *ptype_tbl; member
582 const struct hns3_ptype_table * const ptype_tbl = rxq->ptype_tbl; in hns3_rx_calc_ptype() local
593 if (unlikely(ptype_tbl->ol4table[ol4id])) in hns3_rx_calc_ptype()
594 return ptype_tbl->inner_l2table[l2id] | in hns3_rx_calc_ptype()
595 ptype_tbl->inner_l3table[l3id] | in hns3_rx_calc_ptype()
596 ptype_tbl->inner_l4table[l4id] | in hns3_rx_calc_ptype()
597 ptype_tbl->ol3table[ol3id] | in hns3_rx_calc_ptype()
598 ptype_tbl->ol4table[ol4id] | ptype_tbl->ol2table[ol2id]; in hns3_rx_calc_ptype()
600 return ptype_tbl->l2l3table[l2id][l3id] | in hns3_rx_calc_ptype()
601 ptype_tbl->l4table[l4id]; in hns3_rx_calc_ptype()
H A Dhns3_ethdev.h751 struct hns3_ptype_table ptype_tbl __rte_cache_min_aligned;
H A Dhns3_rxtx.c1745 rxq->ptype_tbl = &hns->ptype_tbl; in hns3_rx_queue_setup()
1979 struct hns3_ptype_table *tbl = &hns->ptype_tbl; in hns3_init_rx_ptype_tble()
/f-stack/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_sse.c331 uint32_t *ptype_tbl) in desc_to_ptype_v() argument
339 rx_pkts[0]->packet_type = ptype_tbl[_mm_extract_epi8(ptype0, 0)]; in desc_to_ptype_v()
340 rx_pkts[1]->packet_type = ptype_tbl[_mm_extract_epi8(ptype0, 8)]; in desc_to_ptype_v()
341 rx_pkts[2]->packet_type = ptype_tbl[_mm_extract_epi8(ptype1, 0)]; in desc_to_ptype_v()
342 rx_pkts[3]->packet_type = ptype_tbl[_mm_extract_epi8(ptype1, 8)]; in desc_to_ptype_v()
362 uint32_t *ptype_tbl = rxq->vsi->adapter->ptype_tbl; in _recv_raw_pkts_vec() local
577 desc_to_ptype_v(descs, &rx_pkts[pos], ptype_tbl); in _recv_raw_pkts_vec()
H A Di40e_rxtx_vec_avx2.c229 const uint32_t *ptype_tbl = rxq->vsi->adapter->ptype_tbl; in _recv_raw_pkts_vec_avx2() local
452 mb6_7 = _mm256_insert_epi32(mb6_7, ptype_tbl[ptype7], 4); in _recv_raw_pkts_vec_avx2()
453 mb6_7 = _mm256_insert_epi32(mb6_7, ptype_tbl[ptype6], 0); 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()
479 mb2_3 = _mm256_insert_epi32(mb2_3, ptype_tbl[ptype3], 4); in _recv_raw_pkts_vec_avx2()
480 mb2_3 = _mm256_insert_epi32(mb2_3, ptype_tbl[ptype2], 0); in _recv_raw_pkts_vec_avx2()
481 mb0_1 = _mm256_insert_epi32(mb0_1, ptype_tbl[ptype1], 4); in _recv_raw_pkts_vec_avx2()
482 mb0_1 = _mm256_insert_epi32(mb0_1, ptype_tbl[ptype0], 0); in _recv_raw_pkts_vec_avx2()
H A Di40e_rxtx_vec_neon.c176 uint32_t *__rte_restrict ptype_tbl) in desc_to_ptype_v() argument
185 rx_pkts[i]->packet_type = ptype_tbl[ptype]; in desc_to_ptype_v()
206 uint32_t *ptype_tbl = rxq->vsi->adapter->ptype_tbl; in _recv_raw_pkts_vec() local
409 desc_to_ptype_v(descs, &rx_pkts[pos], ptype_tbl); in _recv_raw_pkts_vec()
H A Di40e_rxtx.c424 uint32_t *ptype_tbl = rxq->vsi->adapter->ptype_tbl; in i40e_rx_scan_hw_ring() local
473 ptype_tbl[(uint8_t)((qword1 & in i40e_rx_scan_hw_ring()
669 uint32_t *ptype_tbl; in i40e_recv_pkts() local
677 ptype_tbl = rxq->vsi->adapter->ptype_tbl; in i40e_recv_pkts()
737 ptype_tbl[(uint8_t)((qword1 & in i40e_recv_pkts()
793 uint32_t *ptype_tbl = rxq->vsi->adapter->ptype_tbl; in i40e_recv_scattered_pkts() local
905 ptype_tbl[(uint8_t)((qword1 & in i40e_recv_scattered_pkts()
3385 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.h1282 uint32_t ptype_tbl[I40E_MAX_PKT_TYPE] __rte_cache_min_aligned; member
/f-stack/dpdk/drivers/net/ice/
H A Dice_rxtx_vec_sse.c238 uint32_t *ptype_tbl) in ice_rx_desc_to_ptype_v() argument
250 rx_pkts[0]->packet_type = ptype_tbl[_mm_extract_epi16(ptype_all, 1)]; in ice_rx_desc_to_ptype_v()
251 rx_pkts[1]->packet_type = ptype_tbl[_mm_extract_epi16(ptype_all, 3)]; in ice_rx_desc_to_ptype_v()
252 rx_pkts[2]->packet_type = ptype_tbl[_mm_extract_epi16(ptype_all, 5)]; in ice_rx_desc_to_ptype_v()
253 rx_pkts[3]->packet_type = ptype_tbl[_mm_extract_epi16(ptype_all, 7)]; in ice_rx_desc_to_ptype_v()
272 uint32_t *ptype_tbl = rxq->vsi->adapter->ptype_tbl; in _ice_recv_raw_pkts_vec() local
532 ice_rx_desc_to_ptype_v(descs, &rx_pkts[pos], ptype_tbl); in _ice_recv_raw_pkts_vec()
H A Dice_rxtx_vec_avx2.c160 const uint32_t *ptype_tbl = rxq->vsi->adapter->ptype_tbl; in _ice_recv_raw_pkts_vec_avx2() local
414 mb6_7 = _mm256_insert_epi32(mb6_7, ptype_tbl[ptype7], 4); in _ice_recv_raw_pkts_vec_avx2()
415 mb6_7 = _mm256_insert_epi32(mb6_7, ptype_tbl[ptype6], 0); 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()
444 mb2_3 = _mm256_insert_epi32(mb2_3, ptype_tbl[ptype3], 4); in _ice_recv_raw_pkts_vec_avx2()
445 mb2_3 = _mm256_insert_epi32(mb2_3, ptype_tbl[ptype2], 0); in _ice_recv_raw_pkts_vec_avx2()
446 mb0_1 = _mm256_insert_epi32(mb0_1, ptype_tbl[ptype1], 4); in _ice_recv_raw_pkts_vec_avx2()
447 mb0_1 = _mm256_insert_epi32(mb0_1, ptype_tbl[ptype0], 0); in _ice_recv_raw_pkts_vec_avx2()
H A Dice_rxtx_vec_avx512.c155 const uint32_t *ptype_tbl = rxq->vsi->adapter->ptype_tbl; in _ice_recv_raw_pkts_vec_avx512() local
408 (0, 0, 0, ptype_tbl[ptype7], in _ice_recv_raw_pkts_vec_avx512()
409 0, 0, 0, ptype_tbl[ptype6], in _ice_recv_raw_pkts_vec_avx512()
410 0, 0, 0, ptype_tbl[ptype5], in _ice_recv_raw_pkts_vec_avx512()
411 0, 0, 0, ptype_tbl[ptype4]); in _ice_recv_raw_pkts_vec_avx512()
413 (0, 0, 0, ptype_tbl[ptype3], in _ice_recv_raw_pkts_vec_avx512()
414 0, 0, 0, ptype_tbl[ptype2], in _ice_recv_raw_pkts_vec_avx512()
415 0, 0, 0, ptype_tbl[ptype1], in _ice_recv_raw_pkts_vec_avx512()
416 0, 0, 0, ptype_tbl[ptype0]); in _ice_recv_raw_pkts_vec_avx512()
H A Dice_rxtx.c1504 uint32_t *ptype_tbl = rxq->vsi->adapter->ptype_tbl; in ice_rx_scan_hw_ring() local
1543 mb->packet_type = ptype_tbl[ICE_RX_FLEX_DESC_PTYPE_M & in ice_rx_scan_hw_ring()
1732 uint32_t *ptype_tbl = rxq->vsi->adapter->ptype_tbl; in ice_recv_scattered_pkts() local
1840 first_seg->packet_type = ptype_tbl[ICE_RX_FLEX_DESC_PTYPE_M & in ice_recv_scattered_pkts()
2195 uint32_t *ptype_tbl = rxq->vsi->adapter->ptype_tbl; in ice_recv_pkts() local
2244 rxm->packet_type = ptype_tbl[ICE_RX_FLEX_DESC_PTYPE_M & in ice_recv_pkts()
3889 ad->ptype_tbl[i] = ice_get_default_pkt_type(i); in ice_set_default_ptype_table()
H A Dice_ethdev.h476 uint32_t ptype_tbl[ICE_MAX_PKT_TYPE] __rte_cache_min_aligned; member
/f-stack/dpdk/drivers/net/iavf/
H A Diavf_rxtx.c1122 const uint32_t *ptype_tbl; in iavf_recv_pkts() local
1129 ptype_tbl = rxq->vsi->adapter->ptype_tbl; in iavf_recv_pkts()
1189 ptype_tbl[(uint8_t)((qword1 & in iavf_recv_pkts()
1229 const uint32_t *ptype_tbl; in iavf_recv_pkts_flex_rxd() local
1236 ptype_tbl = rxq->vsi->adapter->ptype_tbl; in iavf_recv_pkts_flex_rxd()
1327 const uint32_t *ptype_tbl = rxq->vsi->adapter->ptype_tbl; in iavf_recv_scattered_pkts_flex_rxd() local
1478 const uint32_t *ptype_tbl = rxq->vsi->adapter->ptype_tbl; in iavf_recv_scattered_pkts() local
1587 ptype_tbl[(uint8_t)((qword1 & in iavf_recv_scattered_pkts()
1628 const uint32_t *ptype_tbl = rxq->vsi->adapter->ptype_tbl; in iavf_rx_scan_hw_ring_flex_rxd() local
1705 const uint32_t *ptype_tbl = rxq->vsi->adapter->ptype_tbl; in iavf_rx_scan_hw_ring() local
[all …]
H A Diavf_rxtx_vec_sse.c399 const uint32_t *ptype_tbl = rxq->vsi->adapter->ptype_tbl; in _recv_raw_pkts_vec() local
613 desc_to_ptype_v(descs, &rx_pkts[pos], ptype_tbl); in _recv_raw_pkts_vec()
647 const uint32_t *ptype_tbl = rxq->vsi->adapter->ptype_tbl; in _recv_raw_pkts_vec_flex_rxd() local
907 flex_desc_to_ptype_v(descs, &rx_pkts[pos], ptype_tbl); in _recv_raw_pkts_vec_flex_rxd()
H A Diavf.h203 const uint32_t *ptype_tbl; member
H A Diavf_rxtx_vec_avx2.c145 const uint32_t *type_table = rxq->vsi->adapter->ptype_tbl; in _iavf_recv_raw_pkts_vec_avx2()
643 const uint32_t *type_table = rxq->vsi->adapter->ptype_tbl; in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
H A Diavf_rxtx_vec_avx512.c149 const uint32_t *type_table = rxq->vsi->adapter->ptype_tbl; in _iavf_recv_raw_pkts_vec_avx512()
641 const uint32_t *type_table = rxq->vsi->adapter->ptype_tbl; in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
H A Diavf_ethdev.c1995 adapter->ptype_tbl = iavf_get_default_ptype_table(); in iavf_dev_init()