DPDK-dev Archive on lore.kernel.org
 help / color / mirror / Atom feed
* [PATCH] hash: fix GFNI helpers for building with -O0
@ 2026-09-30  8:49 David Marchand
  2026-09-30  8:53 ` Bruce Richardson
  0 siblings, 1 reply; 3+ messages in thread
From: David Marchand @ 2026-09-30  8:49 UTC (permalink / raw)
  To: dev
  Cc: Yipeng Wang, Sameh Gobriel, Bruce Richardson, Vladimir Medvedkin,
	Konstantin Ananyev

Similarly to commit da31ef54c865 ("hash: fix GFNI stubs export"),
fix "internal" helpers used by public inline helpers by removing the
incorrect __rte_internal annotation.

The issue is usually not seen as those helpers get inlined under
standard compiler optimization level, but it becomes visible when
building with -O0.

Fixes: 4fd8c4cb0de1 ("hash: add new Toeplitz hash implementation")

Signed-off-by: David Marchand <david.marchand@redhat.com>
---
 lib/hash/rte_thash_x86_gfni.h | 3 ---
 1 file changed, 3 deletions(-)

diff --git a/lib/hash/rte_thash_x86_gfni.h b/lib/hash/rte_thash_x86_gfni.h
index 69973503fd..e5abdf2474 100644
--- a/lib/hash/rte_thash_x86_gfni.h
+++ b/lib/hash/rte_thash_x86_gfni.h
@@ -13,7 +13,6 @@
  */
 
 #include <rte_bitops.h>
-#include <rte_compat.h>
 #include <rte_vect.h>
 
 #ifdef __cplusplus
@@ -29,7 +28,6 @@ extern "C" {
 #define RTE_THASH_PERM_MSK_2		0xf0f0f0f0f0f0f0f0
 #define RTE_THASH_REWIND_MSK		0x0000000000113377
 
-__rte_internal
 static inline void
 __rte_thash_xor_reduce(__m512i xor_acc, uint32_t *val_1, uint32_t *val_2)
 {
@@ -64,7 +62,6 @@ __rte_thash_xor_reduce(__m512i xor_acc, uint32_t *val_1, uint32_t *val_2)
 #endif
 }
 
-__rte_internal
 static inline __m512i
 __rte_thash_gfni(const uint64_t *mtrx, const uint8_t *tuple,
 	const uint8_t *secondary_tuple, int len)
-- 
2.54.0


^ permalink raw reply related	[flat|nested] 3+ messages in thread

end of thread, other threads:[~2026-09-30  9:18 UTC | newest]

Thread overview: 3+ messages (download: mbox.gz follow: Atom feed
-- links below jump to the message on this page --
2026-09-30  8:49 [PATCH] hash: fix GFNI helpers for building with -O0 David Marchand
2026-09-30  8:53 ` Bruce Richardson
2026-09-30  9:17   ` David Marchand

This is a public inbox, see mirroring instructions
for how to clone and mirror all data and code used for this inbox