Home
last modified time | relevance | path

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

/f-stack/dpdk/drivers/net/bnxt/
H A Dbnxt_rxr.c226 struct rx_pkt_cmpl *rxcmp; in bnxt_rx_pages() local
239 rxcmp = (struct rx_pkt_cmpl *) in bnxt_rx_pages()
244 bnxt_dump_cmpl(cp_cons, rxcmp); in bnxt_rx_pages()
247 ag_cons = rxcmp->opaque; in bnxt_rx_pages()
666 struct rx_pkt_cmpl *rxcmp; in bnxt_rx_pkt() local
678 rxcmp = (struct rx_pkt_cmpl *) in bnxt_rx_pkt()
681 cmp_type = CMP_TYPE(rxcmp); in bnxt_rx_pkt()
731 cons = rxcmp->opaque; in bnxt_rx_pkt()
739 mbuf->pkt_len = rxcmp->len; in bnxt_rx_pkt()
833 struct rx_pkt_cmpl *rxcmp; in bnxt_recv_pkts() local
[all …]
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)); \
197 __m128i rxcmp[RTE_BNXT_DESCS_PER_LOOP]; in bnxt_recv_pkts_vec() local
223 rxcmp[3] = _mm_load_si128((void *)&cp_desc_ring[cons + 6]); in bnxt_recv_pkts_vec()
227 rxcmp[2] = _mm_load_si128((void *)&cp_desc_ring[cons + 4]); in bnxt_recv_pkts_vec()
233 rxcmp[1] = _mm_load_si128((void *)&cp_desc_ring[cons + 2]); in bnxt_recv_pkts_vec()
237 rxcmp[0] = _mm_load_si128((void *)&cp_desc_ring[cons + 0]); in bnxt_recv_pkts_vec()
271 descs_to_mbufs(rxcmp, rxcmp1, mbuf_init, &rx_pkts[nb_rx_pkts]); in bnxt_recv_pkts_vec()
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), \
205 uint32x4_t rxcmp[RTE_BNXT_DESCS_PER_LOOP]; in bnxt_recv_pkts_vec() local
232 rxcmp[3] = vld1q_u32((void *)&cpr->cp_desc_ring[cons + 6]); in bnxt_recv_pkts_vec()
236 rxcmp[2] = vld1q_u32((void *)&cpr->cp_desc_ring[cons + 4]); in bnxt_recv_pkts_vec()
242 rxcmp[1] = vld1q_u32((void *)&cpr->cp_desc_ring[cons + 2]); in bnxt_recv_pkts_vec()
246 rxcmp[0] = vld1q_u32((void *)&cpr->cp_desc_ring[cons + 0]); in bnxt_recv_pkts_vec()
289 descs_to_mbufs(rxcmp, rxcmp1, mb_init, &rx_pkts[nb_rx_pkts]); in bnxt_recv_pkts_vec()
H A Dbnxt_ethdev.c2894 struct rx_pkt_cmpl *rxcmp; in bnxt_rx_queue_count_op() local
2908 rxcmp = (struct rx_pkt_cmpl *)&cpr->cp_desc_ring[cons]; in bnxt_rx_queue_count_op()
2910 if (!CMP_VALID(rxcmp, raw_cons, cpr->cp_ring_struct)) { in bnxt_rx_queue_count_op()
2928 struct rx_pkt_cmpl *rxcmp; in bnxt_rx_descriptor_status_op() local
2947 rxcmp = (struct rx_pkt_cmpl *)&cpr->cp_desc_ring[cons]; in bnxt_rx_descriptor_status_op()
2950 if (CMPL_VALID(rxcmp, cpr->valid)) in bnxt_rx_descriptor_status_op()
2953 if (CMPL_VALID(rxcmp, !cpr->valid)) in bnxt_rx_descriptor_status_op()