Home
last modified time | relevance | path

Searched refs:write_idx (Results 1 – 14 of 14) sorted by relevance

/dpdk/drivers/net/bnxt/tf_ulp/
H A Dulp_utils.c250 blob->write_idx = 0; in ulp_blob_init()
286 blob->write_idx, in ulp_blob_push()
291 blob->write_idx, in ulp_blob_push()
343 blob->write_idx = offset; in ulp_blob_insert()
346 blob->write_idx, in ulp_blob_insert()
351 blob->write_idx, in ulp_blob_insert()
526 pad = RTE_ALIGN(blob->write_idx, align) - blob->write_idx; in ulp_blob_pad_align()
531 blob->write_idx += pad; in ulp_blob_pad_align()
713 return blob->write_idx; in ulp_blob_data_len_get()
1003 if ((dst->write_idx + src->write_idx) > dst->bitlen) { in ulp_blob_buffer_copy()
[all …]
H A Dulp_utils.h79 uint16_t write_idx; member
H A Dulp_mapper.c1374 uint16_t write_idx = blob->write_idx; in ulp_mapper_field_opc_process() local
1553 fld->description, (val) ? write_idx : 0, val_len); in ulp_mapper_field_opc_process()
/dpdk/drivers/raw/ioat/
H A Drte_idxd_rawdev_fns.h143 if (idxd->hdls_read > write_idx) in __idxd_burst_capacity()
144 write_idx += idxd->desc_ring_mask + 1; in __idxd_burst_capacity()
145 used_space = write_idx - idxd->hdls_read; in __idxd_burst_capacity()
180 if (((write_idx + 2) & mask) == idxd->hdls_read || in __idxd_write_desc()
181 ((write_idx + 1) & mask) == idxd->hdls_read) in __idxd_write_desc()
185 idxd->desc_ring[write_idx].pasid = 0; in __idxd_write_desc()
187 idxd->desc_ring[write_idx].completion = __desc_idx_to_iova(idxd, write_idx & mask); in __idxd_write_desc()
188 idxd->desc_ring[write_idx].src = src; in __idxd_write_desc()
189 idxd->desc_ring[write_idx].dst = dst; in __idxd_write_desc()
190 idxd->desc_ring[write_idx].size = size; in __idxd_write_desc()
[all …]
/dpdk/drivers/event/sw/
H A Devent_ring.h28 uint32_t write_idx; member
60 return r->write_idx - r->read_idx; in rob_ring_count()
75 uint32_t write = r->write_idx; in rob_ring_enqueue()
80 r->write_idx++; in rob_ring_enqueue()
89 const uint32_t write = r->write_idx; in rob_ring_dequeue()
/dpdk/drivers/dma/idxd/
H A Didxd_common.c88 uint16_t write_idx = (idxd->batch_start & mask) + idxd->batch_size; in __idxd_write_desc() local
94 if (((write_idx + 1) & mask) == (idxd->ids_returned & mask)) in __idxd_write_desc()
99 const uint64_t comp_addr = __desc_idx_to_iova(idxd, write_idx & mask); in __idxd_write_desc()
100 _mm256_store_si256((void *)&idxd->desc_ring[write_idx], in __idxd_write_desc()
102 _mm256_store_si256((void *)&idxd->desc_ring[write_idx].size, in __idxd_write_desc()
107 rte_prefetch0_write(&idxd->desc_ring[write_idx + 1]); in __idxd_write_desc()
475 uint16_t write_idx = idxd->batch_start + idxd->batch_size; in idxd_burst_capacity() local
484 used_space = (write_idx - idxd->ids_returned) & idxd->desc_ring_mask; in idxd_burst_capacity()
/dpdk/drivers/net/pfe/
H A Dpfe_hif_lib.h36 u32 write_idx; member
46 u32 write_idx; member
H A Dpfe_hif_lib.c156 queue->write_idx = 0; in hif_lib_client_init_rx_buffers()
225 queue->write_idx = 0; in hif_lib_client_init_tx_buffers()
497 struct tx_queue_desc *desc = queue->base + queue->write_idx; in hif_lib_xmit_pkt()
513 queue->write_idx = (queue->write_idx + 1) & (queue->size - 1); in hif_lib_xmit_pkt()
H A Dpfe_hif.c239 rx_queue->write_idx = 0; in pfe_hif_client_register()
305 struct rx_queue_desc *desc = queue->base + queue->write_idx; in client_put_rxpacket()
324 queue->write_idx = (queue->write_idx + 1) in client_put_rxpacket()
H A Dpfe_hif.h33 u32 write_idx; member
/dpdk/drivers/net/octeontx_ep/
H A Dotx_ep_common.h299 uint32_t write_idx; member
H A Dotx_ep_rxtx.c182 droq->write_idx = 0; in otx_ep_droq_reset_indices()
/dpdk/drivers/net/liquidio/
H A Dlio_struct.h94 uint32_t write_idx; member
H A Dlio_rxtx.c33 droq->write_idx = 0; in lio_droq_reset_indices()