Home
last modified time | relevance | path

Searched refs:desc_addr (Results 1 – 19 of 19) sorted by relevance

/dpdk/examples/vhost/
H A Dvirtio_net.c69 uint64_t desc_addr, desc_gaddr; in enqueue_pkt() local
77 desc_addr = rte_vhost_va_from_guest_pa( in enqueue_pkt()
117 desc_addr = rte_vhost_va_from_guest_pa( in enqueue_pkt()
120 if (unlikely(!desc_addr)) in enqueue_pkt()
154 if (unlikely(!desc_addr)) in enqueue_pkt()
165 if (unlikely(!desc_addr)) in enqueue_pkt()
247 uint64_t desc_addr, desc_gaddr; in dequeue_pkt() local
265 if (unlikely(!desc_addr)) in dequeue_pkt()
282 if (unlikely(!desc_addr)) in dequeue_pkt()
319 if (unlikely(!desc_addr)) in dequeue_pkt()
[all …]
/dpdk/drivers/net/virtio/
H A Dvirtio_user_ethdev.c178 uint64_t desc_addr; in virtio_user_setup_queue_packed() local
184 desc_addr = (uintptr_t)vq->vq_ring_virt_mem; in virtio_user_setup_queue_packed()
185 avail_addr = desc_addr + vq->vq_nentries * in virtio_user_setup_queue_packed()
191 vring->desc = (void *)(uintptr_t)desc_addr; in virtio_user_setup_queue_packed()
205 uint64_t desc_addr, avail_addr, used_addr; in virtio_user_setup_queue_split() local
207 desc_addr = (uintptr_t)vq->vq_ring_virt_mem; in virtio_user_setup_queue_split()
208 avail_addr = desc_addr + vq->vq_nentries * sizeof(struct vring_desc); in virtio_user_setup_queue_split()
214 dev->vrings[queue_idx].desc = (void *)(uintptr_t)desc_addr; in virtio_user_setup_queue_split()
H A Dvirtio_rxtx_packed_avx.h152 void *desc_addr; in virtqueue_dequeue_batch_packed_vec() local
167 desc_addr = &vq->vq_packed.ring.desc[id]; in virtqueue_dequeue_batch_packed_vec()
169 __m512i v_desc = _mm512_loadu_si512(desc_addr); in virtqueue_dequeue_batch_packed_vec()
H A Dvirtio_pci.c476 uint64_t desc_addr, avail_addr, used_addr; in modern_setup_queue() local
482 desc_addr = vq->vq_ring_mem; in modern_setup_queue()
483 avail_addr = desc_addr + vq->vq_nentries * sizeof(struct vring_desc); in modern_setup_queue()
490 io_write64_twopart(desc_addr, &dev->common_cfg->queue_desc_lo, in modern_setup_queue()
504 PMD_INIT_LOG(DEBUG, "\t desc_addr: %" PRIx64, desc_addr); in modern_setup_queue()
/dpdk/drivers/crypto/virtio/
H A Dvirtio_pci.c166 uint64_t desc_addr, avail_addr, used_addr; in modern_setup_queue() local
172 desc_addr = vq->vq_ring_mem; in modern_setup_queue()
173 avail_addr = desc_addr + vq->vq_nentries * sizeof(struct vring_desc); in modern_setup_queue()
180 io_write64_twopart(desc_addr, &hw->common_cfg->queue_desc_lo, in modern_setup_queue()
194 VIRTIO_CRYPTO_INIT_LOG_DBG("\t desc_addr: %" PRIx64, desc_addr); in modern_setup_queue()
/dpdk/drivers/net/ena/base/
H A Dena_com.c322 memset(&io_sq->desc_addr, 0x0, sizeof(io_sq->desc_addr)); in ena_com_init_io_sq()
336 io_sq->desc_addr.virt_addr, in ena_com_init_io_sq()
337 io_sq->desc_addr.phys_addr, in ena_com_init_io_sq()
338 io_sq->desc_addr.mem_handle, in ena_com_init_io_sq()
341 if (!io_sq->desc_addr.virt_addr) { in ena_com_init_io_sq()
349 if (!io_sq->desc_addr.virt_addr) { in ena_com_init_io_sq()
953 if (io_sq->desc_addr.virt_addr) { in ena_com_io_queue_free()
958 io_sq->desc_addr.virt_addr, in ena_com_io_queue_free()
962 io_sq->desc_addr.virt_addr = NULL; in ena_com_io_queue_free()
1276 io_sq->desc_addr.phys_addr); in ena_com_create_io_sq()
[all …]
H A Dena_eth_com.c44 return (void *)((uintptr_t)io_sq->desc_addr.virt_addr + offset); in get_sq_desc_regular_queue()
77 ENA_MEMCPY_TO_DEVICE_64(io_sq->desc_addr.pbuf_dev_addr + dst_offset, in ena_com_write_bounce_buffer_to_dev()
H A Dena_com.h143 struct ena_com_io_desc_addr desc_addr; member
/dpdk/drivers/dma/idxd/
H A Didxd_hw_defs.h37 rte_iova_t desc_addr; /* descriptor pointer for batch */ member
H A Didxd_common.c56 .desc_addr = __desc_idx_to_iova(idxd, in __submit()
/dpdk/drivers/raw/ioat/
H A Drte_idxd_rawdev_fns.h56 rte_iova_t desc_addr; /* descriptor pointer for batch */ member
284 .desc_addr = __desc_idx_to_iova(idxd, idxd->batch_start), in __idxd_perform_ops()
/dpdk/drivers/net/ionic/
H A Dionic_rxtx.c346 uint64_t desc_addr = 0, next_addr; in ionic_tx_tso() local
393 desc_addr = rte_cpu_to_le_64(data_iova + offset); in ionic_tx_tso()
402 desc_addr, desc_nsge, desc_len, in ionic_tx_tso()
432 desc_addr = next_addr; in ionic_tx_tso()
443 desc_addr, desc_nsge, desc_len, in ionic_tx_tso()
/dpdk/lib/vhost/
H A Dvhost.c253 uint64_t desc_addr, uint64_t desc_len) in vhost_alloc_copy_ind_table() argument
267 src = vhost_iova_to_vva(dev, vq, desc_addr, &len, in vhost_alloc_copy_ind_table()
278 desc_addr += len; in vhost_alloc_copy_ind_table()
H A Dvirtio_net.c612 uint64_t desc_addr; in map_one_desc() local
618 desc_addr = vhost_iova_to_vva(dev, vq, in map_one_desc()
622 if (unlikely(!desc_addr)) in map_one_desc()
625 rte_prefetch0((void *)(uintptr_t)desc_addr); in map_one_desc()
628 buf_vec[vec_id].buf_addr = desc_addr; in map_one_desc()
H A Dvhost.h802 uint64_t desc_addr, uint64_t desc_len);
/dpdk/drivers/common/mlx5/
H A Dmlx5_devx_cmds.h468 uint64_t desc_addr; member
H A Dmlx5_devx_cmds.c2008 MLX5_SET64(virtio_q, virtctx, desc_addr, attr->desc_addr); in mlx5_devx_cmd_create_virtq()
H A Dmlx5_prm.h3041 u8 desc_addr[0x40]; member
/dpdk/drivers/vdpa/mlx5/
H A Dmlx5_vdpa_virtq.c321 attr.desc_addr = gpa; in mlx5_vdpa_virtq_setup()