Home
last modified time | relevance | path

Searched refs:raw_cons (Results 1 – 9 of 9) sorted by relevance

/dpdk/drivers/net/bnxt/
H A Dbnxt_rxtx_vec_common.h106 uint16_t cons, raw_cons = txr->tx_raw_cons; in bnxt_tx_cmp_vec_fast() local
113 cons = raw_cons & ring_mask; in bnxt_tx_cmp_vec_fast()
119 raw_cons += num; in bnxt_tx_cmp_vec_fast()
122 cons = raw_cons & ring_mask; in bnxt_tx_cmp_vec_fast()
127 raw_cons += num; in bnxt_tx_cmp_vec_fast()
130 txr->tx_raw_cons = raw_cons; in bnxt_tx_cmp_vec_fast()
137 uint16_t cons, raw_cons = txr->tx_raw_cons; in bnxt_tx_cmp_vec() local
147 cons = raw_cons & ring_mask; in bnxt_tx_cmp_vec()
166 raw_cons += blk; in bnxt_tx_cmp_vec()
171 raw_cons++; in bnxt_tx_cmp_vec()
[all …]
H A Dbnxt_txr.c364 uint16_t raw_cons = txr->tx_raw_cons; in bnxt_tx_cmp_fast() local
381 raw_cons = RING_NEXT(raw_cons); in bnxt_tx_cmp_fast()
388 txr->tx_raw_cons = raw_cons; in bnxt_tx_cmp_fast()
397 uint16_t raw_cons = txr->tx_raw_cons; in bnxt_tx_cmp() local
412 raw_cons = RING_NEXT(raw_cons); in bnxt_tx_cmp()
446 txr->tx_raw_cons = raw_cons; in bnxt_tx_cmp()
453 uint32_t raw_cons = cpr->cp_raw_cons; in bnxt_handle_tx_cp() local
478 raw_cons = NEXT_RAW_CMP(raw_cons); in bnxt_handle_tx_cp()
486 cpr->cp_raw_cons = raw_cons; in bnxt_handle_tx_cp()
595 raw_cons = NEXT_RAW_CMP(raw_cons); in bnxt_flush_tx_cmp()
[all …]
H A Dbnxt_cpr.h31 #define B_CP_DB_REARM(cpr, raw_cons) \ argument
33 DB_RING_IDX(&((cpr)->cp_db), raw_cons)), \
51 #define B_CP_DIS_DB(cpr, raw_cons) \ argument
53 DB_RING_IDX(&((cpr)->cp_db), raw_cons)), \
56 #define B_CP_DB(cpr, raw_cons, ring_mask) \ argument
58 RING_CMPL((ring_mask), raw_cons)), \
139 bnxt_cpr_cmp_valid(const void *cmpl, uint32_t raw_cons, uint32_t ring_size) in bnxt_cpr_cmp_valid() argument
144 expected = !(raw_cons & ring_size); in bnxt_cpr_cmp_valid()
H A Dbnxt_irq.c24 uint32_t cons, raw_cons, cp_ring_size; in bnxt_int_handler() local
35 raw_cons = cpr->cp_raw_cons; in bnxt_int_handler()
49 cons = RING_CMP(cpr->cp_ring_struct, raw_cons); in bnxt_int_handler()
52 if (!bnxt_cpr_cmp_valid(cmp, raw_cons, cp_ring_size)) in bnxt_int_handler()
56 raw_cons = NEXT_RAW_CMP(raw_cons); in bnxt_int_handler()
59 cpr->cp_raw_cons = raw_cons; in bnxt_int_handler()
H A Dbnxt_rxtx_vec_sse.c164 uint32_t raw_cons = cpr->cp_raw_cons; in recv_burst_vec_sse() local
168 _mm_set1_epi32(!!(raw_cons & cp_ring_size)); in recv_burst_vec_sse()
178 cons = raw_cons & (cp_ring_size - 1); in recv_burst_vec_sse()
179 mbcons = (raw_cons / 2) & (rx_ring_size - 1); in recv_burst_vec_sse()
311 uint32_t raw_cons = cpr->cp_raw_cons; in bnxt_handle_tx_cp_vec() local
320 cons = RING_CMPL(ring_mask, raw_cons); in bnxt_handle_tx_cp_vec()
323 if (!bnxt_cpr_cmp_valid(txcmp, raw_cons, ring_mask + 1)) in bnxt_handle_tx_cp_vec()
332 raw_cons = NEXT_RAW_CMP(raw_cons); in bnxt_handle_tx_cp_vec()
340 cpr->cp_raw_cons = raw_cons; in bnxt_handle_tx_cp_vec()
H A Dbnxt_rxtx_vec_neon.c172 uint32_t raw_cons = cpr->cp_raw_cons; in recv_burst_vec_neon() local
177 vdupq_n_u32(!!(raw_cons & cp_ring_size)); in recv_burst_vec_neon()
187 cons = raw_cons & (cp_ring_size - 1); in recv_burst_vec_neon()
188 mbcons = (raw_cons / 2) & (rx_ring_size - 1); in recv_burst_vec_neon()
339 uint32_t raw_cons = cpr->cp_raw_cons; in bnxt_handle_tx_cp_vec() local
348 cons = RING_CMPL(ring_mask, raw_cons); in bnxt_handle_tx_cp_vec()
351 if (!bnxt_cpr_cmp_valid(txcmp, raw_cons, ring_mask + 1)) in bnxt_handle_tx_cp_vec()
360 raw_cons = NEXT_RAW_CMP(raw_cons); in bnxt_handle_tx_cp_vec()
368 cpr->cp_raw_cons = raw_cons; in bnxt_handle_tx_cp_vec()
H A Dbnxt_rxtx_vec_avx2.c35 uint32_t raw_cons = cpr->cp_raw_cons; in recv_burst_vec_avx2() local
40 _mm256_set1_epi32(!!(raw_cons & cp_ring_size)); in recv_burst_vec_avx2()
92 cons = raw_cons & (cp_ring_size - 1); in recv_burst_vec_avx2()
93 mbcons = (raw_cons / 2) & (rx_ring_size - 1); in recv_burst_vec_avx2()
96 if (!bnxt_cpr_cmp_valid(&cp_desc_ring[cons], raw_cons, cp_ring_size)) in recv_burst_vec_avx2()
389 uint32_t raw_cons = cpr->cp_raw_cons; in bnxt_handle_tx_cp_vec() local
398 cons = RING_CMPL(ring_mask, raw_cons); in bnxt_handle_tx_cp_vec()
401 if (!bnxt_cpr_cmp_valid(txcmp, raw_cons, ring_mask + 1)) in bnxt_handle_tx_cp_vec()
405 raw_cons = NEXT_RAW_CMP(raw_cons); in bnxt_handle_tx_cp_vec()
413 cpr->cp_raw_cons = raw_cons; in bnxt_handle_tx_cp_vec()
H A Dbnxt_rxr.c385 uint32_t *raw_cons, void *cmp) in bnxt_discard_rx() argument
388 uint32_t tmp_raw_cons = *raw_cons; in bnxt_discard_rx()
408 *raw_cons = tmp_raw_cons; in bnxt_discard_rx()
848 uint32_t tmp_raw_cons = *raw_cons; in bnxt_rx_pkt()
1015 *raw_cons = tmp_raw_cons; in bnxt_rx_pkt()
1028 uint32_t raw_cons = cpr->cp_raw_cons; in bnxt_recv_pkts() local
1094 raw_cons = NEXT_RAW_CMP(raw_cons); in bnxt_recv_pkts()
1107 cpr->cp_raw_cons = raw_cons; in bnxt_recv_pkts()
1391 uint32_t raw_cons = cpr->cp_raw_cons; in bnxt_flush_rx_cmp() local
1406 raw_cons = NEXT_RAW_CMP(raw_cons); in bnxt_flush_rx_cmp()
[all …]
H A Dbnxt_ethdev.c3159 raw_cons = cpr->cp_raw_cons; in bnxt_rx_queue_count_op()
3177 raw_cons = raw_cons + CMP_LEN(cmpl_type) + agg_cnt; in bnxt_rx_queue_count_op()
3194 raw_cons = raw_cons + CMP_LEN(cmpl_type) + agg_cnt; in bnxt_rx_queue_count_op()
3199 raw_cons += CMP_LEN(cmpl_type); in bnxt_rx_queue_count_op()
3238 raw_cons = cpr->cp_raw_cons + in bnxt_rx_descriptor_status_op()
3261 raw_cons = cpr->cp_raw_cons; in bnxt_rx_descriptor_status_op()
3285 raw_cons = raw_cons + CMP_LEN(cmpl_type) + agg_cnt; in bnxt_rx_descriptor_status_op()
3305 raw_cons = raw_cons + CMP_LEN(cmpl_type) + agg_cnt; in bnxt_rx_descriptor_status_op()
3310 raw_cons += CMP_LEN(cmpl_type); in bnxt_rx_descriptor_status_op()
3337 raw_cons = cpr->cp_raw_cons; in bnxt_tx_descriptor_status_op()
[all …]