> -----Original Message----- > From: dev <dev-boun...@dpdk.org> On Behalf Of Leyi Rong > Sent: Thursday, September 10, 2020 14:55 > To: Richardson, Bruce <bruce.richard...@intel.com>; Lu, Wenzhuo > <wenzhuo...@intel.com>; Zhang, Qi Z > <qi.z.zh...@intel.com> > Cc: dev@dpdk.org; Rong, Leyi <leyi.r...@intel.com> > Subject: [dpdk-dev] [PATCH v1 2/2] net/ice: optimize Tx path on AVX512 vPMD > > Optimize Tx path by using AVX512 instructions and vectorize the > tx free bufs process. > > Signed-off-by: Leyi Rong <leyi.r...@intel.com> > Signed-off-by: Bruce Richardson <bruce.richard...@intel.com> > --- > drivers/net/ice/ice_rxtx.h | 4 + > drivers/net/ice/ice_rxtx_vec_avx512.c | 147 ++++++++++++++++++++++---- > drivers/net/ice/ice_rxtx_vec_common.h | 36 +++++-- > 3 files changed, 158 insertions(+), 29 deletions(-) >
> - _mm256_set_epi64x > + __m512i desc0_3 = > + _mm512_set_epi64 > (hi_qw3, > pkt[3]->buf_physaddr + pkt[3]->data_off, > hi_qw2, > - pkt[2]->buf_physaddr + pkt[2]->data_off); > - __m256i desc0_1 = > - _mm256_set_epi64x > - (hi_qw1, > + pkt[2]->buf_physaddr + pkt[2]->data_off, > + hi_qw1, > pkt[1]->buf_physaddr + pkt[1]->data_off, > hi_qw0, > pkt[0]->buf_physaddr + pkt[0]->data_off); 'buf_physaddr' will be remove in 20.11, we need to use 'buf_iova' instead. > -- > 2.17.1
