mbuf: rename outer IP checksum macro
Rename PKT_RX_EIP_CKSUM_BAD to PKT_RX_OUTER_IP_CKSUM_BAD and deprecate the original name. The new name is better aligned with existing PKT_RX_OUTER_* flags, which should help reduce confusion about its use. Suggested-by: Ferruh Yigit <ferruh.yigit@intel.com> Signed-off-by: Lance Richardson <lance.richardson@broadcom.com> Acked-by: Andrew Rybchenko <andrew.rybchenko@oktetlabs.ru> Acked-by: Ferruh Yigit <ferruh.yigit@intel.com> Acked-by: Ajit Khaparde <ajit.khaparde@broadcom.com>
This commit is contained in:
parent
8312680223
commit
e8a419d6de
@ -864,7 +864,7 @@ pkt_burst_checksum_forward(struct fwd_stream *fs)
|
||||
rx_bad_l4_csum += 1;
|
||||
if (rx_ol_flags & PKT_RX_OUTER_L4_CKSUM_BAD)
|
||||
rx_bad_outer_l4_csum += 1;
|
||||
if (rx_ol_flags & PKT_RX_EIP_CKSUM_BAD)
|
||||
if (rx_ol_flags & PKT_RX_OUTER_IP_CKSUM_BAD)
|
||||
rx_bad_outer_ip_csum += 1;
|
||||
|
||||
/* step 1: dissect packet, parsing optional vlan, ip4/ip6, vxlan
|
||||
|
@ -1620,7 +1620,7 @@ test_get_rx_ol_flag_name(void)
|
||||
VAL_NAME(PKT_RX_IP_CKSUM_BAD),
|
||||
VAL_NAME(PKT_RX_IP_CKSUM_GOOD),
|
||||
VAL_NAME(PKT_RX_IP_CKSUM_NONE),
|
||||
VAL_NAME(PKT_RX_EIP_CKSUM_BAD),
|
||||
VAL_NAME(PKT_RX_OUTER_IP_CKSUM_BAD),
|
||||
VAL_NAME(PKT_RX_VLAN_STRIPPED),
|
||||
VAL_NAME(PKT_RX_IEEE1588_PTP),
|
||||
VAL_NAME(PKT_RX_IEEE1588_TMST),
|
||||
|
@ -612,7 +612,7 @@ Supports inner packet L3 checksum.
|
||||
``mbuf.ol_flags:PKT_TX_OUTER_IP_CKSUM``,
|
||||
``mbuf.ol_flags:PKT_TX_OUTER_IPV4`` | ``PKT_TX_OUTER_IPV6``.
|
||||
* **[uses] mbuf**: ``mbuf.outer_l2_len``, ``mbuf.outer_l3_len``.
|
||||
* **[provides] mbuf**: ``mbuf.ol_flags:PKT_RX_EIP_CKSUM_BAD``.
|
||||
* **[provides] mbuf**: ``mbuf.ol_flags:PKT_RX_OUTER_IP_CKSUM_BAD``.
|
||||
* **[provides] rte_eth_dev_info**: ``rx_offload_capa,rx_queue_offload_capa:DEV_RX_OFFLOAD_OUTER_IPV4_CKSUM``,
|
||||
``tx_offload_capa,tx_queue_offload_capa:DEV_TX_OFFLOAD_OUTER_IPV4_CKSUM``.
|
||||
|
||||
|
@ -113,6 +113,11 @@ Deprecation Notices
|
||||
will be limited to maximum 256 queues.
|
||||
Also compile time flag ``RTE_ETHDEV_QUEUE_STAT_CNTRS`` will be removed.
|
||||
|
||||
* ethdev: The offload flag ``PKT_RX_EIP_CKSUM_BAD`` will be removed and
|
||||
replaced by the new flag ``PKT_RX_OUTER_IP_CKSUM_BAD``. The new name is more
|
||||
consistent with existing outer header checksum status flag naming, which
|
||||
should help in reducing confusion about its usage.
|
||||
|
||||
* sched: To allow more traffic classes, flexible mapping of pipe queues to
|
||||
traffic classes, and subport level configuration of pipes and queues
|
||||
changes will be made to macros, data structures and API functions defined
|
||||
|
@ -434,7 +434,7 @@ octeontx_create_rx_ol_flags_array(void *mem)
|
||||
case OCCTX_ERRLEV_LC:
|
||||
if (errcode == OCCTX_EC_IP4_CSUM) {
|
||||
val |= PKT_RX_IP_CKSUM_BAD;
|
||||
val |= PKT_RX_EIP_CKSUM_BAD;
|
||||
val |= PKT_RX_OUTER_IP_CKSUM_BAD;
|
||||
} else {
|
||||
val |= PKT_RX_IP_CKSUM_GOOD;
|
||||
}
|
||||
|
@ -529,7 +529,7 @@ bnxt_init_ol_flags_tables(struct bnxt_rx_queue *rxq)
|
||||
pt[i] |= PKT_RX_IP_CKSUM_BAD;
|
||||
|
||||
if (i & (RX_PKT_CMPL_ERRORS_T_IP_CS_ERROR >> 4))
|
||||
pt[i] |= PKT_RX_EIP_CKSUM_BAD;
|
||||
pt[i] |= PKT_RX_OUTER_IP_CKSUM_BAD;
|
||||
|
||||
if (i & (RX_PKT_CMPL_ERRORS_L4_CS_ERROR >> 4))
|
||||
pt[i] |= PKT_RX_L4_CKSUM_BAD;
|
||||
|
@ -169,7 +169,7 @@ i40e_rxd_error_to_pkt_flags(uint64_t qword)
|
||||
flags |= PKT_RX_L4_CKSUM_GOOD;
|
||||
|
||||
if (unlikely(error_bits & (1 << I40E_RX_DESC_ERROR_EIPE_SHIFT)))
|
||||
flags |= PKT_RX_EIP_CKSUM_BAD;
|
||||
flags |= PKT_RX_OUTER_IP_CKSUM_BAD;
|
||||
|
||||
return flags;
|
||||
}
|
||||
|
@ -132,10 +132,10 @@ desc_to_olflags_v(vector unsigned long descs[4], struct rte_mbuf **rx_pkts)
|
||||
PKT_RX_IP_CKSUM_BAD,
|
||||
PKT_RX_L4_CKSUM_BAD,
|
||||
PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_BAD,
|
||||
PKT_RX_EIP_CKSUM_BAD,
|
||||
PKT_RX_EIP_CKSUM_BAD | PKT_RX_IP_CKSUM_BAD,
|
||||
PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD,
|
||||
PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD
|
||||
PKT_RX_OUTER_IP_CKSUM_BAD,
|
||||
PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_IP_CKSUM_BAD,
|
||||
PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD,
|
||||
PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD
|
||||
| PKT_RX_IP_CKSUM_BAD,
|
||||
0, 0, 0, 0, 0, 0, 0, 0};
|
||||
|
||||
|
@ -342,13 +342,13 @@ _recv_raw_pkts_vec_avx2(struct i40e_rx_queue *rxq, struct rte_mbuf **rx_pkts,
|
||||
*/
|
||||
const __m256i l3_l4_flags_shuf = _mm256_set_epi8(0, 0, 0, 0, 0, 0, 0, 0,
|
||||
/* shift right 1 bit to make sure it not exceed 255 */
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_GOOD |
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_GOOD |
|
||||
PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_GOOD |
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_GOOD |
|
||||
PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
(PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
@ -356,13 +356,13 @@ _recv_raw_pkts_vec_avx2(struct i40e_rx_queue *rxq, struct rte_mbuf **rx_pkts,
|
||||
(PKT_RX_L4_CKSUM_GOOD | PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
/* second 128-bits */
|
||||
0, 0, 0, 0, 0, 0, 0, 0,
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_GOOD |
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_GOOD |
|
||||
PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_GOOD |
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_GOOD |
|
||||
PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
(PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
@ -372,7 +372,7 @@ _recv_raw_pkts_vec_avx2(struct i40e_rx_queue *rxq, struct rte_mbuf **rx_pkts,
|
||||
const __m256i cksum_mask = _mm256_set1_epi32(
|
||||
PKT_RX_IP_CKSUM_GOOD | PKT_RX_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_GOOD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_EIP_CKSUM_BAD);
|
||||
PKT_RX_OUTER_IP_CKSUM_BAD);
|
||||
|
||||
RTE_SET_USED(avx_aligned); /* for 32B descriptors we don't use this */
|
||||
|
||||
|
@ -337,24 +337,24 @@ _recv_raw_pkts_vec_avx512(struct i40e_rx_queue *rxq, struct rte_mbuf **rx_pkts,
|
||||
const __m256i l3_l4_flags_shuf = _mm256_set_epi8
|
||||
(0, 0, 0, 0, 0, 0, 0, 0,
|
||||
/* shift right 1 bit to make sure it not exceed 255 */
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_EIP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_OUTER_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_BAD) >> 1,
|
||||
PKT_RX_IP_CKSUM_BAD >> 1,
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_GOOD) >> 1,
|
||||
/* second 128-bits */
|
||||
0, 0, 0, 0, 0, 0, 0, 0,
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_EIP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_OUTER_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_BAD) >> 1,
|
||||
PKT_RX_IP_CKSUM_BAD >> 1,
|
||||
@ -363,7 +363,7 @@ _recv_raw_pkts_vec_avx512(struct i40e_rx_queue *rxq, struct rte_mbuf **rx_pkts,
|
||||
const __m256i cksum_mask = _mm256_set1_epi32
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_GOOD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_EIP_CKSUM_BAD);
|
||||
PKT_RX_OUTER_IP_CKSUM_BAD);
|
||||
|
||||
uint16_t i, received;
|
||||
|
||||
|
@ -95,16 +95,16 @@ desc_to_olflags_v(struct i40e_rx_queue *rxq, uint64x2_t descs[4],
|
||||
const uint32x4_t cksum_mask = {
|
||||
PKT_RX_IP_CKSUM_GOOD | PKT_RX_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_GOOD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_EIP_CKSUM_BAD,
|
||||
PKT_RX_OUTER_IP_CKSUM_BAD,
|
||||
PKT_RX_IP_CKSUM_GOOD | PKT_RX_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_GOOD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_EIP_CKSUM_BAD,
|
||||
PKT_RX_OUTER_IP_CKSUM_BAD,
|
||||
PKT_RX_IP_CKSUM_GOOD | PKT_RX_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_GOOD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_EIP_CKSUM_BAD,
|
||||
PKT_RX_OUTER_IP_CKSUM_BAD,
|
||||
PKT_RX_IP_CKSUM_GOOD | PKT_RX_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_GOOD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_EIP_CKSUM_BAD};
|
||||
PKT_RX_OUTER_IP_CKSUM_BAD};
|
||||
|
||||
/* map rss and vlan type to rss hash and vlan flag */
|
||||
const uint8x16_t vlan_flags = {
|
||||
@ -124,11 +124,11 @@ desc_to_olflags_v(struct i40e_rx_queue *rxq, uint64x2_t descs[4],
|
||||
PKT_RX_IP_CKSUM_BAD >> 1,
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_EIP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_OUTER_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
0, 0, 0, 0, 0, 0, 0, 0};
|
||||
|
||||
|
@ -230,16 +230,16 @@ desc_to_olflags_v(struct i40e_rx_queue *rxq, volatile union i40e_rx_desc *rxdp,
|
||||
const __m128i cksum_mask = _mm_set_epi32(
|
||||
PKT_RX_IP_CKSUM_GOOD | PKT_RX_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_GOOD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_EIP_CKSUM_BAD,
|
||||
PKT_RX_OUTER_IP_CKSUM_BAD,
|
||||
PKT_RX_IP_CKSUM_GOOD | PKT_RX_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_GOOD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_EIP_CKSUM_BAD,
|
||||
PKT_RX_OUTER_IP_CKSUM_BAD,
|
||||
PKT_RX_IP_CKSUM_GOOD | PKT_RX_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_GOOD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_EIP_CKSUM_BAD,
|
||||
PKT_RX_OUTER_IP_CKSUM_BAD,
|
||||
PKT_RX_IP_CKSUM_GOOD | PKT_RX_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_GOOD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_EIP_CKSUM_BAD);
|
||||
PKT_RX_OUTER_IP_CKSUM_BAD);
|
||||
|
||||
/* map rss and vlan type to rss hash and vlan flag */
|
||||
const __m128i vlan_flags = _mm_set_epi8(0, 0, 0, 0,
|
||||
@ -254,13 +254,13 @@ desc_to_olflags_v(struct i40e_rx_queue *rxq, volatile union i40e_rx_desc *rxdp,
|
||||
|
||||
const __m128i l3_l4e_flags = _mm_set_epi8(0, 0, 0, 0, 0, 0, 0, 0,
|
||||
/* shift right 1 bit to make sure it not exceed 255 */
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_GOOD |
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_GOOD |
|
||||
PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_GOOD |
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_GOOD |
|
||||
PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
(PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
|
@ -1109,7 +1109,7 @@ iavf_flex_rxd_error_to_pkt_flags(uint16_t stat_err0)
|
||||
flags |= PKT_RX_L4_CKSUM_GOOD;
|
||||
|
||||
if (unlikely(stat_err0 & (1 << IAVF_RX_FLEX_DESC_STATUS0_XSUM_EIPE_S)))
|
||||
flags |= PKT_RX_EIP_CKSUM_BAD;
|
||||
flags |= PKT_RX_OUTER_IP_CKSUM_BAD;
|
||||
|
||||
return flags;
|
||||
}
|
||||
|
@ -264,24 +264,24 @@ _iavf_recv_raw_pkts_vec_avx2(struct iavf_rx_queue *rxq,
|
||||
*/
|
||||
const __m256i l3_l4_flags_shuf = _mm256_set_epi8(0, 0, 0, 0, 0, 0, 0, 0,
|
||||
/* shift right 1 bit to make sure it not exceed 255 */
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_EIP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_OUTER_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_BAD) >> 1,
|
||||
PKT_RX_IP_CKSUM_BAD >> 1,
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_GOOD) >> 1,
|
||||
/* second 128-bits */
|
||||
0, 0, 0, 0, 0, 0, 0, 0,
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_EIP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_OUTER_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_BAD) >> 1,
|
||||
PKT_RX_IP_CKSUM_BAD >> 1,
|
||||
@ -290,7 +290,7 @@ _iavf_recv_raw_pkts_vec_avx2(struct iavf_rx_queue *rxq,
|
||||
const __m256i cksum_mask =
|
||||
_mm256_set1_epi32(PKT_RX_IP_CKSUM_GOOD | PKT_RX_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_GOOD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_EIP_CKSUM_BAD);
|
||||
PKT_RX_OUTER_IP_CKSUM_BAD);
|
||||
|
||||
RTE_SET_USED(avx_aligned); /* for 32B descriptors we don't use this */
|
||||
|
||||
@ -742,13 +742,13 @@ _iavf_recv_raw_pkts_vec_avx2_flex_rxd(struct iavf_rx_queue *rxq,
|
||||
*/
|
||||
const __m256i l3_l4_flags_shuf = _mm256_set_epi8(0, 0, 0, 0, 0, 0, 0, 0,
|
||||
/* shift right 1 bit to make sure it not exceed 255 */
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_GOOD |
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_GOOD |
|
||||
PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_GOOD |
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_GOOD |
|
||||
PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
(PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
@ -756,13 +756,13 @@ _iavf_recv_raw_pkts_vec_avx2_flex_rxd(struct iavf_rx_queue *rxq,
|
||||
(PKT_RX_L4_CKSUM_GOOD | PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
/* second 128-bits */
|
||||
0, 0, 0, 0, 0, 0, 0, 0,
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_GOOD |
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_GOOD |
|
||||
PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_GOOD |
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_GOOD |
|
||||
PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
(PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
@ -771,7 +771,7 @@ _iavf_recv_raw_pkts_vec_avx2_flex_rxd(struct iavf_rx_queue *rxq,
|
||||
const __m256i cksum_mask =
|
||||
_mm256_set1_epi32(PKT_RX_IP_CKSUM_GOOD | PKT_RX_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_GOOD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_EIP_CKSUM_BAD);
|
||||
PKT_RX_OUTER_IP_CKSUM_BAD);
|
||||
/**
|
||||
* data to be shuffled by result of flag mask, shifted down 12.
|
||||
* If RSS(bit12)/VLAN(bit13) are set,
|
||||
|
@ -286,24 +286,24 @@ _iavf_recv_raw_pkts_vec_avx512(struct iavf_rx_queue *rxq,
|
||||
*/
|
||||
const __m256i l3_l4_flags_shuf = _mm256_set_epi8(0, 0, 0, 0, 0, 0, 0, 0,
|
||||
/* shift right 1 bit to make sure it not exceed 255 */
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_EIP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_OUTER_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_BAD) >> 1,
|
||||
PKT_RX_IP_CKSUM_BAD >> 1,
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_GOOD) >> 1,
|
||||
/* second 128-bits */
|
||||
0, 0, 0, 0, 0, 0, 0, 0,
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_EIP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_OUTER_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_BAD) >> 1,
|
||||
PKT_RX_IP_CKSUM_BAD >> 1,
|
||||
@ -312,7 +312,7 @@ _iavf_recv_raw_pkts_vec_avx512(struct iavf_rx_queue *rxq,
|
||||
const __m256i cksum_mask =
|
||||
_mm256_set1_epi32(PKT_RX_IP_CKSUM_GOOD | PKT_RX_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_GOOD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_EIP_CKSUM_BAD);
|
||||
PKT_RX_OUTER_IP_CKSUM_BAD);
|
||||
|
||||
uint16_t i, received;
|
||||
|
||||
@ -758,13 +758,13 @@ _iavf_recv_raw_pkts_vec_avx512_flex_rxd(struct iavf_rx_queue *rxq,
|
||||
*/
|
||||
const __m256i l3_l4_flags_shuf = _mm256_set_epi8(0, 0, 0, 0, 0, 0, 0, 0,
|
||||
/* shift right 1 bit to make sure it not exceed 255 */
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_GOOD |
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_GOOD |
|
||||
PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_GOOD |
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_GOOD |
|
||||
PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
(PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
@ -772,13 +772,13 @@ _iavf_recv_raw_pkts_vec_avx512_flex_rxd(struct iavf_rx_queue *rxq,
|
||||
(PKT_RX_L4_CKSUM_GOOD | PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
/* second 128-bits */
|
||||
0, 0, 0, 0, 0, 0, 0, 0,
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_GOOD |
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_GOOD |
|
||||
PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_GOOD |
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_GOOD |
|
||||
PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
(PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
@ -787,7 +787,7 @@ _iavf_recv_raw_pkts_vec_avx512_flex_rxd(struct iavf_rx_queue *rxq,
|
||||
const __m256i cksum_mask =
|
||||
_mm256_set1_epi32(PKT_RX_IP_CKSUM_GOOD | PKT_RX_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_GOOD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_EIP_CKSUM_BAD);
|
||||
PKT_RX_OUTER_IP_CKSUM_BAD);
|
||||
/**
|
||||
* data to be shuffled by result of flag mask, shifted down 12.
|
||||
* If RSS(bit12)/VLAN(bit13) are set,
|
||||
|
@ -110,16 +110,16 @@ desc_to_olflags_v(struct iavf_rx_queue *rxq, __m128i descs[4],
|
||||
const __m128i cksum_mask = _mm_set_epi32(
|
||||
PKT_RX_IP_CKSUM_GOOD | PKT_RX_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_GOOD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_EIP_CKSUM_BAD,
|
||||
PKT_RX_OUTER_IP_CKSUM_BAD,
|
||||
PKT_RX_IP_CKSUM_GOOD | PKT_RX_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_GOOD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_EIP_CKSUM_BAD,
|
||||
PKT_RX_OUTER_IP_CKSUM_BAD,
|
||||
PKT_RX_IP_CKSUM_GOOD | PKT_RX_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_GOOD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_EIP_CKSUM_BAD,
|
||||
PKT_RX_OUTER_IP_CKSUM_BAD,
|
||||
PKT_RX_IP_CKSUM_GOOD | PKT_RX_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_GOOD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_EIP_CKSUM_BAD);
|
||||
PKT_RX_OUTER_IP_CKSUM_BAD);
|
||||
|
||||
/* map rss and vlan type to rss hash and vlan flag */
|
||||
const __m128i vlan_flags = _mm_set_epi8(0, 0, 0, 0,
|
||||
@ -134,12 +134,12 @@ desc_to_olflags_v(struct iavf_rx_queue *rxq, __m128i descs[4],
|
||||
|
||||
const __m128i l3_l4e_flags = _mm_set_epi8(0, 0, 0, 0, 0, 0, 0, 0,
|
||||
/* shift right 1 bit to make sure it not exceed 255 */
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_EIP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_OUTER_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_BAD) >> 1,
|
||||
PKT_RX_IP_CKSUM_BAD >> 1,
|
||||
@ -227,29 +227,29 @@ flex_desc_to_olflags_v(struct iavf_rx_queue *rxq, __m128i descs[4],
|
||||
|
||||
const __m128i cksum_mask = _mm_set_epi32(PKT_RX_IP_CKSUM_MASK |
|
||||
PKT_RX_L4_CKSUM_MASK |
|
||||
PKT_RX_EIP_CKSUM_BAD,
|
||||
PKT_RX_OUTER_IP_CKSUM_BAD,
|
||||
PKT_RX_IP_CKSUM_MASK |
|
||||
PKT_RX_L4_CKSUM_MASK |
|
||||
PKT_RX_EIP_CKSUM_BAD,
|
||||
PKT_RX_OUTER_IP_CKSUM_BAD,
|
||||
PKT_RX_IP_CKSUM_MASK |
|
||||
PKT_RX_L4_CKSUM_MASK |
|
||||
PKT_RX_EIP_CKSUM_BAD,
|
||||
PKT_RX_OUTER_IP_CKSUM_BAD,
|
||||
PKT_RX_IP_CKSUM_MASK |
|
||||
PKT_RX_L4_CKSUM_MASK |
|
||||
PKT_RX_EIP_CKSUM_BAD);
|
||||
PKT_RX_OUTER_IP_CKSUM_BAD);
|
||||
|
||||
/* map the checksum, rss and vlan fields to the checksum, rss
|
||||
* and vlan flag
|
||||
*/
|
||||
const __m128i cksum_flags = _mm_set_epi8(0, 0, 0, 0, 0, 0, 0, 0,
|
||||
/* shift right 1 bit to make sure it not exceed 255 */
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_GOOD |
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_GOOD |
|
||||
PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_GOOD |
|
||||
(PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_GOOD |
|
||||
PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
(PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
|
@ -1475,7 +1475,7 @@ ice_rxd_error_to_pkt_flags(uint16_t stat_err0)
|
||||
flags |= PKT_RX_L4_CKSUM_GOOD;
|
||||
|
||||
if (unlikely(stat_err0 & (1 << ICE_RX_FLEX_DESC_STATUS0_XSUM_EIPE_S)))
|
||||
flags |= PKT_RX_EIP_CKSUM_BAD;
|
||||
flags |= PKT_RX_OUTER_IP_CKSUM_BAD;
|
||||
|
||||
if (unlikely(stat_err0 & (1 << ICE_RX_FLEX_DESC_STATUS0_XSUM_EUDPE_S)))
|
||||
flags |= PKT_RX_OUTER_L4_CKSUM_BAD;
|
||||
|
@ -258,13 +258,13 @@ _ice_recv_raw_pkts_vec_avx2(struct ice_rx_queue *rxq, struct rte_mbuf **rx_pkts,
|
||||
*/
|
||||
const __m256i l3_l4_flags_shuf =
|
||||
_mm256_set_epi8((PKT_RX_OUTER_L4_CKSUM_BAD >> 20 |
|
||||
PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_BAD >> 20 | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_L4_CKSUM_BAD >> 20 | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_BAD >> 20 | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_L4_CKSUM_BAD >> 20 | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_GOOD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_BAD >> 20 | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_L4_CKSUM_BAD >> 20 | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_GOOD | PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_BAD >> 20 | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
@ -274,13 +274,13 @@ _ice_recv_raw_pkts_vec_avx2(struct ice_rx_queue *rxq, struct rte_mbuf **rx_pkts,
|
||||
PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_BAD >> 20 | PKT_RX_L4_CKSUM_GOOD |
|
||||
PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_GOOD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_GOOD | PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
@ -296,13 +296,13 @@ _ice_recv_raw_pkts_vec_avx2(struct ice_rx_queue *rxq, struct rte_mbuf **rx_pkts,
|
||||
* outer checksum status
|
||||
* shift right 1 bit to make sure it not exceed 255
|
||||
*/
|
||||
(PKT_RX_OUTER_L4_CKSUM_BAD >> 20 | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_L4_CKSUM_BAD >> 20 | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_BAD >> 20 | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_L4_CKSUM_BAD >> 20 | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_BAD >> 20 | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_L4_CKSUM_BAD >> 20 | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_GOOD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_BAD >> 20 | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_L4_CKSUM_BAD >> 20 | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_GOOD | PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_BAD >> 20 | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
@ -312,13 +312,13 @@ _ice_recv_raw_pkts_vec_avx2(struct ice_rx_queue *rxq, struct rte_mbuf **rx_pkts,
|
||||
PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_BAD >> 20 | PKT_RX_L4_CKSUM_GOOD |
|
||||
PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_GOOD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_GOOD | PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
@ -331,7 +331,7 @@ _ice_recv_raw_pkts_vec_avx2(struct ice_rx_queue *rxq, struct rte_mbuf **rx_pkts,
|
||||
const __m256i cksum_mask =
|
||||
_mm256_set1_epi32(PKT_RX_IP_CKSUM_MASK |
|
||||
PKT_RX_L4_CKSUM_MASK |
|
||||
PKT_RX_EIP_CKSUM_BAD |
|
||||
PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_OUTER_L4_CKSUM_MASK);
|
||||
/**
|
||||
* data to be shuffled by result of flag mask, shifted down 12.
|
||||
|
@ -237,13 +237,13 @@ _ice_recv_raw_pkts_vec_avx512(struct ice_rx_queue *rxq,
|
||||
*/
|
||||
const __m256i l3_l4_flags_shuf =
|
||||
_mm256_set_epi8((PKT_RX_OUTER_L4_CKSUM_BAD >> 20 |
|
||||
PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_BAD >> 20 | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_L4_CKSUM_BAD >> 20 | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_BAD >> 20 | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_L4_CKSUM_BAD >> 20 | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_GOOD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_BAD >> 20 | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_L4_CKSUM_BAD >> 20 | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_GOOD | PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_BAD >> 20 | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
@ -253,13 +253,13 @@ _ice_recv_raw_pkts_vec_avx512(struct ice_rx_queue *rxq,
|
||||
PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_BAD >> 20 | PKT_RX_L4_CKSUM_GOOD |
|
||||
PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_GOOD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_GOOD | PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
@ -275,13 +275,13 @@ _ice_recv_raw_pkts_vec_avx512(struct ice_rx_queue *rxq,
|
||||
* outer checksum status
|
||||
* shift right 1 bit to make sure it not exceed 255
|
||||
*/
|
||||
(PKT_RX_OUTER_L4_CKSUM_BAD >> 20 | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_L4_CKSUM_BAD >> 20 | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_BAD >> 20 | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_L4_CKSUM_BAD >> 20 | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_BAD >> 20 | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_L4_CKSUM_BAD >> 20 | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_GOOD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_BAD >> 20 | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_L4_CKSUM_BAD >> 20 | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_GOOD | PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_BAD >> 20 | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
@ -291,13 +291,13 @@ _ice_recv_raw_pkts_vec_avx512(struct ice_rx_queue *rxq,
|
||||
PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_BAD >> 20 | PKT_RX_L4_CKSUM_GOOD |
|
||||
PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_GOOD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_GOOD | PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
@ -310,7 +310,7 @@ _ice_recv_raw_pkts_vec_avx512(struct ice_rx_queue *rxq,
|
||||
const __m256i cksum_mask =
|
||||
_mm256_set1_epi32(PKT_RX_IP_CKSUM_MASK |
|
||||
PKT_RX_L4_CKSUM_MASK |
|
||||
PKT_RX_EIP_CKSUM_BAD |
|
||||
PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_OUTER_L4_CKSUM_MASK);
|
||||
/**
|
||||
* data to be shuffled by result of flag mask, shifted down 12.
|
||||
|
@ -119,32 +119,32 @@ ice_rx_desc_to_olflags_v(struct ice_rx_queue *rxq, __m128i descs[4],
|
||||
const __m128i cksum_mask = _mm_set_epi32(PKT_RX_IP_CKSUM_MASK |
|
||||
PKT_RX_L4_CKSUM_MASK |
|
||||
PKT_RX_OUTER_L4_CKSUM_MASK |
|
||||
PKT_RX_EIP_CKSUM_BAD,
|
||||
PKT_RX_OUTER_IP_CKSUM_BAD,
|
||||
PKT_RX_IP_CKSUM_MASK |
|
||||
PKT_RX_L4_CKSUM_MASK |
|
||||
PKT_RX_OUTER_L4_CKSUM_MASK |
|
||||
PKT_RX_EIP_CKSUM_BAD,
|
||||
PKT_RX_OUTER_IP_CKSUM_BAD,
|
||||
PKT_RX_IP_CKSUM_MASK |
|
||||
PKT_RX_L4_CKSUM_MASK |
|
||||
PKT_RX_OUTER_L4_CKSUM_MASK |
|
||||
PKT_RX_EIP_CKSUM_BAD,
|
||||
PKT_RX_OUTER_IP_CKSUM_BAD,
|
||||
PKT_RX_IP_CKSUM_MASK |
|
||||
PKT_RX_L4_CKSUM_MASK |
|
||||
PKT_RX_OUTER_L4_CKSUM_MASK |
|
||||
PKT_RX_EIP_CKSUM_BAD);
|
||||
PKT_RX_OUTER_IP_CKSUM_BAD);
|
||||
|
||||
/* map the checksum, rss and vlan fields to the checksum, rss
|
||||
* and vlan flag
|
||||
*/
|
||||
const __m128i cksum_flags =
|
||||
_mm_set_epi8((PKT_RX_OUTER_L4_CKSUM_BAD >> 20 |
|
||||
PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_OUTER_IP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_BAD >> 20 | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_L4_CKSUM_BAD >> 20 | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_BAD >> 20 | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_L4_CKSUM_BAD >> 20 | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_GOOD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_BAD >> 20 | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_L4_CKSUM_BAD >> 20 | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_GOOD | PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_BAD >> 20 | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
@ -159,13 +159,13 @@ ice_rx_desc_to_olflags_v(struct ice_rx_queue *rxq, __m128i descs[4],
|
||||
* outer checksum status
|
||||
* shift right 1 bit to make sure it not exceed 255
|
||||
*/
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_GOOD | PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_EIP_CKSUM_BAD |
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_OUTER_IP_CKSUM_BAD |
|
||||
PKT_RX_L4_CKSUM_GOOD | PKT_RX_IP_CKSUM_GOOD) >> 1,
|
||||
(PKT_RX_OUTER_L4_CKSUM_GOOD >> 20 | PKT_RX_L4_CKSUM_BAD |
|
||||
PKT_RX_IP_CKSUM_BAD) >> 1,
|
||||
|
@ -1495,7 +1495,7 @@ rx_desc_error_to_pkt_flags(uint32_t rx_status, uint16_t pkt_info,
|
||||
|
||||
if ((rx_status & IXGBE_RXD_STAT_OUTERIPCS) &&
|
||||
(rx_status & IXGBE_RXDADV_ERR_OUTERIPER)) {
|
||||
pkt_flags |= PKT_RX_EIP_CKSUM_BAD;
|
||||
pkt_flags |= PKT_RX_OUTER_IP_CKSUM_BAD;
|
||||
}
|
||||
|
||||
#ifdef RTE_LIB_SECURITY
|
||||
|
@ -285,7 +285,7 @@ nix_create_rx_ol_flags_array(void *mem)
|
||||
if (errcode == NPC_EC_OIP4_CSUM ||
|
||||
errcode == NPC_EC_IP_FRAG_OFFSET_1) {
|
||||
val |= PKT_RX_IP_CKSUM_BAD;
|
||||
val |= PKT_RX_EIP_CKSUM_BAD;
|
||||
val |= PKT_RX_OUTER_IP_CKSUM_BAD;
|
||||
} else {
|
||||
val |= PKT_RX_IP_CKSUM_GOOD;
|
||||
}
|
||||
|
@ -1632,7 +1632,7 @@ qede_recv_pkts_regular(void *p_rxq, struct rte_mbuf **rx_pkts, uint16_t nb_pkts)
|
||||
"Outer L3 csum failed, flags = 0x%x\n",
|
||||
parse_flag);
|
||||
rxq->rx_hw_errors++;
|
||||
ol_flags |= PKT_RX_EIP_CKSUM_BAD;
|
||||
ol_flags |= PKT_RX_OUTER_IP_CKSUM_BAD;
|
||||
} else {
|
||||
ol_flags |= PKT_RX_IP_CKSUM_GOOD;
|
||||
}
|
||||
@ -1901,7 +1901,7 @@ qede_recv_pkts(void *p_rxq, struct rte_mbuf **rx_pkts, uint16_t nb_pkts)
|
||||
"Outer L3 csum failed, flags = 0x%x\n",
|
||||
parse_flag);
|
||||
rxq->rx_hw_errors++;
|
||||
ol_flags |= PKT_RX_EIP_CKSUM_BAD;
|
||||
ol_flags |= PKT_RX_OUTER_IP_CKSUM_BAD;
|
||||
} else {
|
||||
ol_flags |= PKT_RX_IP_CKSUM_GOOD;
|
||||
}
|
||||
|
@ -305,7 +305,7 @@ sfc_ef100_rx_class_decode(const efx_word_t class, uint64_t *ol_flags)
|
||||
break;
|
||||
case ESE_GZ_RH_HCLASS_L3_CLASS_IP4BAD:
|
||||
ptype |= RTE_PTYPE_L3_IPV4_EXT_UNKNOWN;
|
||||
*ol_flags |= PKT_RX_EIP_CKSUM_BAD;
|
||||
*ol_flags |= PKT_RX_OUTER_IP_CKSUM_BAD;
|
||||
break;
|
||||
case ESE_GZ_RH_HCLASS_L3_CLASS_IP6:
|
||||
ptype |= RTE_PTYPE_L3_IPV6_EXT_UNKNOWN;
|
||||
|
@ -76,7 +76,7 @@ sfc_ef10_rx_ev_to_offloads(const efx_qword_t rx_ev, struct rte_mbuf *m,
|
||||
l4_csum_err_bit = ESF_EZ_RX_TCP_UDP_INNER_CHKSUM_ERR_LBN;
|
||||
if (unlikely(EFX_TEST_QWORD_BIT(rx_ev,
|
||||
ESF_DZ_RX_IPCKSUM_ERR_LBN)))
|
||||
ol_flags |= PKT_RX_EIP_CKSUM_BAD;
|
||||
ol_flags |= PKT_RX_OUTER_IP_CKSUM_BAD;
|
||||
}
|
||||
|
||||
switch (EFX_QWORD_FIELD(rx_ev, ESF_DZ_RX_ETH_TAG_CLASS)) {
|
||||
|
@ -1134,7 +1134,7 @@ rx_desc_error_to_pkt_flags(uint32_t rx_status)
|
||||
|
||||
if (rx_status & TXGBE_RXD_STAT_EIPCS &&
|
||||
rx_status & TXGBE_RXD_ERR_EIPCS) {
|
||||
pkt_flags |= PKT_RX_EIP_CKSUM_BAD;
|
||||
pkt_flags |= PKT_RX_OUTER_IP_CKSUM_BAD;
|
||||
}
|
||||
|
||||
#ifdef RTE_LIB_SECURITY
|
||||
|
@ -755,7 +755,7 @@ const char *rte_get_rx_ol_flag_name(uint64_t mask)
|
||||
case PKT_RX_IP_CKSUM_BAD: return "PKT_RX_IP_CKSUM_BAD";
|
||||
case PKT_RX_IP_CKSUM_GOOD: return "PKT_RX_IP_CKSUM_GOOD";
|
||||
case PKT_RX_IP_CKSUM_NONE: return "PKT_RX_IP_CKSUM_NONE";
|
||||
case PKT_RX_EIP_CKSUM_BAD: return "PKT_RX_EIP_CKSUM_BAD";
|
||||
case PKT_RX_OUTER_IP_CKSUM_BAD: return "PKT_RX_OUTER_IP_CKSUM_BAD";
|
||||
case PKT_RX_VLAN_STRIPPED: return "PKT_RX_VLAN_STRIPPED";
|
||||
case PKT_RX_IEEE1588_PTP: return "PKT_RX_IEEE1588_PTP";
|
||||
case PKT_RX_IEEE1588_TMST: return "PKT_RX_IEEE1588_TMST";
|
||||
@ -799,7 +799,7 @@ rte_get_rx_ol_flag_list(uint64_t mask, char *buf, size_t buflen)
|
||||
{ PKT_RX_IP_CKSUM_NONE, PKT_RX_IP_CKSUM_MASK, NULL },
|
||||
{ PKT_RX_IP_CKSUM_UNKNOWN, PKT_RX_IP_CKSUM_MASK,
|
||||
"PKT_RX_IP_CKSUM_UNKNOWN" },
|
||||
{ PKT_RX_EIP_CKSUM_BAD, PKT_RX_EIP_CKSUM_BAD, NULL },
|
||||
{ PKT_RX_OUTER_IP_CKSUM_BAD, PKT_RX_OUTER_IP_CKSUM_BAD, NULL },
|
||||
{ PKT_RX_VLAN_STRIPPED, PKT_RX_VLAN_STRIPPED, NULL },
|
||||
{ PKT_RX_IEEE1588_PTP, PKT_RX_IEEE1588_PTP, NULL },
|
||||
{ PKT_RX_IEEE1588_TMST, PKT_RX_IEEE1588_TMST, NULL },
|
||||
|
@ -73,8 +73,17 @@ extern "C" {
|
||||
*/
|
||||
#define PKT_RX_IP_CKSUM_BAD (1ULL << 4)
|
||||
|
||||
/** External IP header checksum error. */
|
||||
#define PKT_RX_EIP_CKSUM_BAD (1ULL << 5)
|
||||
/**
|
||||
* This flag is set when the outermost IP header checksum is detected as
|
||||
* wrong by the hardware.
|
||||
*/
|
||||
#define PKT_RX_OUTER_IP_CKSUM_BAD (1ULL << 5)
|
||||
|
||||
/**
|
||||
* Deprecated.
|
||||
* This flag has been renamed, use PKT_RX_OUTER_IP_CKSUM_BAD instead.
|
||||
*/
|
||||
#define PKT_RX_EIP_CKSUM_BAD PKT_RX_OUTER_IP_CKSUM_BAD
|
||||
|
||||
/**
|
||||
* A vlan has been stripped by the hardware and its tci is saved in
|
||||
|
Loading…
Reference in New Issue
Block a user