* [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 related [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@dpdk.org 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 related [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@dpdk.org 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 an external index of several public inboxes, see mirroring instructions on how to clone and mirror all data and code used by this external index.