From mboxrd@z Thu Jan 1 00:00:00 1970 Return-Path: Received: from dpdk.org (dpdk.org [92.243.14.124]) by inbox.dpdk.org (Postfix) with ESMTP id 0B4ABA04B5; Tue, 27 Oct 2020 09:42:33 +0100 (CET) Received: from [92.243.14.124] (localhost [127.0.0.1]) by dpdk.org (Postfix) with ESMTP id A32FB2BDB; Tue, 27 Oct 2020 09:42:31 +0100 (CET) Received: from hqnvemgate26.nvidia.com (hqnvemgate26.nvidia.com [216.228.121.65]) by dpdk.org (Postfix) with ESMTP id BD78B2BD5 for ; Tue, 27 Oct 2020 09:42:28 +0100 (CET) Received: from hqmail.nvidia.com (Not Verified[216.228.121.13]) by hqnvemgate26.nvidia.com (using TLS: TLSv1.2, AES256-SHA) id ; Tue, 27 Oct 2020 01:42:07 -0700 Received: from HQMAIL101.nvidia.com (172.20.187.10) by HQMAIL111.nvidia.com (172.20.187.18) with Microsoft SMTP Server (TLS) id 15.0.1473.3; Tue, 27 Oct 2020 08:42:24 +0000 Received: from NAM10-BN7-obe.outbound.protection.outlook.com (104.47.70.108) by HQMAIL101.nvidia.com (172.20.187.10) with Microsoft SMTP Server (TLS) id 15.0.1473.3 via Frontend Transport; Tue, 27 Oct 2020 08:42:24 +0000 ARC-Seal: i=1; a=rsa-sha256; s=arcselector9901; d=microsoft.com; cv=none; b=Pl6+NIK0+n5CYkArfZjl+kgkNXhjFgK0tUcmyYyxaCaJnDrhvdJ9UELae+RbjQu31P+S3MJS7HQsDW7C+GpuZ3mGbiDWSyeJrtvNDjOssaXzVY2qEReR9DZwwd6D8WaoHVqkBkyRgJiuyRvvCHExx7Z6KKkHpTm5kvTxDUIH8/38a4Q8dGkG1HOKUXof0SOigjOUAbmB+mZlvH4CYDM8XmaMY5+nEzWEPjgcaUkHxApmr8QvEc2ZULViIaQEsDSwvo24Xoyutm6zI2m+NT2jmSt62ZQNXD2KF3WisZhpKTu2hxUxZO3tWJXYHrtwsh7T/f3Xx+4Iaxes/7d8TwIH4A== ARC-Message-Signature: i=1; a=rsa-sha256; c=relaxed/relaxed; d=microsoft.com; s=arcselector9901; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-SenderADCheck; bh=2d2y6XVxLm0cOMgZ6+VsbcQhWqS1vnvTBeCXvQc+OOY=; b=auvSU+yNnpyFjr7Ki3bT9qYmId59aE+mgA6YwyF5uEvPvbGI/CRsfTEKBoxSPSJ9J9wWo6U/gq/Rxo9TSHLLamJkb1IOwrrXlR9+kcub31oE1dYHU5RnBdz6rB7yR/K+4uBXA04cIKoUww6gDyFToHa0yvsBjlxkHksXDEiCqHWddEZE+1cTHD+H4d7WfOLjZjsfuA7pMbxkp2JEv7fB3YhetxSzaNSgB9qo2oyJ6L9/m2HxIN9pGrk5vLMIjb4iylMSOk0mlZdXcuMmYkguemJOxb5/nW6GGx3bb/+OfPAkakJXtnsvjag3PtycXTmI6yxvib1b5Jsvup8xqgODiA== ARC-Authentication-Results: i=1; mx.microsoft.com 1; spf=pass smtp.mailfrom=nvidia.com; dmarc=pass action=none header.from=nvidia.com; dkim=pass header.d=nvidia.com; arc=none Received: from DM6PR12MB4618.namprd12.prod.outlook.com (2603:10b6:5:78::20) by DM6PR12MB4041.namprd12.prod.outlook.com (2603:10b6:5:210::18) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.3477.20; Tue, 27 Oct 2020 08:42:22 +0000 Received: from DM6PR12MB4618.namprd12.prod.outlook.com ([fe80::b5e2:e8fc:9e81:6c09]) by DM6PR12MB4618.namprd12.prod.outlook.com ([fe80::b5e2:e8fc:9e81:6c09%6]) with mapi id 15.20.3477.028; Tue, 27 Oct 2020 08:42:22 +0000 From: Ali Alnubani To: Leyi Rong , "qi.z.zhang@intel.com" , "wenzhuo.lu@intel.com" , "burce.richardson@intel.com" CC: "dev@dpdk.org" , Bruce Richardson Thread-Topic: [dpdk-dev] [PATCH v4 1/3] net/ice: add AVX512 vector path Thread-Index: AQHWqPZB4CV7PxTd6UCaZh65JChxoqmrIvvggAAEXgA= Date: Tue, 27 Oct 2020 08:42:22 +0000 Message-ID: References: <20200910065504.104217-1-leyi.rong@intel.com> <20201023041407.20442-1-leyi.rong@intel.com> <20201023041407.20442-2-leyi.rong@intel.com> In-Reply-To: Accept-Language: en-US Content-Language: en-US X-MS-Has-Attach: X-MS-TNEF-Correlator: authentication-results: intel.com; dkim=none (message not signed) header.d=none;intel.com; dmarc=none action=none header.from=nvidia.com; x-originating-ip: [212.29.221.74] x-ms-publictraffictype: Email x-ms-office365-filtering-correlation-id: df7d6a7c-fa7f-4041-77fb-08d87a543933 x-ms-traffictypediagnostic: DM6PR12MB4041: x-microsoft-antispam-prvs: x-ms-oob-tlc-oobclassifiers: OLM:1227; x-ms-exchange-senderadcheck: 1 x-microsoft-antispam: BCL:0; x-microsoft-antispam-message-info: 3plV9Dxjt5cPPofxqTfXML6YtygKfTG9xYRLIL2WsmyFz7c8CPOrfMXIu0ECF/GiokprLmKnn80zmk/6TbQtnxmQPh9AjGc3S8/SClKrpcS+7pUl+AkzHvZNyr4P3mqkOUfkD0bC/dm2SOW8AwGMICKmNc/LyEX95HZSCMK8cdVzqFZ3ovaUyrMUg4KmjcG2LlRmJt6n0i2lP8XSAgPbR2PRcX2jLm/aEViyuZ11D6ewKoO1wcqv1lOU2itd52kn3qYgH9qBCSchOdtKEDIaq97fUk+NUoTrH/H3W1lNdfH7ltaDaMcWaYziyzI6Wf+2z4Rq/Ph79gXkZhOqSDAluQ== x-forefront-antispam-report: CIP:255.255.255.255; CTRY:; LANG:en; SCL:1; SRV:; IPV:NLI; SFV:NSPM; H:DM6PR12MB4618.namprd12.prod.outlook.com; PTR:; CAT:NONE; SFS:(4636009)(396003)(376002)(346002)(136003)(366004)(39860400002)(5660300002)(71200400001)(33656002)(66556008)(2906002)(66946007)(26005)(316002)(54906003)(8936002)(66446008)(7696005)(64756008)(66476007)(186003)(110136005)(86362001)(76116006)(53546011)(6506007)(2940100002)(478600001)(9686003)(55016002)(8676002)(52536014)(4326008)(83380400001); DIR:OUT; SFP:1101; x-ms-exchange-antispam-messagedata: GcGkuoFwWuG2usLWCTNEvAH9T5hGGLTAVO2PPGiuxDKfmIjVO54EXlut8HQXaFWEcHXjaw5rQVt+3sIZgSkBSrd1RW7sp20aY1fAKipyijEWsMiFwoc1cSebw1OZr9oCzZtH/RJRzQe1YKV4g/Q6bQzQFwJc+9tmQqIcBmHbF+eAQnL9GZU4w8E24+GTvBlOEkJbpzJTKpUV5P3UyZGKaPcUyOih70PXb+aS1ieAjjZ0lGaAdDGfqydTCvhclSlA7dofQVnA99NEymk9qPS+Yn3TF84XfUly6F87pQQPWJUQpB1DxPD8uyc63hhdnyV7zWAtFgBehNdSP7oFxvuI1aR6zzpSzqEXMzMKAmqh5PajGUfKe2pXXWBDpoWKdIiGv5VXBSE2bnlCIJf/VzVEw0ylk5C7Q3hzwA6nD5P9MGME7LZYuzS8k8g6Ia2SNssy9uG9EWznuW0hX+DxkK0apiKNsACmHdswuY/Vq2PwGiu405L+4KwK810xdz5+YBQrrCYtlnRfY7N5hGRikIt0PRvw8mcA9HvsmrHgNKjef/D251gPJAKwLYfV6Bqhf61yJo1En4lT7ADbZfgGO1KlxvMengSN/Y2ynNlYBMqtpDv6kSRThuV2XZxIyEFB0G9eJ2oHrqc9a3Q8AEJpy0Qteg== x-ms-exchange-transport-forked: True Content-Type: text/plain; charset="us-ascii" Content-Transfer-Encoding: quoted-printable MIME-Version: 1.0 X-MS-Exchange-CrossTenant-AuthAs: Internal X-MS-Exchange-CrossTenant-AuthSource: DM6PR12MB4618.namprd12.prod.outlook.com X-MS-Exchange-CrossTenant-Network-Message-Id: df7d6a7c-fa7f-4041-77fb-08d87a543933 X-MS-Exchange-CrossTenant-originalarrivaltime: 27 Oct 2020 08:42:22.1954 (UTC) X-MS-Exchange-CrossTenant-fromentityheader: Hosted X-MS-Exchange-CrossTenant-id: 43083d15-7273-40c1-b7db-39efd9ccc17a X-MS-Exchange-CrossTenant-mailboxtype: HOSTED X-MS-Exchange-CrossTenant-userprincipalname: c5t0e+MbMwek8kHoCbiYcBCqjCLUClEDrcjJJP7N9d/qPLLyWvxhw9D71J7A5JlmaEemgJWUyFXlaTVjNK4sDg== X-MS-Exchange-Transport-CrossTenantHeadersStamped: DM6PR12MB4041 X-OriginatorOrg: Nvidia.com DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=nvidia.com; s=n1; t=1603788127; bh=2d2y6XVxLm0cOMgZ6+VsbcQhWqS1vnvTBeCXvQc+OOY=; h=ARC-Seal:ARC-Message-Signature:ARC-Authentication-Results:From:To: CC:Subject:Thread-Topic:Thread-Index:Date:Message-ID:References: In-Reply-To:Accept-Language:Content-Language:X-MS-Has-Attach: X-MS-TNEF-Correlator:authentication-results:x-originating-ip: x-ms-publictraffictype:x-ms-office365-filtering-correlation-id: x-ms-traffictypediagnostic:x-microsoft-antispam-prvs: x-ms-oob-tlc-oobclassifiers:x-ms-exchange-senderadcheck: x-microsoft-antispam:x-microsoft-antispam-message-info: x-forefront-antispam-report:x-ms-exchange-antispam-messagedata: x-ms-exchange-transport-forked:Content-Type: Content-Transfer-Encoding:MIME-Version: X-MS-Exchange-CrossTenant-AuthAs: X-MS-Exchange-CrossTenant-AuthSource: X-MS-Exchange-CrossTenant-Network-Message-Id: X-MS-Exchange-CrossTenant-originalarrivaltime: X-MS-Exchange-CrossTenant-fromentityheader: X-MS-Exchange-CrossTenant-id:X-MS-Exchange-CrossTenant-mailboxtype: X-MS-Exchange-CrossTenant-userprincipalname: X-MS-Exchange-Transport-CrossTenantHeadersStamped:X-OriginatorOrg; b=efn0gSVyH2pEiDpG8095Ec/sy2/soU1ggVzY4xPnznS5FHKELJUEKYUl3D0Y2TPtF 8vrn1y4afCeafxY5w+3TsI+u35i7G4IDd7mGLjp3LzErGY3X3eJAyuVrJ/VnK8ARtV MkBaHutpM5CFlX7WTAVW3uQGh0ouS9tJgu13z6ri8uYXPTWLpkUZXkyKL0tWrAetby pTAvhBWwMAFofngSBSzMr50NslVvQ5bMv2AWlbZz0idTi6o3xhXj5LCNwzAe7cOcCO 8vlN3FMtlwbKowksYPwmP5Yl4ix2cP0AZKj6kDaanuKPmVH3D3sWZAHhGeLvJYNK3q TdAVjcW7hoLEA== Subject: Re: [dpdk-dev] [PATCH v4 1/3] net/ice: add AVX512 vector path X-BeenThere: dev@dpdk.org X-Mailman-Version: 2.1.15 Precedence: list List-Id: DPDK patches and discussions List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , Errors-To: dev-bounces@dpdk.org Sender: "dev" > -----Original Message----- > From: dev On Behalf Of Ali Alnubani > Sent: Tuesday, October 27, 2020 10:33 AM > To: Leyi Rong ; qi.z.zhang@intel.com; > wenzhuo.lu@intel.com; burce.richardson@intel.com > Cc: dev@dpdk.org; Bruce Richardson > Subject: Re: [dpdk-dev] [PATCH v4 1/3] net/ice: add AVX512 vector path >=20 > Hi, >=20 > > -----Original Message----- > > From: dev 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 ; Bruce Richardson > > > > 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 > > Signed-off-by: Bruce Richardson > > --- >=20 > This patch is causing the following build failure on CentOS 7 with gcc 4.= 8.5: >=20 > """ > 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' > """ >=20 > It reproduces when building with "meson --werror --buildtype=3Ddebug buil= d > && ninja -C build". >=20 It's also causing the following build failure on Ubuntu 18.04 (gcc 7.5.0) a= nd 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: inl= ining failed in call to always_inline '_mm512_shuffle_epi8': target specifi= c 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 =3D _mm512_shuffle_epi8(raw_desc0_3, shuf_msk); ^~~~~ """ Regards, Ali