Home
last modified time | relevance | path

Searched refs:cp_ring_size (Results 1 – 5 of 5) sorted by relevance

/dpdk/drivers/net/bnxt/
H A Dbnxt_irq.c24 uint32_t cons, raw_cons, cp_ring_size; in bnxt_int_handler() local
48 cp_ring_size = cpr->cp_ring_struct->ring_size; in bnxt_int_handler()
52 if (!bnxt_cpr_cmp_valid(cmp, raw_cons, cp_ring_size)) in bnxt_int_handler()
H A Dbnxt_rxtx_vec_avx2.c30 uint16_t cp_ring_size = cpr->cp_ring_struct->ring_size; 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()
96 if (!bnxt_cpr_cmp_valid(&cp_desc_ring[cons], raw_cons, cp_ring_size)) in recv_burst_vec_avx2()
101 (cp_ring_size - cons) / 2)); in recv_burst_vec_avx2()
H A Dbnxt_rxtx_vec_sse.c159 uint16_t cp_ring_size = cpr->cp_ring_struct->ring_size; 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()
187 (cp_ring_size - cons) / 2)); in recv_burst_vec_sse()
H A Dbnxt_rxtx_vec_neon.c167 uint16_t cp_ring_size = cpr->cp_ring_struct->ring_size; 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()
196 (cp_ring_size - cons) / 2)); in recv_burst_vec_neon()
H A Dbnxt_ethdev.c3146 uint32_t desc = 0, raw_cons, cp_ring_size; in bnxt_rx_queue_count_op() local
3160 cp_ring_size = cpr->cp_ring_struct->ring_size; in bnxt_rx_queue_count_op()
3168 if (!bnxt_cpr_cmp_valid(rxcmp, raw_cons, cp_ring_size)) in bnxt_rx_queue_count_op()
3212 uint32_t desc, raw_cons, cp_ring_size; in bnxt_rx_descriptor_status_op() local
3226 cp_ring_size = cpr->cp_ring_struct->ring_size; in bnxt_rx_descriptor_status_op()
3243 if (bnxt_cpr_cmp_valid(rxcmp, raw_cons, cp_ring_size)) in bnxt_rx_descriptor_status_op()
3269 if (!bnxt_cpr_cmp_valid(rxcmp, raw_cons, cp_ring_size)) in bnxt_rx_descriptor_status_op()