[dpdk-dev] [PATCH 3/3] net/iavf: enable AVX512 for TX

Lu, Wenzhuo wenzhuo.lu at intel.com
Thu Sep 17 03:29:27 CEST 2020


Hi Haiyue,

> -----Original Message-----
> From: Wang, Haiyue <haiyue.wang at intel.com>
> Sent: Tuesday, September 15, 2020 9:17 AM
> To: Lu, Wenzhuo <wenzhuo.lu at intel.com>; dev at dpdk.org
> Cc: Lu, Wenzhuo <wenzhuo.lu at intel.com>; Richardson, Bruce
> <bruce.richardson at intel.com>; Rong, Leyi <leyi.rong at intel.com>
> Subject: RE: [dpdk-dev] [PATCH 3/3] net/iavf: enable AVX512 for TX
> 
> > -----Original Message-----
> > From: dev <dev-bounces at dpdk.org> On Behalf Of Wenzhuo Lu
> > Sent: Thursday, September 10, 2020 13:59
> > To: dev at dpdk.org
> > Cc: Lu, Wenzhuo <wenzhuo.lu at intel.com>; Richardson, Bruce
> > <bruce.richardson at intel.com>; Rong, Leyi <leyi.rong at intel.com>
> > Subject: [dpdk-dev] [PATCH 3/3] net/iavf: enable AVX512 for TX
> >
> > To enhance the per-core performance, this patch adds some AVX512
> > instructions to the data path to handle the TX descriptors.
> >
> > Signed-off-by: Wenzhuo Lu <wenzhuo.lu at intel.com>
> > Signed-off-by: Bruce Richardson <bruce.richardson at intel.com>
> > Signed-off-by: Leyi Rong <leyi.rong at intel.com>
> > ---
> >  doc/guides/rel_notes/release_20_11.rst  |   3 +
> >  drivers/net/iavf/iavf_ethdev.c          |   3 +-
> >  drivers/net/iavf/iavf_rxtx.c            |  32 +++-
> >  drivers/net/iavf/iavf_rxtx.h            |   7 +
> >  drivers/net/iavf/iavf_rxtx_vec_avx512.c | 301
> > ++++++++++++++++++++++++++++++++
> >  5 files changed, 338 insertions(+), 8 deletions(-)
> >
> 
> 
> > +		__m512i desc4 =
> > +			_mm512_set_epi64
> > +				((uint64_t)pkt[3]->data_len,
> > +				 pkt[3]->buf_physaddr,
> 
> 'buf_physaddr' will be remove in 20.11, we need to use 'buf_iova' instead.
Thanks for the reminder. Will change it in V2.


More information about the dev mailing list