From patchwork Sat Jul 17 17:08:30 2021 Content-Type: text/plain; charset="utf-8" MIME-Version: 1.0 Content-Transfer-Encoding: 7bit X-Patchwork-Submitter: Liang Ma X-Patchwork-Id: 96009 X-Patchwork-Delegate: thomas@monjalon.net Return-Path: X-Original-To: patchwork@inbox.dpdk.org Delivered-To: patchwork@inbox.dpdk.org Received: from mails.dpdk.org (mails.dpdk.org [217.70.189.124]) by inbox.dpdk.org (Postfix) with ESMTP id EA401A0C47; Sat, 17 Jul 2021 19:09:13 +0200 (CEST) Received: from [217.70.189.124] (localhost [127.0.0.1]) by mails.dpdk.org (Postfix) with ESMTP id 9CF6E4067B; Sat, 17 Jul 2021 19:09:13 +0200 (CEST) Received: from sender11-of-o51.zoho.eu (sender11-of-o51.zoho.eu [31.186.226.237]) by mails.dpdk.org (Postfix) with ESMTP id 0E0A44003C; Sat, 17 Jul 2021 19:09:11 +0200 (CEST) ARC-Seal: i=1; a=rsa-sha256; t=1626541748; cv=none; d=zohomail.eu; s=zohoarc; b=TjoSSKO6VgdrzWiMj2vhdAOwkcYgA7sM5k1hWudHDTHV6s7Df+9YSLsk9rROhHUsrM4MTMpT0GKTTIsvaswQ+DaPgcgLvayiYh6ETmNe7dWBjGoH6jBZAlnUT4T8r1OkWCQAhrh2YD6MNK81WzeQc87+9nTpleuHYzUKsNJaESw= ARC-Message-Signature: i=1; a=rsa-sha256; c=relaxed/relaxed; d=zohomail.eu; s=zohoarc; t=1626541748; h=Cc:Date:From:Message-ID:Subject:To; bh=2l2AvjxHFVq48aesdG0B9Ticls7XjyIrIF5QtOBx50Y=; b=d2o2r1y1o53vrJFjGLMOHDMhAdym2CdCWS7rp3NJSo+xySmyWD2drJbPt8e5zAqUVzsa9y9+fxwXnvMT3HMMQr1Uz+OMBPJdBkiCH6tqMGgYE+antftj9Fvr6j/xmftTTM5uARExm6oCHz3/TP7R9WiBjB3DRAfJfqE/stQoUtk= ARC-Authentication-Results: i=1; mx.zohomail.eu; spf=pass smtp.mailfrom=liangma@liangbit.com; dmarc=pass header.from= Received: from DESKTOP-POQV63C.localdomain (51.37.214.90 [51.37.214.90]) by mx.zoho.eu with SMTPS id 1626541746973212.84075275834675; Sat, 17 Jul 2021 19:09:06 +0200 (CEST) From: Liang Ma To: dev@dpdk.org Cc: yi.rong@intel.com, Liang Ma , stable@dpdk.org, Bruce Richardson , Konstantin Ananyev Date: Sat, 17 Jul 2021 18:08:30 +0100 Message-Id: <20210717170830.1736-1-liangma@liangbit.com> X-Mailer: git-send-email 2.17.1 X-ZohoMailClient: External Subject: [dpdk-dev] [PATCH] buildtools: Check GCC version to avoid GCC 6.3.0 avx512 bug 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" From: Liang Ma GCC 6.3.0 has a known bug which related to _mm512_extracti64x4_epi64. Please reference https://gcc.gnu.org/bugzilla/show_bug.cgi?id=82887 Some DPDK PMD avx512 version heavily use _mm512_extracti64x4_epi6, which casue building failure with debug buildtype. Therefore, it's helpful to disable avx512 for GCC 6.3.0 Bugzilla ID: 717 Fixes: e6a6a138919f (net/i40e: add AVX512 vector path) Fixes: 808a17b3c1e6 (net/ice: add Rx AVX512 offload path) Fixes: 4b64ccb328c9 (net/iavf: fix VLAN extraction in AVX512 path) Cc: stable@dpdk.org Reported-by: Liang Ma Signed-off-by: Liang Ma --- buildtools/binutils-avx512-check.sh | 7 +++++++ 1 file changed, 7 insertions(+) diff --git a/buildtools/binutils-avx512-check.sh b/buildtools/binutils-avx512-check.sh index 2a833b64b7..b86d0b179e 100755 --- a/buildtools/binutils-avx512-check.sh +++ b/buildtools/binutils-avx512-check.sh @@ -5,6 +5,13 @@ AS=${AS:-as} OBJFILE=$(mktemp -t dpdk.binutils-check.XXXXXX) trap 'rm -f "$OBJFILE"' EXIT + +# from https://gcc.gnu.org/bugzilla/show_bug.cgi?id=82887 +GCC_VER=6.3.0 +gcc --version|grep $GCC_VER && { + echo "GCC 6.3.0 is broken with _mm512_extracti64x4_epi64" + exit 1 +} # from https://gcc.gnu.org/bugzilla/show_bug.cgi?id=90028 GATHER_PARAMS='0x8(,%ymm1,1),%ymm0{%k2}'