Home
last modified time | relevance | path

Searched refs:batch_comp_ring (Results 1 – 2 of 2) sorted by relevance

/dpdk/drivers/dma/idxd/
H A Didxd_common.c34 rte_prefetch1(&idxd->batch_comp_ring[idxd->batch_idx_read]); in __submit()
73 _mm256_store_si256((void *)&idxd->batch_comp_ring[idxd->batch_idx_write], in __submit()
173 uint8_t bstatus = (idxd->batch_comp_ring[last_batch_write].status != 0); in idxd_vchan_status()
204 bstatus = idxd->batch_comp_ring[idxd->batch_idx_read].status; in batch_ok()
266 idxd->batch_comp_ring[idxd->batch_idx_read].completed_size -= ret; in batch_completed()
272 idxd->batch_comp_ring[idxd->batch_idx_read].status = desc_comp->status; in batch_completed()
537 memset(idxd->batch_comp_ring, 0, sizeof(*idxd->batch_comp_ring) * in idxd_vchan_setup()
587 sizeof(idxd->batch_comp_ring[0])) * (idxd->max_batches + 1), in idxd_dmadev_create()
588 sizeof(idxd->batch_comp_ring[0]), dev->numa_node); in idxd_dmadev_create()
589 if (idxd->batch_comp_ring == NULL) { in idxd_dmadev_create()
[all …]
H A Didxd_internal.h59 struct idxd_completion *batch_comp_ring; member