Home
last modified time | relevance | path

Searched refs:flags_type (Results 1 – 7 of 7) sorted by relevance

/dpdk/drivers/net/bnxt/
H A Dbnxt_txr.c190 txbd->flags_type = nr_bds << TX_BD_LONG_FLAGS_BD_CNT_SFT; in bnxt_start_xmit()
191 txbd->flags_type |= TX_BD_SHORT_FLAGS_COAL_NOW; in bnxt_start_xmit()
192 txbd->flags_type |= TX_BD_LONG_FLAGS_NO_CMPL; in bnxt_start_xmit()
195 txbd->flags_type |= TX_BD_LONG_FLAGS_LHINT_GTE2K; in bnxt_start_xmit()
197 txbd->flags_type |= lhint_arr[tx_pkt->pkt_len >> 9]; in bnxt_start_xmit()
202 txbd->flags_type |= TX_BD_LONG_TYPE_TX_BD_LONG; in bnxt_start_xmit()
327 txbd->flags_type |= TX_BD_SHORT_TYPE_TX_BD_SHORT; in bnxt_start_xmit()
342 txbd->flags_type = TX_BD_SHORT_TYPE_TX_BD_SHORT; in bnxt_start_xmit()
348 txbd->flags_type |= TX_BD_LONG_FLAGS_PACKET_END; in bnxt_start_xmit()
523 last_txbd->flags_type &= ~TX_BD_LONG_FLAGS_NO_CMPL; in bnxt_xmit_pkts()
H A Dbnxt_rxtx_vec_neon.c81 uint32x4_t flags_type, flags2, index, errors, rss_flags; in descs_to_mbufs() local
93 flags_type = vreinterpretq_u32_u64(vcombine_u64(vget_low_u64(t0), in descs_to_mbufs()
95 ptype_idx = vshrq_n_u32(vandq_u32(flags_type, flags_type_mask), in descs_to_mbufs()
115 rss_flags = vshrq_n_u32(vandq_u32(flags_type, rss_mask), 9); in descs_to_mbufs()
403 txbd->flags_type = bnxt_xmit_flags_len(tx_mbuf->data_len, in bnxt_xmit_fixed_burst_vec()
412 txbd->flags_type &= ~TX_BD_LONG_FLAGS_NO_CMPL; in bnxt_xmit_fixed_burst_vec()
H A Dbnxt_rxtx_vec_sse.c74 __m128i t0, t1, flags_type, flags2, index, errors, rss_flags; in descs_to_mbufs() local
84 flags_type = _mm_unpacklo_epi64(t0, t1); in descs_to_mbufs()
85 ptype_idx = _mm_srli_epi32(_mm_and_si128(flags_type, flags_type_mask), in descs_to_mbufs()
102 rss_flags = _mm_srli_epi32(_mm_and_si128(flags_type, rss_mask), 9); in descs_to_mbufs()
409 txbd[-1].flags_type &= ~TX_BD_LONG_FLAGS_NO_CMPL; in bnxt_xmit_fixed_burst_vec()
H A Dbnxt_rxr.c191 if (likely(tpa_start->flags_type & in bnxt_tpa_get_metadata()
533 uint32_t flags_type, flags2; in bnxt_parse_pkt_type() local
536 flags_type = rte_le_to_cpu_16(rxcmp->flags_type); in bnxt_parse_pkt_type()
549 index = BNXT_CMPL_ITYPE_TO_IDX(flags_type) | in bnxt_parse_pkt_type()
651 uint16_t flags_type, errors, flags; in bnxt_set_ol_flags() local
654 flags_type = rte_le_to_cpu_16(rxcmp->flags_type); in bnxt_set_ol_flags()
678 if (flags_type & RX_PKT_CMPL_FLAGS_RSS_VALID) { in bnxt_set_ol_flags()
684 if (unlikely((flags_type & RX_PKT_CMPL_FLAGS_MASK) == in bnxt_set_ol_flags()
930 if (unlikely((rte_le_to_cpu_16(rxcmp->flags_type) & in bnxt_rx_pkt()
1290 rx_bd_ring[j].flags_type = rte_cpu_to_le_16(type); in bnxt_init_rxbds()
H A Dbnxt_rxtx_vec_avx2.c73 __m256i t0, t1, flags_type, flags2, index, errors; in recv_burst_vec_avx2() local
189 flags_type = _mm256_unpacklo_epi64(t0, t1); in recv_burst_vec_avx2()
190 ptype_idx = _mm256_and_si256(flags_type, flags_type_mask); in recv_burst_vec_avx2()
291 rss_flags = _mm256_and_si256(flags_type, rss_mask); in recv_burst_vec_avx2()
535 txbd[-1].flags_type &= ~TX_BD_LONG_FLAGS_NO_CMPL; in bnxt_xmit_fixed_burst_vec()
H A Dbnxt_rxr.h332 uint16_t flags_type = v2_cmp->flags_type & in bnxt_parse_pkt_type_v2() local
363 switch (flags_type) { in bnxt_parse_pkt_type_v2()
H A Dhsi_struct_def_dpdk.h2418 uint16_t flags_type; member
2528 uint16_t flags_type; member
2932 uint16_t flags_type; member
3240 uint16_t flags_type; member
3279 uint16_t flags_type; member
3331 uint16_t flags_type; member
3391 uint16_t flags_type; member
3420 uint16_t flags_type; member
3922 uint16_t flags_type; member
4041 uint16_t flags_type; member
[all …]