Home
last modified time | relevance | path

Searched refs:zero (Results 1 – 25 of 78) sorted by relevance

1234

/dpdk/drivers/net/virtio/
H A Dvirtio_rxtx_simple_altivec.c53 const __vector unsigned char zero = {0}; in virtio_recv_pkts_vec() local
135 pkt_mb[0] = vec_perm(desc[0], zero, shuf_msk1); in virtio_recv_pkts_vec()
136 pkt_mb[1] = vec_perm(desc[0], zero, shuf_msk2); in virtio_recv_pkts_vec()
146 pkt_mb[2] = vec_perm(desc[1], zero, shuf_msk1); in virtio_recv_pkts_vec()
147 pkt_mb[3] = vec_perm(desc[1], zero, shuf_msk2); in virtio_recv_pkts_vec()
157 pkt_mb[4] = vec_perm(desc[2], zero, shuf_msk1); in virtio_recv_pkts_vec()
158 pkt_mb[5] = vec_perm(desc[2], zero, shuf_msk2); in virtio_recv_pkts_vec()
168 pkt_mb[6] = vec_perm(desc[3], zero, shuf_msk1); in virtio_recv_pkts_vec()
169 pkt_mb[7] = vec_perm(desc[3], zero, shuf_msk2); in virtio_recv_pkts_vec()
/dpdk/drivers/net/mlx5/
H A Dmlx5_rxtx_vec_altivec.h173 rxdf1 = vec_perm(mcqe1, zero, shuf_mask1); in rxq_cq_decompress_v()
302 zero, flow_mark_shuf); in rxq_cq_decompress_v()
304 zero, flow_mark_shuf); in rxq_cq_decompress_v()
312 (__vector unsigned int)zero); in rxq_cq_decompress_v()
322 (__vector unsigned int)zero); in rxq_cq_decompress_v()
620 (__vector unsigned int)zero); in rxq_cq_to_ptype_oflags_v()
671 (__vector unsigned int)zero); in rxq_cq_to_ptype_oflags_v()
1098 (__vector unsigned int)zero); in rxq_cq_process_v()
1109 (__vector unsigned int)zero); in rxq_cq_process_v()
1130 (__vector unsigned int)zero); in rxq_cq_process_v()
[all …]
H A Dmlx5_rxtx_vec_sse.h110 const __m128i zero = _mm_setzero_si128(); in rxq_cq_decompress_v() local
111 const __m128i ones = _mm_cmpeq_epi32(zero, zero); in rxq_cq_decompress_v()
183 byte_cnt = _mm_hadd_epi16(byte_cnt, zero); in rxq_cq_decompress_v()
222 _mm_cmpeq_epi32(ftag, zero); in rxq_cq_decompress_v()
387 const __m128i zero = _mm_setzero_si128(); in rxq_cq_to_ptype_oflags_v() local
455 ptype = _mm_packs_epi32(ptype, zero); in rxq_cq_to_ptype_oflags_v()
558 const __m128i zero = _mm_setzero_si128(); in rxq_cq_process_v() local
559 const __m128i ones = _mm_cmpeq_epi32(zero, zero); in rxq_cq_process_v()
709 comp_mask = _mm_packs_epi32(comp_mask, zero); in rxq_cq_process_v()
733 opcode = _mm_packs_epi32(opcode, zero); in rxq_cq_process_v()
[all …]
/dpdk/lib/fib/
H A Ddir24_8_avx512.c19 const __m512i zero = _mm512_set1_epi32(0); in dir24_8_vec_lookup_x16() local
56 idxes = _mm512_mask_i32gather_epi32(zero, msk_ext, in dir24_8_vec_lookup_x16()
60 idxes = _mm512_mask_i32gather_epi32(zero, msk_ext, in dir24_8_vec_lookup_x16()
64 idxes = _mm512_mask_i32gather_epi32(zero, msk_ext, in dir24_8_vec_lookup_x16()
84 const __m512i zero = _mm512_set1_epi32(0); in dir24_8_vec_lookup_x8_8b() local
107 idxes = _mm512_mask_i64gather_epi64(zero, msk_ext, idxes, in dir24_8_vec_lookup_x8_8b()
H A Dtrie_avx512.c74 const __m512i zero = _mm512_set1_epi32(0); in trie_vec_lookup_x16x2() local
165 tmp_1 = _mm512_mask_i32gather_epi32(zero, msk_ext_1, in trie_vec_lookup_x16x2()
167 tmp_2 = _mm512_mask_i32gather_epi32(zero, msk_ext_2, in trie_vec_lookup_x16x2()
172 tmp_1 = _mm512_mask_i32gather_epi32(zero, msk_ext_1, in trie_vec_lookup_x16x2()
174 tmp_2 = _mm512_mask_i32gather_epi32(zero, msk_ext_2, in trie_vec_lookup_x16x2()
220 const __m512i zero = _mm512_set1_epi32(0); in trie_vec_lookup_x8x2_8b() local
281 tmp_1 = _mm512_mask_i64gather_epi64(zero, msk_ext_1, in trie_vec_lookup_x8x2_8b()
283 tmp_2 = _mm512_mask_i64gather_epi64(zero, msk_ext_2, in trie_vec_lookup_x8x2_8b()
/dpdk/lib/acl/
H A Dacl_run_avx512x8.h162 static const uint32_t zero; in _m256_mask_gather_epi8x4() local
165 (uintptr_t)&zero); in _m256_mask_gather_epi8x4()
179 _F_(gather_bytes)(__m256i zero, const __m256i p[2], const uint32_t m[2], in _F_()
189 _mm256_castsi256_si128(zero), in _F_()
192 _mm256_castsi256_si128(zero), in _F_()
H A Dacl_run_avx512x16.h198 static const uint32_t zero; in _m512_mask_gather_epi8x8() local
201 (uintptr_t)&zero); in _m512_mask_gather_epi8x8()
219 _F_(gather_bytes)(__m512i zero, const __m512i p[2], const uint32_t m[2], in _F_()
229 _mm512_castsi512_si256(zero), in _F_()
232 _mm512_castsi512_si256(zero), in _F_()
H A Dacl_run_avx512_common.h140 _T_simd one, zero, t, p[2]; in _F_() local
145 zero = _M_SI_(xor)(one, one); in _F_()
148 t = _M_MGI_(mask_i32gather_epi32)(zero, msk, *di, div, sizeof(div[0])); in _F_()
172 return _F_(gather_bytes)(zero, p, m, bnum); in _F_()
413 const _T_simd zero = _M_I_(set1_epi32)(0); in _F_() local
420 cr = _M_MGI_(mask_i32gather_epi32)(zero, msk, mch, res, sizeof(res[0])); in _F_()
421 cp = _M_MGI_(mask_i32gather_epi32)(zero, msk, mch, pri, sizeof(pri[0])); in _F_()
433 nr = _M_MGI_(mask_i32gather_epi32)(zero, msk, mch, res, in _F_()
435 np = _M_MGI_(mask_i32gather_epi32)(zero, msk, mch, pri, in _F_()
/dpdk/doc/guides/nics/
H A Dmemif.rst49 …"zero-copy=yes", "Enable/disable zero-copy client mode. Only relevant to client, requires '--singl…
102 regions. For no-zero-copy, rings and buffers are stored inside single memory
105 region n (no-zero-copy):
127 last 1024 will belong to S2C ring. In case of zero-copy, buffers are dequeued and
178 Zero-copy client can be enabled with memif configuration option 'zero-copy=yes'. This option
181 for each packet buffer, resulting in worse performance than with zero-copy disabled.
189 Server interface functions the same as with zero-copy disabled.
223 You can also enable ``zero-copy`` on ``client`` interface::
225 …dk-testpmd -l 2-3 --proc-type=primary --file-prefix=pmd2 --vdev=net_memif,zero-copy=yes --single-f…
247 vpp# create interface memif id 0 server no-zero-copy
H A Dnull.rst9 On Rx it returns requested number of empty packets (all zero). On Tx it just frees all sent packets.
H A Daf_xdp.rst52 * For PMD zero copy, it requires kernel version later than v5.4-rc1;
85 per page. In the PMD we report the maximum MTU for zero copy to be equal
134 'busy_budget' vdevarg to zero:
H A Dixgbe.rst133 It returns zero if using nb_pkt < 32 as the expected packet number in the receive handler.
280 UDP with zero checksum is reported as error
286 To support UDP zero checksum, the zero and bad UDP checksum packet is marked as
/dpdk/drivers/net/mlx4/
H A Dmlx4_utils.c54 unsigned int cnt, int zero, int socket) in mlx4_mallocv_inline() argument
83 if (!zero) in mlx4_mallocv_inline()
/dpdk/drivers/common/mlx5/
H A Dmlx5_malloc.c149 mlx5_alloc_align(size_t size, unsigned int align, unsigned int zero) in mlx5_alloc_align() argument
159 if (zero) in mlx5_alloc_align()
/dpdk/drivers/net/mvpp2/
H A Dmrvl_flow.c848 struct rte_ether_addr zero; in mrvl_parse_eth() local
857 memset(&zero, 0, sizeof(zero)); in mrvl_parse_eth()
859 if (memcmp(&mask->dst, &zero, sizeof(mask->dst))) { in mrvl_parse_eth()
865 if (memcmp(&mask->src, &zero, sizeof(mask->src))) { in mrvl_parse_eth()
1038 struct rte_ipv6_hdr zero; in mrvl_parse_ip6() local
1050 memset(&zero, 0, sizeof(zero)); in mrvl_parse_ip6()
1060 zero.src_addr, sizeof(mask->hdr.src_addr))) { in mrvl_parse_ip6()
1067 zero.dst_addr, sizeof(mask->hdr.dst_addr))) { in mrvl_parse_ip6()
/dpdk/drivers/net/ixgbe/
H A Dixgbe_rxtx_vec_neon.c25 uint64x2_t zero = vdupq_n_u64(0); in ixgbe_rxq_rearm() local
40 zero); in ixgbe_rxq_rearm()
61 dma_addr0 = vsetq_lane_u64(paddr, zero, 0); in ixgbe_rxq_rearm()
67 dma_addr1 = vsetq_lane_u64(paddr, zero, 0); in ixgbe_rxq_rearm()
/dpdk/doc/guides/sample_app_ug/
H A Dvhost_crypto.rst34 [--zero-copy]
48 * zero-copy: the presence of this item means the ZERO-COPY feature will be
H A Dvhost.rst149 **--dequeue-zero-copy**
150 Dequeue zero copy will be enabled when this option is given. it is worth to
151 note that if NIC is bound to driver with iommu enabled, dequeue zero copy
H A Dipv4_multicast.rst14 The application demonstrates the use of zero-copy buffers for packet forwarding.
185 This is the most important part of the application since it demonstrates the use of zero- copy buff…
186 …approaches for creating the outgoing packet and although both are based on the data zero-copy idea,
/dpdk/doc/guides/prog_guide/
H A Dtraffic_management.rst82 Each hierarchy node has zero or one private shaper (only one node using it)
83 and/or zero, one or several shared shapers (multiple nodes use the same shaper
93 configured by setting the rate of the committed bucket to zero, which
97 bigger than zero, as well as greater than or equal to the rate of the committed
123 has zero or one private WRED context (only one leaf node using it) and/or zero,
H A Dip_fragment_reassembly_lib.rst15 To avoid copying of the actual packet's data zero-copy technique is used (rte_pktmbuf_attach).
24 Note that for IPv4, header checksum is not recalculated and is set to zero.
H A Dpacket_classif_access_ctrl.rst68 …A zero-based value that represents the position of the field inside the rule; 0 to N-1 for N field…
307 When no rules match, returned value is zero.
327 Setting it to the value greater than zero, instructs rte_acl_build() to:
332 Setting it to zero makes rte_acl_build() to use the default behavior:
534 * For categories 2 and 3, there are no matches, so results[2] and results[3] contain zero,
/dpdk/drivers/net/iavf/
H A Diavf_rxtx_vec_sse.c489 __m128i zero, staterr, sterr_tmp1, sterr_tmp2; in _recv_raw_pkts_vec() local
568 zero = _mm_xor_si128(dd_check, dd_check); in _recv_raw_pkts_vec()
607 staterr = _mm_packs_epi32(staterr, zero); in _recv_raw_pkts_vec()
659 const __m128i zero = _mm_setzero_si128(); in _recv_raw_pkts_vec_flex_rxd() local
902 staterr = _mm_packs_epi32(staterr, zero); in _recv_raw_pkts_vec_flex_rxd()
/dpdk/lib/net/
H A Drte_ip.h327 uint8_t zero; /* zero. */ in rte_ipv4_phdr_cksum() member
336 psd_hdr.zero = 0; in rte_ipv4_phdr_cksum()
/dpdk/drivers/crypto/caam_jr/
H A Dcaam_jr_desc.h156 /* 15 */ unsigned int zero:1; member

1234