Home
last modified time | relevance | path

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

/f-stack/dpdk/drivers/net/bnxt/
H A Dbnxt_rxr.c392 flags2 = rte_le_to_cpu_32(rxcmp1->flags2); in bnxt_parse_pkt_type()
471 flags = rte_le_to_cpu_32(rxcmp1->flags2) & in bnxt_set_ol_flags()
539 flags2 = rte_le_to_cpu_32(rxcmp1->flags2); in bnxt_ulp_set_mark_in_mbuf()
540 meta = rte_le_to_cpu_32(rxcmp1->metadata); in bnxt_ulp_set_mark_in_mbuf()
610 mbuf->hash.fdir.id = rxcmp1->cfa_code; in bnxt_ulp_set_mark_in_mbuf()
623 struct rx_pkt_cmpl_hi *rxcmp1, in bnxt_set_mark_in_mbuf() argument
638 flags2 = rte_le_to_cpu_16(rxcmp1->flags2); in bnxt_set_mark_in_mbuf()
639 meta = rte_le_to_cpu_32(rxcmp1->metadata); in bnxt_set_mark_in_mbuf()
667 struct rx_pkt_cmpl_hi *rxcmp1; in bnxt_rx_pkt() local
714 (struct rx_tpa_end_cmpl_hi *)rxcmp1); in bnxt_rx_pkt()
[all …]
H A Dbnxt_rxtx_vec_sse.c38 #define GET_DESC_FIELDS(rxcmp, rxcmp1, shuf_msk, ptype_idx, pi, ret) \ argument
51 r = _mm_blend_epi16(r, _mm_slli_si128((rxcmp1), 6), 0x20); \
196 __m128i rxcmp1[RTE_BNXT_DESCS_PER_LOOP]; in bnxt_recv_pkts_vec() local
221 rxcmp1[3] = _mm_load_si128((void *)&cp_desc_ring[cons + 7]); in bnxt_recv_pkts_vec()
225 rxcmp1[2] = _mm_load_si128((void *)&cp_desc_ring[cons + 5]); in bnxt_recv_pkts_vec()
229 tmp1 = _mm_unpackhi_epi32(rxcmp1[2], rxcmp1[3]); in bnxt_recv_pkts_vec()
231 rxcmp1[1] = _mm_load_si128((void *)&cp_desc_ring[cons + 3]); in bnxt_recv_pkts_vec()
235 rxcmp1[0] = _mm_load_si128((void *)&cp_desc_ring[cons + 1]); in bnxt_recv_pkts_vec()
239 tmp0 = _mm_unpackhi_epi32(rxcmp1[0], rxcmp1[1]); 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
53 vlan_tci = vgetq_lane_u32((rxcmp1), 1); \
204 uint32x4_t rxcmp1[RTE_BNXT_DESCS_PER_LOOP]; in bnxt_recv_pkts_vec() local
230 rxcmp1[3] = vld1q_u32((void *)&cpr->cp_desc_ring[cons + 7]); in bnxt_recv_pkts_vec()
234 rxcmp1[2] = vld1q_u32((void *)&cpr->cp_desc_ring[cons + 5]); in bnxt_recv_pkts_vec()
238 t1 = vreinterpretq_u64_u32(vzip2q_u32(rxcmp1[2], rxcmp1[3])); in bnxt_recv_pkts_vec()
240 rxcmp1[1] = vld1q_u32((void *)&cpr->cp_desc_ring[cons + 3]); in bnxt_recv_pkts_vec()
244 rxcmp1[0] = vld1q_u32((void *)&cpr->cp_desc_ring[cons + 1]); in bnxt_recv_pkts_vec()
248 t0 = vreinterpretq_u64_u32(vzip2q_u32(rxcmp1[0], rxcmp1[1])); 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_rxr.h93 struct rx_pkt_cmpl_hi *rxcmp1,