[dpdk-dev] [PATCH v1 2/2] net/ice: optimize Tx path on AVX512 vPMD

[Wang, Haiyue]

> -----Original Message-----
> From: dev <dev-bounces at dpdk.org> On Behalf Of Leyi Rong
> Sent: Thursday, September 10, 2020 14:55
> To: Richardson, Bruce <bruce.richardson at intel.com>; Lu, Wenzhuo <wenzhuo.lu at intel.com>; Zhang, Qi Z
> <qi.z.zhang at intel.com>
> Cc: dev at dpdk.org; Rong, Leyi <leyi.rong at 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.rong at intel.com>
> Signed-off-by: Bruce Richardson <bruce.richardson at 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