From: Leyi Rong Date: Tue, 15 Oct 2019 07:50:34 +0000 (+0800) Subject: net/ice: support RSS in AVX path X-Git-Url: http://git.droids-corp.org/?a=commitdiff_plain;h=43840e9d699c52b1d225fb28b0ce6d76cdeb0580;p=dpdk.git 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 --- 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 */