| /dpdk/drivers/net/bnxt/ |
| H A D | bnxt_rxtx_vec_sse.c | 32 tmp = _mm_extract_epi32((errors), (pi)); \
74 __m128i t0, t1, flags_type, flags2, index, errors, rss_flags; in descs_to_mbufs() local
113 errors = _mm_srli_epi32(_mm_unpacklo_epi64(t0, t1), 4); in descs_to_mbufs()
114 errors = _mm_and_si128(errors, _mm_set1_epi32(0xF)); in descs_to_mbufs()
115 errors = _mm_and_si128(errors, flags2); in descs_to_mbufs()
117 index = _mm_andnot_si128(errors, flags2); in descs_to_mbufs()
118 errors = _mm_or_si128(errors, _mm_srli_epi32(is_tunnel, 1)); in descs_to_mbufs()
122 GET_OL_FLAGS(rss_flags, index, errors, 0, ol_flags); in descs_to_mbufs()
126 GET_OL_FLAGS(rss_flags, index, errors, 1, ol_flags); in descs_to_mbufs()
130 GET_OL_FLAGS(rss_flags, index, errors, 2, ol_flags); in descs_to_mbufs()
[all …]
|
| H A D | bnxt_rxtx_vec_neon.c | 32 tmp = vgetq_lane_u32((errors), (pi)); \
81 uint32x4_t flags_type, flags2, index, errors, rss_flags; in descs_to_mbufs() local
123 errors = vreinterpretq_u32_u64(vcombine_u64(vget_low_u64(t0), in descs_to_mbufs()
129 errors = vandq_u32(vshrq_n_u32(errors, 4), flags2_error_mask); in descs_to_mbufs()
130 errors = vandq_u32(errors, flags2); in descs_to_mbufs()
132 index = vbicq_u32(flags2, errors); in descs_to_mbufs()
133 errors = vorrq_u32(errors, vshrq_n_u32(is_tunnel, 1)); in descs_to_mbufs()
137 GET_OL_FLAGS(rss_flags, index, errors, 0, ol_flags); in descs_to_mbufs()
140 GET_OL_FLAGS(rss_flags, index, errors, 1, ol_flags); in descs_to_mbufs()
143 GET_OL_FLAGS(rss_flags, index, errors, 2, ol_flags); in descs_to_mbufs()
[all …]
|
| H A D | bnxt_rxtx_vec_avx2.c | 73 __m256i t0, t1, flags_type, flags2, index, errors; in recv_burst_vec_avx2() local
229 errors = _mm256_srli_epi32(errors_v2, 4); in recv_burst_vec_avx2()
230 errors = _mm256_and_si256(errors, _mm256_set1_epi32(0xF)); in recv_burst_vec_avx2()
231 errors = _mm256_and_si256(errors, flags2); in recv_burst_vec_avx2()
233 index = _mm256_andnot_si256(errors, flags2); in recv_burst_vec_avx2()
234 errors = _mm256_or_si256(errors, in recv_burst_vec_avx2()
246 errors = _mm256_i32gather_epi32((int *)rxr->ol_flags_err_table, in recv_burst_vec_avx2()
247 errors, sizeof(uint32_t)); in recv_burst_vec_avx2()
293 ol_flags = _mm256_or_si256(ol_flags, errors); in recv_burst_vec_avx2()
|
| H A D | bnxt_rxr.c | 651 uint16_t flags_type, errors, flags; in bnxt_set_ol_flags() local
664 errors = rte_le_to_cpu_16(rxcmp1->errors_v2) & in bnxt_set_ol_flags()
669 errors = (errors >> 4) & flags; in bnxt_set_ol_flags()
671 ol_flags = rxr->ol_flags_table[flags & ~errors]; in bnxt_set_ol_flags()
673 if (unlikely(errors)) { in bnxt_set_ol_flags()
674 errors |= (flags & RX_PKT_CMPL_FLAGS2_T_IP_CS_CALC) << 2; in bnxt_set_ol_flags()
675 ol_flags |= rxr->ol_flags_err_table[errors]; in bnxt_set_ol_flags()
|
| /dpdk/devtools/ |
| H A D | check-spdx-tag.sh | 7 errors=0
32 errors=$(wc -l < $tmpfile)
69 echo "total: $errors errors, $warnings warnings"
70 exit $errors
|
| /dpdk/doc/guides/nics/ |
| H A D | kni.rst | 131 RX errors 0 dropped 0 overruns 0 frame 0
133 TX errors 0 dropped 0 overruns 0 carrier 0 collisions 0
138 RX errors 0 dropped 0 overruns 0 frame 0
140 TX errors 0 dropped 0 overruns 0 carrier 0 collisions 0
|
| /dpdk/app/test/ |
| H A D | test_dmadev.c | 55 printf("Errors: %"PRIu64"\r", stats.errors); in runtest()
59 if (check_err_stats && stats.errors != 0) in runtest()
371 if (stats.errors != baseline.errors + err_count) in test_failure_in_full_burst()
373 stats.errors, baseline.errors + err_count); in test_failure_in_full_burst()
781 if (stats.completed != 0 || stats.submitted != 0 || stats.errors != 0) in test_dmadev_instance()
784 stats.completed, stats.submitted, stats.errors); in test_dmadev_instance()
|
| /dpdk/drivers/net/avp/ |
| H A D | avp_ethdev.c | 228 uint64_t errors; member
1551 rxq->errors++; in avp_recv_pkts()
1713 txq->errors += nb_pkts; in avp_xmit_scattered_pkts()
1760 txq->errors += orig_nb_pkts; in avp_xmit_scattered_pkts()
1773 txq->errors += orig_nb_pkts; in avp_xmit_scattered_pkts()
1832 txq->errors++; in avp_xmit_pkts()
1855 txq->errors += nb_pkts; in avp_xmit_pkts()
1865 txq->errors++; in avp_xmit_pkts()
1897 txq->errors++; in avp_xmit_pkts()
2280 rxq->errors = 0; in avp_dev_stats_reset()
[all …]
|
| /dpdk/drivers/net/axgbe/ |
| H A D | axgbe_rxtx.h | 93 uint64_t errors; member
145 uint64_t errors; member
|
| /dpdk/drivers/net/virtio/ |
| H A D | virtio_rxtx.c | 1024 rxvq->stats.errors++; in virtio_recv_pkts()
1044 rxvq->stats.errors++; in virtio_recv_pkts()
1127 rxvq->stats.errors++; in virtio_recv_pkts_packed()
1147 rxvq->stats.errors++; in virtio_recv_pkts_packed()
1239 rxvq->stats.errors++; in virtio_recv_pkts_inorder()
1270 rxvq->stats.errors++; in virtio_recv_pkts_inorder()
1333 rxvq->stats.errors++; in virtio_recv_pkts_inorder()
1423 rxvq->stats.errors++; in virtio_recv_mergeable_pkts()
1449 rxvq->stats.errors++; in virtio_recv_mergeable_pkts()
1512 rxvq->stats.errors++; in virtio_recv_mergeable_pkts()
[all …]
|
| H A D | virtio_rxtx.h | 13 uint64_t errors; member
|
| /dpdk/drivers/net/e1000/base/ |
| H A D | e1000_api.h | 124 #define TBI_ACCEPT(a, status, errors, length, last_byte, \ argument
127 (((errors) & E1000_RXD_ERR_FRAME_ERR_MASK) == E1000_RXD_ERR_CE) && \
|
| /dpdk/drivers/dma/hisilicon/ |
| H A D | hisi_dmadev.c | 409 hw->errors = 0; in hisi_dma_start()
445 stats->errors = hw->errors; in hisi_dma_stats_get()
458 hw->errors = 0; in hisi_dma_stats_reset()
578 hw->submitted, hw->completed, hw->errors, hw->qfulls); in hisi_dma_dump()
760 hw->errors += !!status[i]; in hisi_dma_completed_status()
|
| H A D | hisi_dmadev.h | 243 uint64_t errors; member
|
| /dpdk/doc/guides/prog_guide/ |
| H A D | asan.rst | 9 is a widely-used debugging tool to detect memory access errors.
11 overruns in C/C++ programs, and other similar errors, as well as
|
| /dpdk/drivers/net/hinic/ |
| H A D | hinic_pmd_rx.h | 65 u64 errors; member
|
| /dpdk/drivers/net/netvsc/ |
| H A D | hn_rxtx.c | 418 ++txq->stats.errors; in hn_nvs_send_completed()
599 ++rxq->stats.errors; in hn_rxpkt()
621 ++rxq->stats.errors; in hn_rxpkt()
724 ++rxq->stats.errors; in hn_rndis_rx_data()
1204 ++txq->stats.errors; in hn_flush_txagg()
1568 ++txq->stats.errors; in hn_xmit_pkts()
|
| /dpdk/doc/guides/howto/ |
| H A D | debug_troubleshoot.rst | 259 * Isolate if the cause of errors for err_count using ``rte_cryptodev_stats``.
267 * Isolate if the cause of errors for err_count using ``rte_cryptodev_stats``.
438 #. If there are vendor or application specific metadata, check for errors due
443 possible errors in the secondary process where the configuration fails and
|
| /dpdk/drivers/dma/ioat/ |
| H A D | ioat_dmadev.c | 363 ioat->stats.errors); in __dev_dump()
461 ioat->stats.errors += fails; in ioat_completed()
514 ioat->stats.errors += fails; in ioat_completed_status()
|
| /dpdk/lib/ipsec/ |
| H A D | ipsec_telemetry.c | 90 sa->statistics.errors.count); in handle_telemetry_cmd_ipsec_sa_stats()
|
| H A D | sa.h | 141 } errors; member
|
| /dpdk/drivers/vdpa/mlx5/ |
| H A D | mlx5_vdpa.h | 51 uint64_t errors; member
|
| /dpdk/drivers/net/dpaa2/mc/ |
| H A D | fsl_dpdmux_cmd.h | 258 uint32_t errors; member
|
| /dpdk/doc/guides/tools/ |
| H A D | testbbdev.rst | 483 ``OK`` means no errors are expected. Cannot be used with other values.
564 ``OK`` means no errors are expected. Cannot be used with other values.
687 ``OK`` means no errors are expected. Cannot be used with other values.
795 ``OK`` means no errors are expected. Cannot be used with other values.
|
| /dpdk/drivers/dma/cnxk/ |
| H A D | cnxk_dmadev.c | 362 dpivf->stats.errors++; in cnxk_dmadev_completed()
389 dpivf->stats.errors++; in cnxk_dmadev_completed_status()
|