Searched refs:cp_desc_ring (Results 1 – 9 of 9) sorted by relevance
151 struct cmpl_base *cp_desc_ring = cpr->cp_desc_ring; in bnxt_recv_pkts_vec() local175 rte_prefetch0(&cp_desc_ring[cons]); in bnxt_recv_pkts_vec()176 rte_prefetch0(&cp_desc_ring[cons + 4]); in bnxt_recv_pkts_vec()213 rte_prefetch0(&cp_desc_ring[cons + 8]); in bnxt_recv_pkts_vec()214 rte_prefetch0(&cp_desc_ring[cons + 12]); in bnxt_recv_pkts_vec()223 rxcmp[3] = _mm_load_si128((void *)&cp_desc_ring[cons + 6]); in bnxt_recv_pkts_vec()227 rxcmp[2] = _mm_load_si128((void *)&cp_desc_ring[cons + 4]); in bnxt_recv_pkts_vec()233 rxcmp[1] = _mm_load_si128((void *)&cp_desc_ring[cons + 2]); in bnxt_recv_pkts_vec()237 rxcmp[0] = _mm_load_si128((void *)&cp_desc_ring[cons + 0]); in bnxt_recv_pkts_vec()301 struct cmpl_base *cp_desc_ring = cpr->cp_desc_ring; in bnxt_handle_tx_cp_vec() local[all …]
158 struct cmpl_base *cp_desc_ring = cpr->cp_desc_ring; in bnxt_recv_pkts_vec() local183 rte_prefetch0(&cp_desc_ring[cons]); in bnxt_recv_pkts_vec()184 rte_prefetch0(&cp_desc_ring[cons + 4]); in bnxt_recv_pkts_vec()222 rte_prefetch0(&cp_desc_ring[cons + 8]); in bnxt_recv_pkts_vec()223 rte_prefetch0(&cp_desc_ring[cons + 12]); in bnxt_recv_pkts_vec()232 rxcmp[3] = vld1q_u32((void *)&cpr->cp_desc_ring[cons + 6]); in bnxt_recv_pkts_vec()236 rxcmp[2] = vld1q_u32((void *)&cpr->cp_desc_ring[cons + 4]); in bnxt_recv_pkts_vec()242 rxcmp[1] = vld1q_u32((void *)&cpr->cp_desc_ring[cons + 2]); in bnxt_recv_pkts_vec()246 rxcmp[0] = vld1q_u32((void *)&cpr->cp_desc_ring[cons + 0]); in bnxt_recv_pkts_vec()319 struct cmpl_base *cp_desc_ring = cpr->cp_desc_ring; in bnxt_handle_tx_cp_vec() local[all …]
98 ring->bd = (void *)cpr->cp_desc_ring; in bnxt_init_tx_ring_struct()435 struct cmpl_base *cp_desc_ring = cpr->cp_desc_ring; in bnxt_handle_tx_cp() local445 txcmp = (struct tx_cmpl *)&cpr->cp_desc_ring[cons]; in bnxt_handle_tx_cp()446 rte_prefetch_non_temporal(&cp_desc_ring[(cons + 2) & in bnxt_handle_tx_cp()453 rte_prefetch0(&cp_desc_ring[cons]); in bnxt_handle_tx_cp()
190 agg_cmpl = (struct rx_pkt_cmpl *)&cpr->cp_desc_ring[last_cp_cons]; in bnxt_agg_bufs_valid()240 &cpr->cp_desc_ring[cp_cons]; in bnxt_rx_pages()679 &cpr->cp_desc_ring[cp_cons]; in bnxt_rx_pkt()697 rxcmp1 = (struct rx_pkt_cmpl_hi *)&cpr->cp_desc_ring[cp_cons]; in bnxt_rx_pkt()867 rxcmp = (struct rx_pkt_cmpl *)&cpr->cp_desc_ring[cons]; in bnxt_recv_pkts()1059 ring->bd = (void *)cpr->cp_desc_ring; in bnxt_init_rx_ring_struct()
289 cp_ring_info->cp_desc_ring = cp_ring->bd; in bnxt_alloc_rings()308 nq_ring_info->cp_desc_ring = nq_ring->bd; in bnxt_alloc_rings()448 ring->bd = (void *)nqr->cp_desc_ring; in bnxt_alloc_rxtx_nq_ring()839 ring->bd = (void *)cpr->cp_desc_ring; in bnxt_alloc_async_ring_struct()
46 cmp = &cpr->cp_desc_ring[cons]; in bnxt_int_handler()
89 struct cmpl_base *cp_desc_ring; member
2907 rte_prefetch0(&cpr->cp_desc_ring[cons]); in bnxt_rx_queue_count_op()2908 rxcmp = (struct rx_pkt_cmpl *)&cpr->cp_desc_ring[cons]; in bnxt_rx_queue_count_op()2947 rxcmp = (struct rx_pkt_cmpl *)&cpr->cp_desc_ring[cons]; in bnxt_rx_descriptor_status_op()2989 txcmp = (struct tx_pkt_cmpl *)&cpr->cp_desc_ring[cons]; in bnxt_tx_descriptor_status_op()
2531 memset(cpr->cp_desc_ring, 0, cpr->cp_ring_struct->ring_size * in bnxt_free_nq_ring()2532 sizeof(*cpr->cp_desc_ring)); in bnxt_free_nq_ring()2544 memset(cpr->cp_desc_ring, 0, cpr->cp_ring_struct->ring_size * in bnxt_free_cp_ring()2545 sizeof(*cpr->cp_desc_ring)); in bnxt_free_cp_ring()