Searched refs:cp_desc_ring (Results 1 – 10 of 10) sorted by relevance
169 struct cmpl_base *cp_desc_ring = cpr->cp_desc_ring; in recv_burst_vec_neon() local191 rte_prefetch0(&cp_desc_ring[cons]); in recv_burst_vec_neon()192 rte_prefetch0(&cp_desc_ring[cons + 4]); in recv_burst_vec_neon()229 rte_prefetch0(&cp_desc_ring[cons + 8]); in recv_burst_vec_neon()230 rte_prefetch0(&cp_desc_ring[cons + 12]); in recv_burst_vec_neon()241 ((void *)&cpr->cp_desc_ring[cons + 7], in recv_burst_vec_neon()248 ((void *)&cpr->cp_desc_ring[cons + 5], in recv_burst_vec_neon()257 ((void *)&cpr->cp_desc_ring[cons + 3], in recv_burst_vec_neon()264 ((void *)&cpr->cp_desc_ring[cons + 1], in recv_burst_vec_neon()343 struct cmpl_base *cp_desc_ring = cpr->cp_desc_ring; in bnxt_handle_tx_cp_vec() local[all …]
161 struct cmpl_base *cp_desc_ring = cpr->cp_desc_ring; in recv_burst_vec_sse() local182 rte_prefetch0(&cp_desc_ring[cons]); in recv_burst_vec_sse()183 rte_prefetch0(&cp_desc_ring[cons + 4]); in recv_burst_vec_sse()223 rte_prefetch0(&cp_desc_ring[cons + 8]); in recv_burst_vec_sse()224 rte_prefetch0(&cp_desc_ring[cons + 12]); in recv_burst_vec_sse()233 rxcmp[3] = _mm_load_si128((void *)&cp_desc_ring[cons + 6]); in recv_burst_vec_sse()237 rxcmp[2] = _mm_load_si128((void *)&cp_desc_ring[cons + 4]); in recv_burst_vec_sse()243 rxcmp[1] = _mm_load_si128((void *)&cp_desc_ring[cons + 2]); in recv_burst_vec_sse()247 rxcmp[0] = _mm_load_si128((void *)&cp_desc_ring[cons + 0]); in recv_burst_vec_sse()315 struct cmpl_base *cp_desc_ring = cpr->cp_desc_ring; in bnxt_handle_tx_cp_vec() local[all …]
32 struct cmpl_base *cp_desc_ring = cpr->cp_desc_ring; in recv_burst_vec_avx2() local138 desc7 = _mm256_load_si256((void *)&cp_desc_ring[cons + 14]); in recv_burst_vec_avx2()140 desc6 = _mm256_load_si256((void *)&cp_desc_ring[cons + 12]); in recv_burst_vec_avx2()142 desc5 = _mm256_load_si256((void *)&cp_desc_ring[cons + 10]); in recv_burst_vec_avx2()144 desc4 = _mm256_load_si256((void *)&cp_desc_ring[cons + 8]); in recv_burst_vec_avx2()146 desc3 = _mm256_load_si256((void *)&cp_desc_ring[cons + 6]); in recv_burst_vec_avx2()148 desc2 = _mm256_load_si256((void *)&cp_desc_ring[cons + 4]); in recv_burst_vec_avx2()150 desc1 = _mm256_load_si256((void *)&cp_desc_ring[cons + 2]); in recv_burst_vec_avx2()152 desc0 = _mm256_load_si256((void *)&cp_desc_ring[cons + 0]); in recv_burst_vec_avx2()393 struct cmpl_base *cp_desc_ring = cpr->cp_desc_ring; in bnxt_handle_tx_cp_vec() local[all …]
102 ring->bd = (void *)cpr->cp_desc_ring; in bnxt_init_tx_ring_struct()465 txcmp = (struct tx_cmpl *)&cpr->cp_desc_ring[cons]; in bnxt_handle_tx_cp()582 struct cmpl_base *cp_desc_ring = cpr->cp_desc_ring; in bnxt_flush_tx_cmp() local589 txcmp = (struct tx_cmpl *)&cp_desc_ring[cons]; in bnxt_flush_tx_cmp()
299 agg_cmpl = (struct rx_pkt_cmpl *)&cpr->cp_desc_ring[last_cp_cons]; in bnxt_agg_bufs_valid()349 &cpr->cp_desc_ring[cp_cons]; in bnxt_rx_pages()859 &cpr->cp_desc_ring[cp_cons]; in bnxt_rx_pkt()877 rxcmp1 = (struct rx_pkt_cmpl_hi *)&cpr->cp_desc_ring[cp_cons]; in bnxt_rx_pkt()1065 rxcmp = (struct rx_pkt_cmpl *)&cpr->cp_desc_ring[cons]; in bnxt_recv_pkts()1251 ring->bd = (void *)cpr->cp_desc_ring; in bnxt_init_rx_ring_struct()1398 rxcmp = (struct rx_pkt_cmpl *)&cpr->cp_desc_ring[cons]; in bnxt_flush_rx_cmp()
295 cp_ring_info->cp_desc_ring = cp_ring->bd; in bnxt_alloc_rings()314 nq_ring_info->cp_desc_ring = nq_ring->bd; in bnxt_alloc_rings()466 ring->bd = (void *)nqr->cp_desc_ring; in bnxt_alloc_rxtx_nq_ring()850 ring->bd = (void *)cpr->cp_desc_ring; in bnxt_alloc_async_ring_struct()
82 struct cmpl_base *cp_desc_ring; member
50 cmp = &cpr->cp_desc_ring[cons]; in bnxt_int_handler()
3166 rxcmp = (struct rx_pkt_cmpl *)&cpr->cp_desc_ring[cons]; in bnxt_rx_queue_count_op()3241 rxcmp = (struct rx_pkt_cmpl *)&cpr->cp_desc_ring[cons]; in bnxt_rx_descriptor_status_op()3267 rxcmp = (struct rx_pkt_cmpl *)&cpr->cp_desc_ring[cons]; in bnxt_rx_descriptor_status_op()3323 struct cmpl_base *cp_desc_ring; in bnxt_tx_descriptor_status_op() local3338 cp_desc_ring = cpr->cp_desc_ring; in bnxt_tx_descriptor_status_op()3347 txcmp = (struct tx_cmpl *)&cp_desc_ring[cons]; in bnxt_tx_descriptor_status_op()
2684 memset(cpr->cp_desc_ring, 0, in bnxt_free_nq_ring()2685 cpr->cp_ring_struct->ring_size * sizeof(*cpr->cp_desc_ring)); in bnxt_free_nq_ring()2696 memset(cpr->cp_desc_ring, 0, in bnxt_free_cp_ring()2697 cpr->cp_ring_struct->ring_size * sizeof(*cpr->cp_desc_ring)); in bnxt_free_cp_ring()