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 C737DA04DB; Thu, 15 Oct 2020 13:54:21 +0200 (CEST) Received: from [92.243.14.124] (localhost [127.0.0.1]) by dpdk.org (Postfix) with ESMTP id D76C41E4C8; Thu, 15 Oct 2020 13:54:19 +0200 (CEST) Received: from mga07.intel.com (mga07.intel.com [134.134.136.100]) by dpdk.org (Postfix) with ESMTP id 58EE91DDE5 for ; Thu, 15 Oct 2020 13:54:18 +0200 (CEST) IronPort-SDR: 0+Dr4mHi+mNXM1GVvY0zVOwjJGyiKRPLvJUjmGZA1Vensxkx7BdYBmkIYAWjb8grmGggMcuTwG a7dHQq9bsUFw== X-IronPort-AV: E=McAfee;i="6000,8403,9774"; a="230525182" X-IronPort-AV: E=Sophos;i="5.77,378,1596524400"; d="scan'208";a="230525182" X-Amp-Result: SKIPPED(no attachment in message) X-Amp-File-Uploaded: False Received: from fmsmga007.fm.intel.com ([10.253.24.52]) by orsmga105.jf.intel.com with ESMTP/TLS/ECDHE-RSA-AES256-GCM-SHA384; 15 Oct 2020 04:54:10 -0700 IronPort-SDR: bE0KfJXxQtRnotIt0dK3tkG7aghEIRWhHl9OioEiySsxXuNtdKGr3KbbhTGMFRMqDMX7g6Opyl HYP2glpBpUkA== X-ExtLoop1: 1 X-IronPort-AV: E=Sophos;i="5.77,378,1596524400"; d="scan'208";a="300283302" Received: from sivswdev08.ir.intel.com ([10.237.217.47]) by fmsmga007.fm.intel.com with ESMTP; 15 Oct 2020 04:54:08 -0700 From: Konstantin Ananyev To: dev@dpdk.org Cc: alialnu@mellanox.com, david.marchand@redhat.com, Konstantin Ananyev Date: Thu, 15 Oct 2020 12:53:56 +0100 Message-Id: <20201015115356.28171-1-konstantin.ananyev@intel.com> X-Mailer: git-send-email 2.18.0 Subject: [dpdk-dev] [PATCH] acl: fix build failure with gcc 5.4.0 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" gcc 5.4 fails with: ../lib/librte_acl/acl_run_avx512x8.h: In function 'match_process_avx512x8': ../lib/librte_acl/acl_run_avx512x8.h:382:31: error: pointer targets in passing argument 1 of '_mm256_mask_i32scatter_epi32' differ in signedness [-Werror=pointer-sign] Later gcc versions work fine, as for them parameter type was changed to 'void *'. Fixed by applying explicit cast for offending argument. Fixes: b64c2295f7fc ("acl: add 256-bit AVX512 classify method") Fixes: 45da22e42ec3 ("acl: add 512-bit AVX512 classify method") Signed-off-by: Konstantin Ananyev --- lib/librte_acl/acl_run_avx512_common.h | 4 ++-- 1 file changed, 2 insertions(+), 2 deletions(-) diff --git a/lib/librte_acl/acl_run_avx512_common.h b/lib/librte_acl/acl_run_avx512_common.h index 1baf79b7a..fafaf591e 100644 --- a/lib/librte_acl/acl_run_avx512_common.h +++ b/lib/librte_acl/acl_run_avx512_common.h @@ -246,8 +246,8 @@ _F_(match_process)(struct acl_flow_avx512 *flow, uint32_t *fmsk, tr_hi[0] = _M_I_(mask_mov_epi32)(tr_hi[0], rmsk[0], _SV_(trhi_idle)); /* save found match indexes */ - _M_I_(mask_i32scatter_epi32)(flow->matches, rmsk[0], idx[0], res, - sizeof(flow->matches[0])); + _M_I_(mask_i32scatter_epi32)((void *)flow->matches, rmsk[0], idx[0], + res, sizeof(flow->matches[0])); /* update masks and start new flows for matches */ n = update_flow_mask(flow, fmsk, rmsk); -- 2.25.1