> -----Original Message----- > From: dev <dev-boun...@dpdk.org> On Behalf Of Ali Alnubani > Sent: Tuesday, October 27, 2020 10:33 AM > To: Leyi Rong <leyi.r...@intel.com>; qi.z.zh...@intel.com; > wenzhuo...@intel.com; burce.richard...@intel.com > Cc: dev@dpdk.org; Bruce Richardson <bruce.richard...@intel.com> > Subject: Re: [dpdk-dev] [PATCH v4 1/3] net/ice: add AVX512 vector path > > Hi, > > > -----Original Message----- > > From: dev <dev-boun...@dpdk.org> On Behalf Of Leyi Rong > > Sent: Friday, October 23, 2020 7:14 AM > > To: qi.z.zh...@intel.com; wenzhuo...@intel.com; > > burce.richard...@intel.com > > Cc: dev@dpdk.org; Leyi Rong <leyi.r...@intel.com>; Bruce Richardson > > <bruce.richard...@intel.com> > > Subject: [dpdk-dev] [PATCH v4 1/3] net/ice: add AVX512 vector path > > > > Add AVX512 support for ice PMD. This patch adds ice_rxtx_vec_avx512.c > > to support ice AVX512 vPMD. > > > > This patch aims to enable AVX512 on ice vPMD. Main changes are focus > > on Rx path compared with AVX2 vPMD. > > > > Signed-off-by: Leyi Rong <leyi.r...@intel.com> > > Signed-off-by: Bruce Richardson <bruce.richard...@intel.com> > > --- > > This patch is causing the following build failure on CentOS 7 with gcc 4.8.5: > > """ > drivers/librte_net_ice.a(net_ice_ice_rxtx.c.o): In function > `ice_set_rx_function': > drivers/net/ice/ice_rxtx.c:3034: undefined reference to > `ice_recv_scattered_pkts_vec_avx512' > drivers/net/ice/ice_rxtx.c:3050: undefined reference to > `ice_recv_pkts_vec_avx512' > drivers/librte_net_ice.a(net_ice_ice_rxtx.c.o): In function > `ice_set_tx_function': > drivers/net/ice/ice_rxtx.c:3243: undefined reference to > `ice_xmit_pkts_vec_avx512' > """ > > It reproduces when building with "meson --werror --buildtype=debug build > && ninja -C build". >
It's also causing the following build failure on Ubuntu 18.04 (gcc 7.5.0) and on OpenSUSE Leap 15.2 (gcc 7.5.0): """ drivers/net/ice/ice_rxtx_vec_avx512.c: In function '_ice_recv_raw_pkts_vec_avx512': /usr/lib/gcc/x86_64-linux-gnu/7/include/avx512bwintrin.h:1831:1: error: inlining failed in call to always_inline '_mm512_shuffle_epi8': target specific option mismatch _mm512_shuffle_epi8 (__m512i __A, __m512i __B) ^~~~~~~~~~~~~~~~~~~ drivers/net/ice/ice_rxtx_vec_avx512.c:350:11: note: called from here __m512i mb0_3 = _mm512_shuffle_epi8(raw_desc0_3, shuf_msk); ^~~~~ """ Regards, Ali