From: Ali Alnubani <alialnu@nvidia.com>
To: Leyi Rong <leyi.rong@intel.com>,
"qi.z.zhang@intel.com" <qi.z.zhang@intel.com>,
"wenzhuo.lu@intel.com" <wenzhuo.lu@intel.com>,
"burce.richardson@intel.com" <burce.richardson@intel.com>
Cc: "dev@dpdk.org" <dev@dpdk.org>,
Bruce Richardson <bruce.richardson@intel.com>
Subject: Re: [dpdk-dev] [PATCH v4 1/3] net/ice: add AVX512 vector path
Date: Tue, 27 Oct 2020 08:42:22 +0000 [thread overview]
Message-ID: <DM6PR12MB461871DFAA1D279933F9356BDA160@DM6PR12MB4618.namprd12.prod.outlook.com> (raw)
In-Reply-To: <DM6PR12MB4618D96B5E5201C6A56CE6ECDA160@DM6PR12MB4618.namprd12.prod.outlook.com>
> -----Original Message-----
> From: dev <dev-bounces@dpdk.org> On Behalf Of Ali Alnubani
> Sent: Tuesday, October 27, 2020 10:33 AM
> To: Leyi Rong <leyi.rong@intel.com>; qi.z.zhang@intel.com;
> wenzhuo.lu@intel.com; burce.richardson@intel.com
> Cc: dev@dpdk.org; Bruce Richardson <bruce.richardson@intel.com>
> Subject: Re: [dpdk-dev] [PATCH v4 1/3] net/ice: add AVX512 vector path
>
> Hi,
>
> > -----Original Message-----
> > From: dev <dev-bounces@dpdk.org> On Behalf Of Leyi Rong
> > Sent: Friday, October 23, 2020 7:14 AM
> > To: qi.z.zhang@intel.com; wenzhuo.lu@intel.com;
> > burce.richardson@intel.com
> > Cc: dev@dpdk.org; Leyi Rong <leyi.rong@intel.com>; Bruce Richardson
> > <bruce.richardson@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.rong@intel.com>
> > Signed-off-by: Bruce Richardson <bruce.richardson@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
next prev parent reply other threads:[~2020-10-27 8:42 UTC|newest]
Thread overview: 25+ messages / expand[flat|nested] mbox.gz Atom feed top
2020-09-10 6:55 [dpdk-dev] [PATCH v1 0/2] AVX512 vPMD on ice Leyi Rong
2020-09-10 6:55 ` [dpdk-dev] [PATCH v1 1/2] net/ice: add AVX512 vector path Leyi Rong
2020-09-10 9:32 ` Bruce Richardson
2020-09-10 6:55 ` [dpdk-dev] [PATCH v1 2/2] net/ice: optimize Tx path on AVX512 vPMD Leyi Rong
2020-09-15 1:17 ` Wang, Haiyue
2020-09-18 3:35 ` [dpdk-dev] [PATCH v2 0/3] AVX512 vPMD on ice Leyi Rong
2020-09-18 3:35 ` [dpdk-dev] [PATCH v2 1/3] net/ice: add AVX512 vector path Leyi Rong
2020-09-18 3:35 ` [dpdk-dev] [PATCH v2 2/3] net/ice: add RSS hash parsing in AVX512 path Leyi Rong
2020-09-18 3:35 ` [dpdk-dev] [PATCH v2 3/3] net/ice: optimize Tx path on AVX512 vPMD Leyi Rong
2020-10-20 10:51 ` [dpdk-dev] [PATCH v3 0/3] AVX512 vPMD on ice Leyi Rong
2020-10-20 10:51 ` [dpdk-dev] [PATCH v3 1/3] net/ice: add AVX512 vector path Leyi Rong
2020-10-20 10:51 ` [dpdk-dev] [PATCH v3 2/3] net/ice: add RSS hash parsing in AVX512 path Leyi Rong
2020-10-20 10:51 ` [dpdk-dev] [PATCH v3 3/3] net/ice: optimize Tx path on AVX512 vPMD Leyi Rong
2020-10-23 4:14 ` [dpdk-dev] [PATCH v4 0/3] AVX512 vPMD on ice Leyi Rong
2020-10-23 4:14 ` [dpdk-dev] [PATCH v4 1/3] net/ice: add AVX512 vector path Leyi Rong
2020-10-25 16:23 ` David Marchand
2020-10-26 7:12 ` Rong, Leyi
2020-10-26 8:09 ` David Marchand
2020-10-27 10:19 ` Bruce Richardson
2020-10-27 10:22 ` Ferruh Yigit
2020-10-27 8:32 ` Ali Alnubani
2020-10-27 8:42 ` Ali Alnubani [this message]
2020-10-23 4:14 ` [dpdk-dev] [PATCH v4 2/3] net/ice: add RSS hash parsing in AVX512 path Leyi Rong
2020-10-23 4:14 ` [dpdk-dev] [PATCH v4 3/3] net/ice: optimize Tx path on AVX512 vPMD Leyi Rong
2020-10-23 9:39 ` [dpdk-dev] [PATCH v4 0/3] AVX512 vPMD on ice Zhang, Qi Z
Reply instructions:
You may reply publicly to this message via plain-text email
using any one of the following methods:
* Save the following mbox file, import it into your mail client,
and reply-to-all from there: mbox
Avoid top-posting and favor interleaved quoting:
https://en.wikipedia.org/wiki/Posting_style#Interleaved_style
* Reply using the --to, --cc, and --in-reply-to
switches of git-send-email(1):
git send-email \
--in-reply-to=DM6PR12MB461871DFAA1D279933F9356BDA160@DM6PR12MB4618.namprd12.prod.outlook.com \
--to=alialnu@nvidia.com \
--cc=bruce.richardson@intel.com \
--cc=burce.richardson@intel.com \
--cc=dev@dpdk.org \
--cc=leyi.rong@intel.com \
--cc=qi.z.zhang@intel.com \
--cc=wenzhuo.lu@intel.com \
/path/to/YOUR_REPLY
https://kernel.org/pub/software/scm/git/docs/git-send-email.html
* If your mail client supports setting the In-Reply-To header
via mailto: links, try the mailto: link
Be sure your reply has a Subject: header at the top and a blank line
before the message body.
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.