Home
last modified time | relevance | path

Searched refs:rxcmp (Results 1 – 5 of 5) sorted by relevance

/dpdk/drivers/net/bnxt/
H A Dbnxt_rxr.c335 struct rx_pkt_cmpl *rxcmp; in bnxt_rx_pages() local
348 rxcmp = (struct rx_pkt_cmpl *) in bnxt_rx_pages()
356 ag_cons = rxcmp->opaque; in bnxt_rx_pages()
391 cmp_type = CMP_TYPE(rxcmp); in bnxt_discard_rx()
846 struct rx_pkt_cmpl *rxcmp; in bnxt_rx_pkt() local
858 rxcmp = (struct rx_pkt_cmpl *) in bnxt_rx_pkt()
861 cmp_type = CMP_TYPE(rxcmp); in bnxt_rx_pkt()
909 cons = rxcmp->opaque; in bnxt_rx_pkt()
925 mbuf->pkt_len = rxcmp->len; in bnxt_rx_pkt()
1033 struct rx_pkt_cmpl *rxcmp; in bnxt_recv_pkts() local
[all …]
H A Dbnxt_rxr.h199 #define RX_CMP_VLAN_VALID(rxcmp) \ argument
200 (((struct rx_pkt_v2_cmpl *)rxcmp)->metadata1_payload_offset & \
210 struct rx_pkt_cmpl *rxcmp, in bnxt_rx_vlan_v2() argument
213 if (RX_CMP_VLAN_VALID(rxcmp)) { in bnxt_rx_vlan_v2()
325 struct rx_pkt_cmpl *rxcmp, in bnxt_parse_pkt_type_v2() argument
329 (struct rx_pkt_v2_cmpl *)(rxcmp); in bnxt_parse_pkt_type_v2()
349 vlan = !!RX_CMP_VLAN_VALID(rxcmp); in bnxt_parse_pkt_type_v2()
H A Dbnxt_rxtx_vec_sse.c38 #define GET_DESC_FIELDS(rxcmp, rxcmp1, shuf_msk, ptype_idx, pi, ret) \ argument
44 r = _mm_shuffle_epi8((rxcmp), (shuf_msk)); \
207 __m128i rxcmp[BNXT_RX_DESCS_PER_LOOP_VEC128]; in recv_burst_vec_sse() local
233 rxcmp[3] = _mm_load_si128((void *)&cp_desc_ring[cons + 6]); in recv_burst_vec_sse()
237 rxcmp[2] = _mm_load_si128((void *)&cp_desc_ring[cons + 4]); in recv_burst_vec_sse()
243 rxcmp[1] = _mm_load_si128((void *)&cp_desc_ring[cons + 2]); in recv_burst_vec_sse()
247 rxcmp[0] = _mm_load_si128((void *)&cp_desc_ring[cons + 0]); in recv_burst_vec_sse()
267 descs_to_mbufs(rxcmp, rxcmp1, mbuf_init, &rx_pkts[nb_rx_pkts], in recv_burst_vec_sse()
H A Dbnxt_rxtx_vec_neon.c38 #define GET_DESC_FIELDS(rxcmp, rxcmp1, shuf_msk, ptype_idx, pkt_idx, ret) \ argument
45 r = vreinterpretq_u32_u8(vqtbl1q_u8(vreinterpretq_u8_u32(rxcmp), \
216 uint32x4_t rxcmp[BNXT_RX_DESCS_PER_LOOP_VEC128]; in recv_burst_vec_neon() local
243 rxcmp[3] = vld1q_u32((void *)&cpr->cp_desc_ring[cons + 6]); in recv_burst_vec_neon()
250 rxcmp[2] = vld1q_u32((void *)&cpr->cp_desc_ring[cons + 4]); in recv_burst_vec_neon()
259 rxcmp[1] = vld1q_u32((void *)&cpr->cp_desc_ring[cons + 2]); in recv_burst_vec_neon()
266 rxcmp[0] = vld1q_u32((void *)&cpr->cp_desc_ring[cons + 0]); in recv_burst_vec_neon()
295 descs_to_mbufs(rxcmp, rxcmp1, mb_init, &rx_pkts[nb_rx_pkts], in recv_burst_vec_neon()
H A Dbnxt_ethdev.c3148 struct rx_pkt_cmpl *rxcmp; in bnxt_rx_queue_count_op() local
3171 cmpl_type = CMP_TYPE(rxcmp); in bnxt_rx_queue_count_op()
3176 agg_cnt = BNXT_RX_L2_AGG_BUFS(rxcmp); in bnxt_rx_queue_count_op()
3185 p5_tpa_end = (void *)rxcmp; in bnxt_rx_queue_count_op()
3190 tpa_end = (void *)rxcmp; in bnxt_rx_queue_count_op()
3214 struct rx_pkt_cmpl *rxcmp; in bnxt_rx_descriptor_status_op() local
3234 struct rx_pkt_cmpl *rxcmp; in bnxt_rx_descriptor_status_op() local
3272 cmpl_type = CMP_TYPE(rxcmp); in bnxt_rx_descriptor_status_op()
3278 cons = rxcmp->opaque; in bnxt_rx_descriptor_status_op()
3296 p5_tpa_end = (void *)rxcmp; in bnxt_rx_descriptor_status_op()
[all …]