From 43840e9d699c52b1d225fb28b0ce6d76cdeb0580 Mon Sep 17 00:00:00 2001 From: Leyi Rong Date: Tue, 15 Oct 2019 15:50:34 +0800 Subject: [PATCH] net/ice: support RSS in AVX path Support 32 bits RSS in FlexMD fields in AVX path. Signed-off-by: Leyi Rong Acked-by: Wenzhuo Lu --- drivers/net/ice/ice_rxtx_vec_avx2.c | 8 ++++---- 1 file changed, 4 insertions(+), 4 deletions(-) diff --git a/drivers/net/ice/ice_rxtx_vec_avx2.c b/drivers/net/ice/ice_rxtx_vec_avx2.c index f32222bb4b..be50677c2f 100644 --- a/drivers/net/ice/ice_rxtx_vec_avx2.c +++ b/drivers/net/ice/ice_rxtx_vec_avx2.c @@ -191,8 +191,8 @@ _ice_recv_raw_pkts_vec_avx2(struct ice_rx_queue *rxq, struct rte_mbuf **rx_pkts, const __m256i shuf_msk = _mm256_set_epi8 (/* first descriptor */ - 0xFF, 0xFF, - 0xFF, 0xFF, /* rss not supported */ + 15, 14, + 13, 12, /* octet 12~15, 32 bits rss */ 11, 10, /* octet 10~11, 16 bits vlan_macip */ 5, 4, /* octet 4~5, 16 bits data_len */ 0xFF, 0xFF, /* skip hi 16 bits pkt_len, zero out */ @@ -200,8 +200,8 @@ _ice_recv_raw_pkts_vec_avx2(struct ice_rx_queue *rxq, struct rte_mbuf **rx_pkts, 0xFF, 0xFF, /* pkt_type set as unknown */ 0xFF, 0xFF, /*pkt_type set as unknown */ /* second descriptor */ - 0xFF, 0xFF, - 0xFF, 0xFF, /* rss not supported */ + 15, 14, + 13, 12, /* octet 12~15, 32 bits rss */ 11, 10, /* octet 10~11, 16 bits vlan_macip */ 5, 4, /* octet 4~5, 16 bits data_len */ 0xFF, 0xFF, /* skip hi 16 bits pkt_len, zero out */ -- 2.20.1