From mboxrd@z Thu Jan 1 00:00:00 1970 Return-Path: Received: from mails.dpdk.org (mails.dpdk.org [217.70.189.124]) by inbox.dpdk.org (Postfix) with ESMTP id 3B864A034F; Tue, 9 Nov 2021 19:08:41 +0100 (CET) Received: from [217.70.189.124] (localhost [127.0.0.1]) by mails.dpdk.org (Postfix) with ESMTP id EAA7C40E03; Tue, 9 Nov 2021 19:08:40 +0100 (CET) Received: from mga04.intel.com (mga04.intel.com [192.55.52.120]) by mails.dpdk.org (Postfix) with ESMTP id 2592641100 for ; Tue, 9 Nov 2021 19:08:38 +0100 (CET) X-IronPort-AV: E=McAfee;i="6200,9189,10163"; a="231233824" X-IronPort-AV: E=Sophos;i="5.87,220,1631602800"; d="scan'208";a="231233824" Received: from orsmga005.jf.intel.com ([10.7.209.41]) by fmsmga104.fm.intel.com with ESMTP/TLS/ECDHE-RSA-AES256-GCM-SHA384; 09 Nov 2021 10:08:38 -0800 X-ExtLoop1: 1 X-IronPort-AV: E=Sophos;i="5.87,220,1631602800"; d="scan'208";a="669503952" Received: from orsmsx606.amr.corp.intel.com ([10.22.229.19]) by orsmga005.jf.intel.com with ESMTP; 09 Nov 2021 10:08:37 -0800 Received: from orsmsx611.amr.corp.intel.com (10.22.229.24) by ORSMSX606.amr.corp.intel.com (10.22.229.19) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_128_GCM_SHA256) id 15.1.2242.12; Tue, 9 Nov 2021 10:08:37 -0800 Received: from ORSEDG602.ED.cps.intel.com (10.7.248.7) by orsmsx611.amr.corp.intel.com (10.22.229.24) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_128_GCM_SHA256) id 15.1.2242.12 via Frontend Transport; Tue, 9 Nov 2021 10:08:37 -0800 Received: from NAM12-BN8-obe.outbound.protection.outlook.com (104.47.55.176) by edgegateway.intel.com (134.134.137.103) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.1.2242.12; Tue, 9 Nov 2021 10:08:37 -0800 ARC-Seal: i=1; a=rsa-sha256; s=arcselector9901; d=microsoft.com; cv=none; b=M3eI6xsclL5k6o+fCd3ItwhKluKYjmf5WGuSv/hP7VEGGwMwzSETuRJ5BCxfBTmvXo9AI33GPPCqf3/8QLbibS++oAMLSasxdPyMzRwt4x/MIIzJdXokd7IGhXAddFNl0Rkd4xMf2yJr277lHuFz9k3V9UdtAU1yZ9y1+yLrUmg/MKiVgyHKVb8f0kt07MBxY6lMt8EeaHgl7krh8LN6s9o43mY6auDOfausrc1wX6eq/bAxMgFwT3L7CsHJXEct4zdNKcuMVklwym1RCL+OYEC1cf/0eFrcCWk6s4ebWvHrhzTI25ovySgnBVpnx0nXWRhOZTbALxOvf686Ov19Gw== 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-AntiSpam-MessageData-ChunkCount:X-MS-Exchange-AntiSpam-MessageData-0:X-MS-Exchange-AntiSpam-MessageData-1; bh=xETo/riER16bv0oea0qpdv33DEP/2F5o/1IK4btfZbE=; b=WO1bwUbqgtt9BFeVrdm1ADD5ix1YJwxfm6xH/j1F4aV/I12aB1gnBnggPaiQinA0gSAKX3/YWPQxrlPAqrkpgg7wIcEm7s/wWeLGa0T8QLiEPILmoREaGwXDv53TdadxioUiOaq5yab/IA/0AWPrp84I6OEcAwYbFjFAZBk2pi2IcG2TBdnNTycK/Wr0gX9WtsIki2S9yJJEWC7wgHpbbj9hFpAGMSSlz7KoOJmH2pxsoHeZLZclBdJvt2IePtMzZmRsa1oSQGBDCKlUdCft2ZXdSXnvH52nLytvnnRKW9/5SRODwKbxwMAlna4IOGxMVrVrBRM3J56XSOgU/LHR+Q== ARC-Authentication-Results: i=1; mx.microsoft.com 1; spf=pass smtp.mailfrom=intel.com; dmarc=pass action=none header.from=intel.com; dkim=pass header.d=intel.com; arc=none DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=intel.onmicrosoft.com; s=selector2-intel-onmicrosoft-com; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-SenderADCheck; bh=xETo/riER16bv0oea0qpdv33DEP/2F5o/1IK4btfZbE=; b=lLA9GNIHUODbfnHMVEhCASumThZODJ85C+P1gGZfmRKZoE9ExrKi6ZfwWt8oQ81mDlcvfLG1XyffqRaV4SjTECT8x+kix91v1O4maGfvtR1e9iSz9jV/XwGC4lKWMDhVM66FLKh7uue8drAJ73sOUu7neavnme4onA2ke6eNSCo= Received: from SN6PR11MB3408.namprd11.prod.outlook.com (2603:10b6:805:bc::22) by SA2PR11MB4987.namprd11.prod.outlook.com (2603:10b6:806:113::24) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.4669.13; Tue, 9 Nov 2021 18:08:34 +0000 Received: from SN6PR11MB3408.namprd11.prod.outlook.com ([fe80::990:798c:6e6d:1d72]) by SN6PR11MB3408.namprd11.prod.outlook.com ([fe80::990:798c:6e6d:1d72%4]) with mapi id 15.20.4669.016; Tue, 9 Nov 2021 18:08:34 +0000 From: "Ji, Kai" To: "Medvedkin, Vladimir" , "dev@dpdk.org" CC: "thomas@monjalon.net" , "david.marchand@redhat.com" , "Ananyev, Konstantin" , "lance.richardson@broadcom.com" , "Medvedkin, Vladimir" , "Wang, Yipeng1" , "Gobriel, Sameh" , "Richardson, Bruce" Thread-Topic: [dpdk-dev] [PATCH] hash: fix thash gfni implementation Thread-Index: AQHX1Y7Zj/gvMqggH0CBS1mJQsJUnKv7fd9Q Date: Tue, 9 Nov 2021 18:08:33 +0000 Message-ID: References: <20211109172456.147140-1-vladimir.medvedkin@intel.com> In-Reply-To: <20211109172456.147140-1-vladimir.medvedkin@intel.com> Accept-Language: en-IE, en-US Content-Language: en-US X-MS-Has-Attach: X-MS-TNEF-Correlator: dlp-reaction: no-action dlp-version: 11.6.200.16 dlp-product: dlpe-windows authentication-results: intel.com; dkim=none (message not signed) header.d=none;intel.com; dmarc=none action=none header.from=intel.com; x-ms-publictraffictype: Email x-ms-office365-filtering-correlation-id: 64049475-d099-4419-06ab-08d9a3abf1c1 x-ms-traffictypediagnostic: SA2PR11MB4987: x-ld-processed: 46c98d88-e344-4ed4-8496-4ed7712e255d,ExtAddr x-microsoft-antispam-prvs: x-ms-oob-tlc-oobclassifiers: OLM:4303; x-ms-exchange-senderadcheck: 1 x-ms-exchange-antispam-relay: 0 x-microsoft-antispam: BCL:0; x-microsoft-antispam-message-info: EMea53xvm8qgqdvtawfr461IgIuEIydpyuYk8sTQvgQiGBYoGbpWoePYDVzxkvn/tAUdVSVHa19G5hSeES2yFtRKDmfVTfogNULUG9QG9bnkCMgap7exdK6/GocnzaIw+s3Qhz/WMv6UJkmw0OgpioJ+EAUjq2bKEex1SIfI0EXdjQZOIWlQEOwGMQK6lPRaJBvYYDGUoKr3PUXaUBrNya1zmnt2tublI73Lc9xP1Zh+NZQ1Uw87s8LFsKOXPfFHJTXA0BJylgPSvUg4J6ZsDpD7q3+7kQcS8vbo9s+8LLSBR+JCs6kq1tfr7rBR1Maa+RjGLH090qYahb6gx7KPZLH+E6iWgf+ZXRfzNTaqRBUgtKiwdcisRMh/4ydvBuHbxSQwy5bY/XqK/ZtyXaFjSUe1VlNtGw3pL9QIFItO4LkbLchq1hUuYuRU3WEAQ2zrMKBzykAomdAgjo8CG/hbMDeSe+mjbEX9Wl6ko7Oj+wdxy1Q3gvU+KSnQyhy8tBXkHe3LMZShFRmrTvzDGgYNAIllU0vZMciNkDHUNS+9zP4+qMzAKk3owiynAiATnQPpy6I1oXfeQca/w3HxzeZMAr5EkRosAw39oORYjAoFLlmNVzhzOfFCymSHr4/3U2rnmqUyTUr+3vVpIbqw4Yhqb8eVUlabMTpmlQwTFoFb6uIOBouAf+YZ4thgsXlbkacwZlYu7pTv0bbybUrpNkkhSg== x-forefront-antispam-report: CIP:255.255.255.255; CTRY:; LANG:en; SCL:1; SRV:; IPV:NLI; SFV:NSPM; H:SN6PR11MB3408.namprd11.prod.outlook.com; PTR:; CAT:NONE; SFS:(366004)(6506007)(53546011)(38070700005)(186003)(86362001)(54906003)(55016002)(2906002)(122000001)(83380400001)(4326008)(8676002)(82960400001)(33656002)(7696005)(5660300002)(8936002)(4744005)(107886003)(52536014)(66946007)(38100700002)(71200400001)(66476007)(316002)(508600001)(76116006)(26005)(66556008)(9686003)(66446008)(64756008)(110136005); DIR:OUT; SFP:1102; x-ms-exchange-antispam-messagedata-chunkcount: 1 x-ms-exchange-antispam-messagedata-0: =?us-ascii?Q?U94Yoa5RfIk5yrTDxXyNSK0HrVNmMPXHqAEuD5C5sUD/W0ASVn2iCukHPyh9?= =?us-ascii?Q?KDkfc9Z0BAtk8Qqhqs0sHb+yXsj/HqgxkIBNvPuSjFaUHXpAM55TTFJJ2XDL?= =?us-ascii?Q?TJBCTRZrHuBYOjGnNctk/Sj3xqs+UfPAfETP3NrKg/UccefG1qk0VBUIHD0r?= =?us-ascii?Q?RdVD4254jNQJgPJ7xGlhNLsWp1fIU7WIc4zARC2XjJk7bjAg/ybpRZzJnZwS?= =?us-ascii?Q?4NkMYbUlzWmRre1E4kddTM66P/agR61LifmVR+uNC/wJ4mNzwhgDxRLkxfFt?= =?us-ascii?Q?bYg3MjNiyK3owRqJM/G5a+FzMw9SHqAUWQy9v+1yApaT+ys5kb2S+bg/0v14?= =?us-ascii?Q?Mlj9pJjmo/gsBH0b9M3PiTd3uWMo5GnhmWF4FxkpEyrosyIQ4qejjUUEIk8b?= =?us-ascii?Q?AKTX1c4WAo5R4QFeNdojvIov6k+38y5nsthWbLqjRjwRqzzp0S0Z1mZ24lYd?= =?us-ascii?Q?a/ZRE3WPqP8ZKBY8vcYqi2y5cRkHBXieyfBx6BxucTU2KPqts7D0uw6wUw0Z?= =?us-ascii?Q?RfhFe/gsEnlTb4RBqARHBx/m7JdmNpFtXDuhg3PGlpLK/M4ZmZdAuof8328C?= =?us-ascii?Q?+EkAxRwtGCdGiUnqb7/MDyAO3PcFaP+/ucNtmBcWuiqyenGNKBSdjFOQlgrR?= =?us-ascii?Q?rLd7ZMPAjtGLGpoqEzyMdepK68x0gfZCWWBosvK3UWtmp2Rq7qJW+j4yhyK8?= =?us-ascii?Q?quKIDvHa3gp9ecBpfDtIWDSYqSeBJ+NRXqWu73H8pYA9qBI1D9rk6xSUHIrm?= =?us-ascii?Q?MK3zae+j1oHo4Bq5b8xNKvDlVNFUPpmdcERScC262uYB49pitJbR0rGtUmMy?= =?us-ascii?Q?8MF/JGUlG8MdnxQJEncsj1ei/xWGmy0RJ8NsefC6NLdqjptOely8XKONgHPH?= =?us-ascii?Q?jws4rBfJyAb6EfFhW7Vn/bRPC4qtybz4XLJztLH5NCqG1R/Sl60hAGJ7d1lp?= =?us-ascii?Q?CRle5KlI+jJOxS5RWRk5okRtBWEC2syK6r7g6W3g2UzhZLp/zbQ/KueQ9K33?= =?us-ascii?Q?FECz4qMgNanDM+0wZhCzkr91KRxWd/EUhU3OvAHNfxPlgEecjksUwXvg4qfx?= =?us-ascii?Q?KUphbXujwknebrFTQ2ofhjZE3jA5U5oRlO6cO+ruU+Ys99SKvSUny4NfKh1Y?= =?us-ascii?Q?yD5Ophgzm8bArRlT+uoqr/u6CbI8p+Ab5Zm9Em7iUl3umsoWO9514xfl1E16?= =?us-ascii?Q?RCQC+z0waIogbe4Td5KJuLnw1orh9ZgNKVBLvqOOtCc0hFIs7h0kt9igZf8w?= =?us-ascii?Q?mOiEZ77H1dMVcpZljt7jNIpkmtPNghw4mWQZO8z6nTSJ5EbWBiVvLAcfRjoX?= =?us-ascii?Q?EE/BPRkavmo7e8S/WmJa7TfpSCIMVb3sdDqJdUO0ZMZ3t1aJr+GGEpQtnFVJ?= =?us-ascii?Q?13Gsl5LvwlbdQMNS0LEhozhQz5Skl2lvjxtKBT6vX3bmrB5ho95D/aAGTQxu?= =?us-ascii?Q?ryLhVcBQhGRIcLO1ce+hdjPkcJnWYTl3mYlDc4Pb43K88TmmtSJtWAlnoODm?= =?us-ascii?Q?rxLZaVTxXoJB3kbg4PwxLfjo3pqxbUS8mvkBF2O4f2mt2NX0H4YGCAyBfol3?= =?us-ascii?Q?zLK8dunlAlXl53+ggz/4ox1TfGKg6vNMBDrcksftAv73EdaakrNVPtlYYTTO?= =?us-ascii?Q?3yQadFjDHB+dYo4YeEwkpUo=3D?= 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: SN6PR11MB3408.namprd11.prod.outlook.com X-MS-Exchange-CrossTenant-Network-Message-Id: 64049475-d099-4419-06ab-08d9a3abf1c1 X-MS-Exchange-CrossTenant-originalarrivaltime: 09 Nov 2021 18:08:33.8980 (UTC) X-MS-Exchange-CrossTenant-fromentityheader: Hosted X-MS-Exchange-CrossTenant-id: 46c98d88-e344-4ed4-8496-4ed7712e255d X-MS-Exchange-CrossTenant-mailboxtype: HOSTED X-MS-Exchange-CrossTenant-userprincipalname: /zfwMhdyRq1kXsrOc1aHjIA9mLHbgwVUXzAhUBrtArhL/Oogm1nwcWMCQU6NdLGSY3poyHjdNB2+6P6ALCZMmQ== X-MS-Exchange-Transport-CrossTenantHeadersStamped: SA2PR11MB4987 X-OriginatorOrg: intel.com Subject: Re: [dpdk-dev] [PATCH] hash: fix thash gfni implementation X-BeenThere: dev@dpdk.org X-Mailman-Version: 2.1.29 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 Vladimir Medvedkin > Sent: Tuesday, November 9, 2021 5:25 PM > To: dev@dpdk.org > Cc: thomas@monjalon.net; david.marchand@redhat.com; Ananyev, > Konstantin ; > lance.richardson@broadcom.com; Medvedkin, Vladimir > ; Wang, Yipeng1 > ; Gobriel, Sameh ; > Richardson, Bruce > Subject: [dpdk-dev] [PATCH] hash: fix thash gfni implementation >=20 > This patch replaces _mm512_set_epi8 with _mm512_set_epi32 due to the > lack of support by some compilers. > Also this patch checks if AVX512F is supported along with GFNI. > This is done if the code is built on a platform that supports GFNI, but d= oes not > support AVX512. >=20 > Fixes: 4fd8c4cb0de1 ("hash: add new Toeplitz hash implementation") > Cc: vladimir.medvedkin@intel.com >=20 > Signed-off-by: Vladimir Medvedkin Acked-by: Ji, Kai