* [dpdk-dev] [PATCH 0/2] add RSS support in ice vector path
@ 2019-10-15 7:50 Leyi Rong
2019-10-15 7:50 ` [dpdk-dev] [PATCH 1/2] net/ice: add RSS support in SSE path Leyi Rong
` (2 more replies)
0 siblings, 3 replies; 6+ messages in thread
From: Leyi Rong @ 2019-10-15 7:50 UTC (permalink / raw)
To: wenzhuo.lu, qi.z.zhang, xiaolong.ye; +Cc: dev, Leyi Rong
This patchset support 32 bits RSS in FlexMD fields in
ice vector path, both SSE and AVX paths.
Leyi Rong (2):
net/ice: add RSS support in SSE path
net/ice: add RSS support in AVX path
drivers/net/ice/ice_rxtx_vec_avx2.c | 8 ++++----
drivers/net/ice/ice_rxtx_vec_sse.c | 2 +-
2 files changed, 5 insertions(+), 5 deletions(-)
--
2.17.1
^ permalink raw reply [flat|nested] 6+ messages in thread* [dpdk-dev] [PATCH 1/2] net/ice: add RSS support in SSE path 2019-10-15 7:50 [dpdk-dev] [PATCH 0/2] add RSS support in ice vector path Leyi Rong @ 2019-10-15 7:50 ` Leyi Rong 2019-10-16 6:02 ` Lu, Wenzhuo 2019-10-15 7:50 ` [dpdk-dev] [PATCH 2/2] net/ice: add RSS support in AVX path Leyi Rong 2019-10-16 6:30 ` [dpdk-dev] [PATCH 0/2] add RSS support in ice vector path Ye Xiaolong 2 siblings, 1 reply; 6+ messages in thread From: Leyi Rong @ 2019-10-15 7:50 UTC (permalink / raw) To: wenzhuo.lu, qi.z.zhang, xiaolong.ye; +Cc: dev, Leyi Rong Support 32 bits RSS in FlexMD fields in SSE path. Signed-off-by: Leyi Rong <leyi.rong@intel.com> --- drivers/net/ice/ice_rxtx_vec_sse.c | 2 +- 1 file changed, 1 insertion(+), 1 deletion(-) diff --git a/drivers/net/ice/ice_rxtx_vec_sse.c b/drivers/net/ice/ice_rxtx_vec_sse.c index 2ae9370f4..9d5f1f194 100644 --- a/drivers/net/ice/ice_rxtx_vec_sse.c +++ b/drivers/net/ice/ice_rxtx_vec_sse.c @@ -230,7 +230,7 @@ _ice_recv_raw_pkts_vec(struct ice_rx_queue *rxq, struct rte_mbuf **rx_pkts, const __m128i zero = _mm_setzero_si128(); /* mask to shuffle from desc. to mbuf */ const __m128i shuf_msk = _mm_set_epi8 - (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 high 16 bits pkt_len, zero out */ -- 2.17.1 ^ permalink raw reply [flat|nested] 6+ messages in thread
* Re: [dpdk-dev] [PATCH 1/2] net/ice: add RSS support in SSE path 2019-10-15 7:50 ` [dpdk-dev] [PATCH 1/2] net/ice: add RSS support in SSE path Leyi Rong @ 2019-10-16 6:02 ` Lu, Wenzhuo 0 siblings, 0 replies; 6+ messages in thread From: Lu, Wenzhuo @ 2019-10-16 6:02 UTC (permalink / raw) To: Rong, Leyi, Zhang, Qi Z, Ye, Xiaolong; +Cc: dev Hi, > -----Original Message----- > From: Rong, Leyi > Sent: Tuesday, October 15, 2019 3:51 PM > To: Lu, Wenzhuo <wenzhuo.lu@intel.com>; Zhang, Qi Z > <qi.z.zhang@intel.com>; Ye, Xiaolong <xiaolong.ye@intel.com> > Cc: dev@dpdk.org; Rong, Leyi <leyi.rong@intel.com> > Subject: [PATCH 1/2] net/ice: add RSS support in SSE path > > Support 32 bits RSS in FlexMD fields in SSE path. > > Signed-off-by: Leyi Rong <leyi.rong@intel.com> Acked-by: Wenzhuo Lu <wenzhuo.lu@intel.com> ^ permalink raw reply [flat|nested] 6+ messages in thread
* [dpdk-dev] [PATCH 2/2] net/ice: add RSS support in AVX path 2019-10-15 7:50 [dpdk-dev] [PATCH 0/2] add RSS support in ice vector path Leyi Rong 2019-10-15 7:50 ` [dpdk-dev] [PATCH 1/2] net/ice: add RSS support in SSE path Leyi Rong @ 2019-10-15 7:50 ` Leyi Rong 2019-10-16 6:03 ` Lu, Wenzhuo 2019-10-16 6:30 ` [dpdk-dev] [PATCH 0/2] add RSS support in ice vector path Ye Xiaolong 2 siblings, 1 reply; 6+ messages in thread From: Leyi Rong @ 2019-10-15 7:50 UTC (permalink / raw) To: wenzhuo.lu, qi.z.zhang, xiaolong.ye; +Cc: dev, Leyi Rong Support 32 bits RSS in FlexMD fields in AVX path. Signed-off-by: Leyi Rong <leyi.rong@intel.com> --- 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 f32222bb4..be50677c2 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.17.1 ^ permalink raw reply [flat|nested] 6+ messages in thread
* Re: [dpdk-dev] [PATCH 2/2] net/ice: add RSS support in AVX path 2019-10-15 7:50 ` [dpdk-dev] [PATCH 2/2] net/ice: add RSS support in AVX path Leyi Rong @ 2019-10-16 6:03 ` Lu, Wenzhuo 0 siblings, 0 replies; 6+ messages in thread From: Lu, Wenzhuo @ 2019-10-16 6:03 UTC (permalink / raw) To: Rong, Leyi, Zhang, Qi Z, Ye, Xiaolong; +Cc: dev Hi, > -----Original Message----- > From: Rong, Leyi > Sent: Tuesday, October 15, 2019 3:51 PM > To: Lu, Wenzhuo <wenzhuo.lu@intel.com>; Zhang, Qi Z > <qi.z.zhang@intel.com>; Ye, Xiaolong <xiaolong.ye@intel.com> > Cc: dev@dpdk.org; Rong, Leyi <leyi.rong@intel.com> > Subject: [PATCH 2/2] net/ice: add RSS support in AVX path > > Support 32 bits RSS in FlexMD fields in AVX path. > > Signed-off-by: Leyi Rong <leyi.rong@intel.com> Acked-by: Wenzhuo Lu <wenzhuo.lu@intel.com> ^ permalink raw reply [flat|nested] 6+ messages in thread
* Re: [dpdk-dev] [PATCH 0/2] add RSS support in ice vector path 2019-10-15 7:50 [dpdk-dev] [PATCH 0/2] add RSS support in ice vector path Leyi Rong 2019-10-15 7:50 ` [dpdk-dev] [PATCH 1/2] net/ice: add RSS support in SSE path Leyi Rong 2019-10-15 7:50 ` [dpdk-dev] [PATCH 2/2] net/ice: add RSS support in AVX path Leyi Rong @ 2019-10-16 6:30 ` Ye Xiaolong 2 siblings, 0 replies; 6+ messages in thread From: Ye Xiaolong @ 2019-10-16 6:30 UTC (permalink / raw) To: Leyi Rong; +Cc: wenzhuo.lu, qi.z.zhang, dev On 10/15, Leyi Rong wrote: >This patchset support 32 bits RSS in FlexMD fields in >ice vector path, both SSE and AVX paths. > >Leyi Rong (2): > net/ice: add RSS support in SSE path > net/ice: add RSS support in AVX path > > drivers/net/ice/ice_rxtx_vec_avx2.c | 8 ++++---- > drivers/net/ice/ice_rxtx_vec_sse.c | 2 +- > 2 files changed, 5 insertions(+), 5 deletions(-) > >-- >2.17.1 > Series applied to dpdk-next-net-intel. ^ permalink raw reply [flat|nested] 6+ messages in thread
end of thread, other threads:[~2019-10-16 6:33 UTC | newest] Thread overview: 6+ messages (download: mbox.gz / follow: Atom feed) -- links below jump to the message on this page -- 2019-10-15 7:50 [dpdk-dev] [PATCH 0/2] add RSS support in ice vector path Leyi Rong 2019-10-15 7:50 ` [dpdk-dev] [PATCH 1/2] net/ice: add RSS support in SSE path Leyi Rong 2019-10-16 6:02 ` Lu, Wenzhuo 2019-10-15 7:50 ` [dpdk-dev] [PATCH 2/2] net/ice: add RSS support in AVX path Leyi Rong 2019-10-16 6:03 ` Lu, Wenzhuo 2019-10-16 6:30 ` [dpdk-dev] [PATCH 0/2] add RSS support in ice vector path Ye Xiaolong
This is a public inbox, see mirroring instructions for how to clone and mirror all data and code used for this inbox; as well as URLs for NNTP newsgroup(s).