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 721BA468E4 for ; Thu, 12 Jun 2025 23:08:01 +0200 (CEST) Received: from mails.dpdk.org (localhost [127.0.0.1]) by mails.dpdk.org (Postfix) with ESMTP id 6C94C42E00; Thu, 12 Jun 2025 23:08:01 +0200 (CEST) Received: from mail-wr1-f53.google.com (mail-wr1-f53.google.com [209.85.221.53]) by mails.dpdk.org (Postfix) with ESMTP id 6719E42E37 for ; Thu, 12 Jun 2025 23:08:00 +0200 (CEST) Received: by mail-wr1-f53.google.com with SMTP id ffacd0b85a97d-3a54700a46eso1209326f8f.1 for ; Thu, 12 Jun 2025 14:08:00 -0700 (PDT) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=gmail.com; s=20230601; t=1749762480; x=1750367280; darn=dpdk.org; h=content-transfer-encoding:mime-version:references:in-reply-to :message-id:date:subject:cc:to:from:from:to:cc:subject:date :message-id:reply-to; bh=qatNo0z64H4a+OIzpZkKVKshr/WJVeu7Tw7dtBbwby4=; b=Gc51fXFtVQIs+TnpS6tpjTjoGE71WLdfhhmZBOD7WdboIQZzqOhhIY66OCCorgrepP E/X+XhdxTRQvxl17zWsmdSkSnrlaH+VY6SFxHi/KdmXcmeq3cQOQJs8WyvVd0HEofRDW lbFjUCJWvugxpnLrTlpghHRt9tGZ188CoQuhXSHpN4uD3rSfpc26Kr6XIC0n1avV05A2 K70DswUjOT80nBhqauF5f3NfH7qS7CYP//ZxArt6dOOLZXLvrB5YSIffzt2BRxEGadHA i7VhKf1nMevSwlB1YKFXs1qsdcAM7wA4n5+z9k6DzqI7+oLwvoFXJNWMr+EDKX5y8ky6 o01w== X-Google-DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=1e100.net; s=20230601; t=1749762480; x=1750367280; h=content-transfer-encoding:mime-version:references:in-reply-to :message-id:date:subject:cc:to:from:x-gm-message-state:from:to:cc :subject:date:message-id:reply-to; bh=qatNo0z64H4a+OIzpZkKVKshr/WJVeu7Tw7dtBbwby4=; b=rYjt8i4jPuYQN+RX9WbEta0/m54qOHqDqGTFh+j1nkRAwPaJYRSq/caAsuQJsHQg3v vwn7pn5F2gtRl265bAdebcdGxnLtmkjVYahZFmYLAuH8n/IOc1WZQKpUS1R3pCehnwTC g1XboaH+sYpzuKU4r8P57hcMKo1lzuOlbrrj5TMdXyyNtfBoi46SrT0ltYR+DMT6pAmO gqdsdzq/ovvP34gXT0bbh10SjmfnwzcEELQ6nOv/Nk/poz4ApPWlkEhkIFHMrO+m4tOg 20iB05leCYBF7XvgKjppmAVBOjQOzbU4tTDzctfnqtw/GxmMgTv1v1XoQxlQ9F+hQ6Xo JQVg== X-Forwarded-Encrypted: i=1; AJvYcCVsG977q5xziYIZDtmiXC8cZcLN0bIuD6r9lTrsNtu4LPrZMvhymFmavj/aJaCNE7/tmBjhj3Q=@dpdk.org X-Gm-Message-State: AOJu0YyD4W8pn2UsLPMbo3zEIfdsTA8ss2NAS56RDdmGjr7tBej/ohXw yYe7sPf2FUtC+ETv0Ktfab4H9VLy+2KE3h0rOaPuKiLWY6Ys+mkdUavfugOijZVD X-Gm-Gg: ASbGncv+mr7GyjkyLlPDiHkK/1SC9KunzNlMmRpYHoH80Y1LHFU5zAo7pKSZUSWWpYe WEcpyWUsmgLFCRcETwxSOgpZn458F3Q0blK5Q1tfBqiYvWQNDLxcVZG/wII+if6opeLlrJpi58P nSg6dczq/DxxuoJ13YLHZDT4TrL0w5SLVlSp75o/QlcUse+TsndeUeEKC59LZv3BIuUb/RmWB6G LZjPn4InXofYcch/SsEOC6YOX/nXisTTVkpF0t94EfPfUSX3wkGrZrHe2FCmIoTyMpQ4HuwS4lC JPFDEuuDnqUuYeTNC9QVEt66Je663I5C9aTyb59bzg6EoSB4g/i8buomfZ58bEL4uFUw X-Google-Smtp-Source: AGHT+IG8YXUAQ4l2EYD/6zRHGDgnM1HTD5eGeZBzn88X/1eUh2uaLtsuI37Vy/2/DWzdXbcqi1udCA== X-Received: by 2002:a05:6000:401e:b0:3a4:dd02:f724 with SMTP id ffacd0b85a97d-3a56871749fmr653833f8f.43.1749762479856; Thu, 12 Jun 2025 14:07:59 -0700 (PDT) Received: from localhost ([2a01:4b00:d036:ae00:f2df:571a:ae4c:bef2]) by smtp.gmail.com with UTF8SMTPSA id ffacd0b85a97d-3a568b1eb9bsm364303f8f.69.2025.06.12.14.07.58 (version=TLS1_3 cipher=TLS_AES_256_GCM_SHA384 bits=256/256); Thu, 12 Jun 2025 14:07:59 -0700 (PDT) From: luca.boccassi@gmail.com To: David Marchand Cc: Konstantin Ananyev , Bruce Richardson , dpdk stable Subject: patch 'acl: fix build with GCC 15 on aarch64' has been queued to stable release 22.11.9 Date: Thu, 12 Jun 2025 22:06:25 +0100 Message-ID: <20250612210733.2506558-8-luca.boccassi@gmail.com> X-Mailer: git-send-email 2.47.2 In-Reply-To: <20250612210733.2506558-1-luca.boccassi@gmail.com> References: <20250612210733.2506558-1-luca.boccassi@gmail.com> MIME-Version: 1.0 Content-Type: text/plain; charset=UTF-8 Content-Transfer-Encoding: 8bit X-BeenThere: stable@dpdk.org X-Mailman-Version: 2.1.29 Precedence: list List-Id: patches for DPDK stable branches List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , Errors-To: stable-bounces@dpdk.org Hi, FYI, your patch has been queued to stable release 22.11.9 Note it hasn't been pushed to http://dpdk.org/browse/dpdk-stable yet. It will be pushed if I get no objections before 06/14/25. So please shout if anyone has objections. Also note that after the patch there's a diff of the upstream commit vs the patch applied to the branch. This will indicate if there was any rebasing needed to apply to the stable branch. If there were code changes for rebasing (ie: not only metadata diffs), please double check that the rebase was correctly done. Queued patches are on a temporary branch at: https://github.com/bluca/dpdk-stable This queued commit can be viewed at: https://github.com/bluca/dpdk-stable/commit/373738b2787fef6aa0a435955674218ecb2280a0 Thanks. Luca Boccassi --- >From 373738b2787fef6aa0a435955674218ecb2280a0 Mon Sep 17 00:00:00 2001 From: David Marchand Date: Wed, 26 Mar 2025 11:29:02 +0100 Subject: [PATCH] acl: fix build with GCC 15 on aarch64 MIME-Version: 1.0 Content-Type: text/plain; charset=UTF-8 Content-Transfer-Encoding: 8bit [ upstream commit 6cde8a3dda49ad2721ac15faedf1965cdb4980b0 ] Caught in OBS for Fedora Rawhide on aarch64: [ 198s] In file included from ../lib/acl/acl_run_neon.h:7, [ 198s] from ../lib/acl/acl_run_neon.c:5: [ 198s] In function ‘alloc_completion’, [ 198s] inlined from ‘acl_start_next_trie’ at ../lib/acl/acl_run.h:140:24, [ 198s] inlined from ‘search_neon_4.isra’ at ../lib/acl/acl_run_neon.h:239:20: [ 198s] ../lib/acl/acl_run.h:93:25: error: ‘cmplt’ may be used uninitialized [-Werror=maybe-uninitialized] [ 198s] 93 | if (p[n].count == 0) { [ 198s] | ~~~~^~~~~~ [ 198s] ../lib/acl/acl_run_neon.h: In function ‘search_neon_4.isra’: [ 198s] ../lib/acl/acl_run_neon.h:230:27: note: ‘cmplt’ declared here [ 198s] 230 | struct completion cmplt[4]; [ 198s] | ^~~~~ The code was resetting sequentially cmpl[].count at the exact index that later call to alloc_completion uses. While this code seems correct, GCC 15 does not understand this (probably when applying some optimisations). Instead, reset cmpl[].count all at once in acl_set_flow, and cleanup the various vectorized implementations accordingly. Bugzilla ID: 1678 Signed-off-by: David Marchand Acked-by: Konstantin Ananyev Tested-by: Konstantin Ananyev Acked-by: Bruce Richardson --- lib/acl/acl_run.h | 5 +++++ lib/acl/acl_run_altivec.h | 8 ++------ lib/acl/acl_run_avx2.h | 4 +--- lib/acl/acl_run_neon.h | 8 ++------ lib/acl/acl_run_scalar.c | 4 +--- lib/acl/acl_run_sse.h | 8 ++------ 6 files changed, 13 insertions(+), 24 deletions(-) diff --git a/lib/acl/acl_run.h b/lib/acl/acl_run.h index 7d215de9d6..533f233f68 100644 --- a/lib/acl/acl_run.h +++ b/lib/acl/acl_run.h @@ -176,6 +176,8 @@ acl_set_flow(struct acl_flow_data *flows, struct completion *cmplt, uint32_t cmplt_size, const uint8_t **data, uint32_t *results, uint32_t data_num, uint32_t categories, const uint64_t *trans) { + unsigned int i; + flows->num_packets = 0; flows->started = 0; flows->trie = 0; @@ -187,6 +189,9 @@ acl_set_flow(struct acl_flow_data *flows, struct completion *cmplt, flows->data = data; flows->results = results; flows->trans = trans; + + for (i = 0; i < cmplt_size; i++) + cmplt[i].count = 0; } typedef void (*resolve_priority_t) diff --git a/lib/acl/acl_run_altivec.h b/lib/acl/acl_run_altivec.h index 4556e1503b..bcf62ee084 100644 --- a/lib/acl/acl_run_altivec.h +++ b/lib/acl/acl_run_altivec.h @@ -197,10 +197,8 @@ search_altivec_8(const struct rte_acl_ctx *ctx, const uint8_t **data, acl_set_flow(&flows, cmplt, RTE_DIM(cmplt), data, results, total_packets, categories, ctx->trans_table); - for (n = 0; n < MAX_SEARCHES_ALTIVEC8; n++) { - cmplt[n].count = 0; + for (n = 0; n < MAX_SEARCHES_ALTIVEC8; n++) index_array[n] = acl_start_next_trie(&flows, parms, n, ctx); - } /* Check for any matches. */ acl_match_check_x4(0, ctx, parms, &flows, (uint64_t *)&index_array[0]); @@ -268,10 +266,8 @@ search_altivec_4(const struct rte_acl_ctx *ctx, const uint8_t **data, acl_set_flow(&flows, cmplt, RTE_DIM(cmplt), data, results, total_packets, categories, ctx->trans_table); - for (n = 0; n < MAX_SEARCHES_ALTIVEC4; n++) { - cmplt[n].count = 0; + for (n = 0; n < MAX_SEARCHES_ALTIVEC4; n++) index_array[n] = acl_start_next_trie(&flows, parms, n, ctx); - } /* Check for any matches. */ acl_match_check_x4(0, ctx, parms, &flows, index_array); diff --git a/lib/acl/acl_run_avx2.h b/lib/acl/acl_run_avx2.h index 0b8967f22e..e069fb85b2 100644 --- a/lib/acl/acl_run_avx2.h +++ b/lib/acl/acl_run_avx2.h @@ -171,10 +171,8 @@ search_avx2x16(const struct rte_acl_ctx *ctx, const uint8_t **data, acl_set_flow(&flows, cmplt, RTE_DIM(cmplt), data, results, total_packets, categories, ctx->trans_table); - for (n = 0; n < RTE_DIM(cmplt); n++) { - cmplt[n].count = 0; + for (n = 0; n < RTE_DIM(cmplt); n++) index_array[n] = acl_start_next_trie(&flows, parms, n, ctx); - } t0 = _mm256_set_epi64x(index_array[5], index_array[4], index_array[1], index_array[0]); diff --git a/lib/acl/acl_run_neon.h b/lib/acl/acl_run_neon.h index 69d1b6d9e1..e31d56e7d0 100644 --- a/lib/acl/acl_run_neon.h +++ b/lib/acl/acl_run_neon.h @@ -170,10 +170,8 @@ search_neon_8(const struct rte_acl_ctx *ctx, const uint8_t **data, acl_set_flow(&flows, cmplt, RTE_DIM(cmplt), data, results, total_packets, categories, ctx->trans_table); - for (n = 0; n < 8; n++) { - cmplt[n].count = 0; + for (n = 0; n < 8; n++) index_array[n] = acl_start_next_trie(&flows, parms, n, ctx); - } /* Check for any matches. */ acl_match_check_x4(0, ctx, parms, &flows, &index_array[0]); @@ -232,10 +230,8 @@ search_neon_4(const struct rte_acl_ctx *ctx, const uint8_t **data, acl_set_flow(&flows, cmplt, RTE_DIM(cmplt), data, results, total_packets, categories, ctx->trans_table); - for (n = 0; n < 4; n++) { - cmplt[n].count = 0; + for (n = 0; n < 4; n++) index_array[n] = acl_start_next_trie(&flows, parms, n, ctx); - } /* Check for any matches. */ acl_match_check_x4(0, ctx, parms, &flows, index_array); diff --git a/lib/acl/acl_run_scalar.c b/lib/acl/acl_run_scalar.c index 3d61e79409..a3661b1b6b 100644 --- a/lib/acl/acl_run_scalar.c +++ b/lib/acl/acl_run_scalar.c @@ -121,10 +121,8 @@ rte_acl_classify_scalar(const struct rte_acl_ctx *ctx, const uint8_t **data, acl_set_flow(&flows, cmplt, RTE_DIM(cmplt), data, results, num, categories, ctx->trans_table); - for (n = 0; n < MAX_SEARCHES_SCALAR; n++) { - cmplt[n].count = 0; + for (n = 0; n < MAX_SEARCHES_SCALAR; n++) index_array[n] = acl_start_next_trie(&flows, parms, n, ctx); - } transition0 = index_array[0]; transition1 = index_array[1]; diff --git a/lib/acl/acl_run_sse.h b/lib/acl/acl_run_sse.h index 93286a2c38..4ec819a215 100644 --- a/lib/acl/acl_run_sse.h +++ b/lib/acl/acl_run_sse.h @@ -205,10 +205,8 @@ search_sse_8(const struct rte_acl_ctx *ctx, const uint8_t **data, acl_set_flow(&flows, cmplt, RTE_DIM(cmplt), data, results, total_packets, categories, ctx->trans_table); - for (n = 0; n < MAX_SEARCHES_SSE8; n++) { - cmplt[n].count = 0; + for (n = 0; n < MAX_SEARCHES_SSE8; n++) index_array[n] = acl_start_next_trie(&flows, parms, n, ctx); - } /* * indices1 contains index_array[0,1] @@ -293,10 +291,8 @@ search_sse_4(const struct rte_acl_ctx *ctx, const uint8_t **data, acl_set_flow(&flows, cmplt, RTE_DIM(cmplt), data, results, total_packets, categories, ctx->trans_table); - for (n = 0; n < MAX_SEARCHES_SSE4; n++) { - cmplt[n].count = 0; + for (n = 0; n < MAX_SEARCHES_SSE4; n++) index_array[n] = acl_start_next_trie(&flows, parms, n, ctx); - } indices1 = _mm_loadu_si128((xmm_t *) &index_array[0]); indices2 = _mm_loadu_si128((xmm_t *) &index_array[2]); -- 2.47.2 --- Diff of the applied patch vs upstream commit (please double-check if non-empty: --- --- - 2025-06-12 22:06:24.200349928 +0100 +++ 0008-acl-fix-build-with-GCC-15-on-aarch64.patch 2025-06-12 22:06:23.794043032 +0100 @@ -1 +1 @@ -From 6cde8a3dda49ad2721ac15faedf1965cdb4980b0 Mon Sep 17 00:00:00 2001 +From 373738b2787fef6aa0a435955674218ecb2280a0 Mon Sep 17 00:00:00 2001 @@ -8,0 +9,2 @@ +[ upstream commit 6cde8a3dda49ad2721ac15faedf1965cdb4980b0 ] + @@ -36 +37,0 @@ -Cc: stable@dpdk.org @@ -52 +53 @@ -index 7f092413cd..9fd3e60021 100644 +index 7d215de9d6..533f233f68 100644 @@ -75 +76 @@ -index 2d398ffded..d5ccdb94f0 100644 +index 4556e1503b..bcf62ee084 100644 @@ -78 +79 @@ -@@ -199,10 +199,8 @@ search_altivec_8(const struct rte_acl_ctx *ctx, const uint8_t **data, +@@ -197,10 +197,8 @@ search_altivec_8(const struct rte_acl_ctx *ctx, const uint8_t **data, @@ -90 +91 @@ -@@ -270,10 +268,8 @@ search_altivec_4(const struct rte_acl_ctx *ctx, const uint8_t **data, +@@ -268,10 +266,8 @@ search_altivec_4(const struct rte_acl_ctx *ctx, const uint8_t **data, @@ -119 +120 @@ -index 63074f871d..3b9bd0cc39 100644 +index 69d1b6d9e1..e31d56e7d0 100644 @@ -122 +123 @@ -@@ -172,10 +172,8 @@ search_neon_8(const struct rte_acl_ctx *ctx, const uint8_t **data, +@@ -170,10 +170,8 @@ search_neon_8(const struct rte_acl_ctx *ctx, const uint8_t **data, @@ -134 +135 @@ -@@ -234,10 +232,8 @@ search_neon_4(const struct rte_acl_ctx *ctx, const uint8_t **data, +@@ -232,10 +230,8 @@ search_neon_4(const struct rte_acl_ctx *ctx, const uint8_t **data, @@ -147 +148 @@ -index 8ffb40776c..32ebe3119b 100644 +index 3d61e79409..a3661b1b6b 100644 @@ -150 +151 @@ -@@ -124,10 +124,8 @@ rte_acl_classify_scalar(const struct rte_acl_ctx *ctx, const uint8_t **data, +@@ -121,10 +121,8 @@ rte_acl_classify_scalar(const struct rte_acl_ctx *ctx, const uint8_t **data,