| /dpdk/drivers/net/i40e/ |
| H A D | i40e_rxtx_vec_avx512.c | 925 uint32_t copied = 0; in i40e_tx_free_bufs_avx512() local 927 while (copied < n) { in i40e_tx_free_bufs_avx512() 928 const __m512i a = _mm512_load_si512(&txep[copied]); in i40e_tx_free_bufs_avx512() 929 const __m512i b = _mm512_load_si512(&txep[copied + 8]); in i40e_tx_free_bufs_avx512() 930 const __m512i c = _mm512_load_si512(&txep[copied + 16]); in i40e_tx_free_bufs_avx512() 931 const __m512i d = _mm512_load_si512(&txep[copied + 24]); in i40e_tx_free_bufs_avx512() 933 _mm512_storeu_si512(&cache_objs[copied], a); in i40e_tx_free_bufs_avx512() 934 _mm512_storeu_si512(&cache_objs[copied + 8], b); in i40e_tx_free_bufs_avx512() 935 _mm512_storeu_si512(&cache_objs[copied + 16], c); in i40e_tx_free_bufs_avx512() 936 _mm512_storeu_si512(&cache_objs[copied + 24], d); in i40e_tx_free_bufs_avx512() [all …]
|
| /dpdk/drivers/net/ice/ |
| H A D | ice_rxtx_vec_avx512.c | 1020 uint32_t copied = 0; in ice_tx_free_bufs_avx512() local 1022 while (copied < n) { in ice_tx_free_bufs_avx512() 1023 const __m512i a = _mm512_loadu_si512(&txep[copied]); in ice_tx_free_bufs_avx512() 1024 const __m512i b = _mm512_loadu_si512(&txep[copied + 8]); in ice_tx_free_bufs_avx512() 1025 const __m512i c = _mm512_loadu_si512(&txep[copied + 16]); in ice_tx_free_bufs_avx512() 1026 const __m512i d = _mm512_loadu_si512(&txep[copied + 24]); in ice_tx_free_bufs_avx512() 1028 _mm512_storeu_si512(&cache_objs[copied], a); in ice_tx_free_bufs_avx512() 1029 _mm512_storeu_si512(&cache_objs[copied + 8], b); in ice_tx_free_bufs_avx512() 1030 _mm512_storeu_si512(&cache_objs[copied + 16], c); in ice_tx_free_bufs_avx512() 1031 _mm512_storeu_si512(&cache_objs[copied + 24], d); in ice_tx_free_bufs_avx512() [all …]
|
| /dpdk/drivers/net/iavf/ |
| H A D | iavf_rxtx_vec_avx512.c | 1746 uint32_t copied = 0; in iavf_tx_free_bufs_avx512() local 1748 while (copied < n) { in iavf_tx_free_bufs_avx512() 1749 const __m512i a = _mm512_loadu_si512(&txep[copied]); in iavf_tx_free_bufs_avx512() 1750 const __m512i b = _mm512_loadu_si512(&txep[copied + 8]); in iavf_tx_free_bufs_avx512() 1751 const __m512i c = _mm512_loadu_si512(&txep[copied + 16]); in iavf_tx_free_bufs_avx512() 1752 const __m512i d = _mm512_loadu_si512(&txep[copied + 24]); in iavf_tx_free_bufs_avx512() 1754 _mm512_storeu_si512(&cache_objs[copied], a); in iavf_tx_free_bufs_avx512() 1755 _mm512_storeu_si512(&cache_objs[copied + 8], b); in iavf_tx_free_bufs_avx512() 1756 _mm512_storeu_si512(&cache_objs[copied + 16], c); in iavf_tx_free_bufs_avx512() 1757 _mm512_storeu_si512(&cache_objs[copied + 24], d); in iavf_tx_free_bufs_avx512() [all …]
|
| /dpdk/drivers/net/mlx5/ |
| H A D | mlx5_rxtx_vec.c | 208 uint16_t copied = 0; in rxq_copy_mprq_mbuf_v() local 252 pkts[copied++] = elts[i]; in rxq_copy_mprq_mbuf_v() 263 return copied; in rxq_copy_mprq_mbuf_v()
|
| /dpdk/doc/guides/prog_guide/ |
| H A D | ring_lib.rst | 112 First, *ring->prod_head* and ring->cons_tail are copied in local variables. 130 The added object is copied in the ring (obj4). 165 First, ring->cons_head and ring->prod_tail are copied in local variables. 183 The dequeued object (obj1) is copied in the pointer given by the user. 218 On both cores, *ring->prod_head* and ring->cons_tail are copied in local variables.
|
| H A D | ip_fragment_reassembly_lib.rst | 23 Then L3 header is copied from the original mbuf into the 'direct' mbuf and updated to reflect new f…
|
| H A D | generic_segmentation_offload_lib.rst | 83 These headers are copied from the original packet into each output segment.
|
| H A D | lpm_lib.rst | 135 This means the rule is copied to all the entries (as long as they are not in use) which would also …
|
| H A D | lpm6_lib.rst | 148 This means the rule is copied to all the entries (as long as they are not in use) which would also …
|
| /dpdk/doc/guides/sample_app_ug/ |
| H A D | dma.rst | 293 HW copy mode), the copied packets are enqueued to the ``rx_to_tx_ring``, which 297 dequeues copied packets from the ``rx_to_tx_ring``. Then each packet MAC address is changed 320 The metadata in this example is copied from ``rx_descriptor_fields1`` marker of
|
| H A D | kernel_nic_interface.rst | 312 The KNI library automatically frees the mbufs after the kernel successfully copied the mbufs.
|
| /dpdk/drivers/net/thunderx/ |
| H A D | nicvf_ethdev.c | 302 size_t copied; in nicvf_dev_supported_ptypes_get() local 322 copied = sizeof(ptypes_common); in nicvf_dev_supported_ptypes_get() 323 memcpy(ptypes, ptypes_common, copied); in nicvf_dev_supported_ptypes_get() 325 memcpy((char *)ptypes + copied, ptypes_tunnel, in nicvf_dev_supported_ptypes_get() 327 copied += sizeof(ptypes_tunnel); in nicvf_dev_supported_ptypes_get() 330 memcpy((char *)ptypes + copied, &ptypes_end, sizeof(ptypes_end)); in nicvf_dev_supported_ptypes_get()
|
| /dpdk/doc/guides/platform/ |
| H A D | bluefield.rst | 82 They can also be simply copied from the filesystem of a working BlueField platform.
|
| H A D | octeontx.rst | 80 If the kernel and modules are cross-compiled and copied to the target board,
|
| /dpdk/doc/guides/compressdevs/ |
| H A D | isal.rst | 126 * To build with meson, the **libisal.pc** file, must be copied into "pkgconfig",
|
| /dpdk/doc/guides/freebsd_gsg/ |
| H A D | install_from_ports.rst | 78 An example application can therefore be copied to a user's home directory and
|
| /dpdk/doc/guides/nics/ |
| H A D | netvsc.rst | 134 of the VMBus send buffer will be copied; larger packets always have to
|
| H A D | mlx5.rst | 670 packet is mem-copied to a user-provided mbuf if the size of Rx packet is less 764 value, the packet data won't be copied by the driver at all, data buffer 766 data will be copied into WQE. This may improve PCI bandwidth utilization for 788 won't be copied, and data buffer is addressed with pointer. If packet length 789 is less or equal, all packet data will be copied into WQE. This may improve PCI
|
| H A D | ice.rst | 137 The extraction metadata is copied into the registered dynamic mbuf field, and
|
| H A D | dpaa2.rst | 269 a list of pointers to memory where received Ethernet data is to be copied.
|
| /dpdk/doc/guides/contributing/ |
| H A D | documentation.rst | 250 Code can be indented 4 spaces, especially if it is copied from source files. 446 …For example a long command line could be documented like this and still work if copied directly fr…
|
| /dpdk/doc/guides/howto/ |
| H A D | debug_troubleshoot.rst | 419 packets get copied over in RX|TX callback by the secondary process using
|
| /dpdk/doc/guides/rawdevs/ |
| H A D | ioat.rst | 227 pointers if packet data is being copied.
|
| /dpdk/doc/guides/rel_notes/ |
| H A D | release_20_05.rst | 201 their results are then combined and copied into the output buffer. This is
|