Searched refs:rxcmp1 (Results 1 – 4 of 4) sorted by relevance
| /dpdk/drivers/net/bnxt/ |
| H A D | bnxt_rxtx_vec_neon.c | 53 vlan_tci = vgetq_lane_u32((rxcmp1), 1); \
240 rxcmp1[3] = vreinterpretq_u32_u64(vld1q_lane_u64 in recv_burst_vec_neon()
242 vreinterpretq_u64_u32(rxcmp1[3]), 0)); in recv_burst_vec_neon()
247 rxcmp1[2] = vreinterpretq_u32_u64(vld1q_lane_u64 in recv_burst_vec_neon()
249 vreinterpretq_u64_u32(rxcmp1[2]), 0)); in recv_burst_vec_neon()
252 t1 = vreinterpretq_u64_u32(vzip2q_u32(rxcmp1[2], rxcmp1[3])); in recv_burst_vec_neon()
256 rxcmp1[1] = vreinterpretq_u32_u64(vld1q_lane_u64 in recv_burst_vec_neon()
258 vreinterpretq_u64_u32(rxcmp1[1]), 0)); in recv_burst_vec_neon()
263 rxcmp1[0] = vreinterpretq_u32_u64(vld1q_lane_u64 in recv_burst_vec_neon()
265 vreinterpretq_u64_u32(rxcmp1[0]), 0)); in recv_burst_vec_neon()
[all …]
|
| H A D | bnxt_rxr.h | 120 struct rx_pkt_cmpl_hi *rxcmp1,
188 static inline void bnxt_set_vlan(struct rx_pkt_cmpl_hi *rxcmp1, in bnxt_set_vlan() argument
191 uint32_t metadata = rte_le_to_cpu_32(rxcmp1->metadata); in bnxt_set_vlan()
203 #define RX_CMP_METADATA0_VID(rxcmp1) \ argument
204 ((((struct rx_pkt_v2_cmpl_hi *)rxcmp1)->metadata0) & \
211 struct rx_pkt_cmpl_hi *rxcmp1) in bnxt_rx_vlan_v2() argument
214 mbuf->vlan_tci = RX_CMP_METADATA0_VID(rxcmp1); in bnxt_rx_vlan_v2()
265 struct rx_pkt_cmpl_hi *rxcmp1) in bnxt_parse_csum_v2() argument
268 (struct rx_pkt_v2_cmpl_hi *)(rxcmp1); in bnxt_parse_csum_v2()
326 struct rx_pkt_cmpl_hi *rxcmp1) in bnxt_parse_pkt_type_v2() argument
[all …]
|
| H A D | bnxt_rxtx_vec_sse.c | 38 #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); \
206 __m128i rxcmp1[BNXT_RX_DESCS_PER_LOOP_VEC128]; in recv_burst_vec_sse() local
231 rxcmp1[3] = _mm_load_si128((void *)&cp_desc_ring[cons + 7]); in recv_burst_vec_sse()
235 rxcmp1[2] = _mm_load_si128((void *)&cp_desc_ring[cons + 5]); in recv_burst_vec_sse()
239 tmp1 = _mm_unpackhi_epi32(rxcmp1[2], rxcmp1[3]); in recv_burst_vec_sse()
241 rxcmp1[1] = _mm_load_si128((void *)&cp_desc_ring[cons + 3]); in recv_burst_vec_sse()
245 rxcmp1[0] = _mm_load_si128((void *)&cp_desc_ring[cons + 1]); in recv_burst_vec_sse()
249 tmp0 = _mm_unpackhi_epi32(rxcmp1[0], rxcmp1[1]); 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 D | bnxt_rxr.c | 537 flags2 = rte_le_to_cpu_32(rxcmp1->flags2); in bnxt_parse_pkt_type()
656 flags = rte_le_to_cpu_32(rxcmp1->flags2) & in bnxt_set_ol_flags()
738 flags2 = rte_le_to_cpu_32(rxcmp1->flags2); in bnxt_ulp_set_mark_in_mbuf()
739 meta = rte_le_to_cpu_32(rxcmp1->metadata); in bnxt_ulp_set_mark_in_mbuf()
809 mbuf->hash.fdir.id = rxcmp1->cfa_code; in bnxt_ulp_set_mark_in_mbuf()
822 struct rx_pkt_cmpl_hi *rxcmp1, in bnxt_set_mark_in_mbuf() argument
847 struct rx_pkt_cmpl_hi *rxcmp1; in bnxt_rx_pkt() local
892 (struct rx_tpa_end_cmpl_hi *)rxcmp1); in bnxt_rx_pkt()
937 bnxt_parse_csum_v2(mbuf, rxcmp1); in bnxt_rx_pkt()
939 bnxt_rx_vlan_v2(mbuf, rxcmp, rxcmp1); in bnxt_rx_pkt()
[all …]
|