diff mbox series

[ovs-dev,v2] sparse: Fix build with DPDK and GCC 12.

Message ID 20230209125759.927942-1-david.marchand@redhat.com
State Accepted
Commit fc3d5e1dad0a45a84fae2b6157a5d55e40adf429
Headers show
Series [ovs-dev,v2] sparse: Fix build with DPDK and GCC 12. | expand

Checks

Context Check Description
ovsrobot/apply-robot success apply and check: success
ovsrobot/github-robot-_Build_and_Test fail github build: failed
ovsrobot/intel-ovs-compilation success test: success

Commit Message

David Marchand Feb. 9, 2023, 12:57 p.m. UTC
rte_vect.h pulls some AVX512 instrinsics headers added in GCC 12 [1]
trigger a lot of warnings:

libtool: compile:  env "REAL_CC=ccache gcc" "CHECK=sparse -Wsparse-error
	-I ../include/sparse -I ../include -m64 -I /usr/local/include
	" cgcc -target=x86_64 -target=host_os_specs -D__MMX__=1
	-D__MMX_WITH_SSE__=1 -D__SSE2_MATH__=1 -D__SSE_MATH__=1
	-D__SSE__=1 -D__SSE2__=1 -DHAVE_CONFIG_H -I. -I.. -I ../include
	-I ./include -I ../lib -I ./lib -Wstrict-prototypes -Wall
	-Wextra -Wno-sign-compare -Wpointer-arith -Wformat
	-Wformat-security -Wswitch-enum -Wunused-parameter
	-Wbad-function-cast -Wcast-align -Wstrict-prototypes
	-Wold-style-definition -Wmissing-prototypes
	-Wmissing-field-initializers -fno-strict-aliasing
	-Wswitch-bool -Wlogical-not-parentheses -Wsizeof-array-argument
	-Wbool-compare -Wshift-negative-value -Wduplicated-cond -Wshadow
	-Wmultistatement-macros -Wcast-align=strict -mssse3
	-I/home/dmarchan/git/pub/dpdk.org/22.11/install/include
	-include rte_config.h -I/usr/local/include -Werror
	-D_FILE_OFFSET_BITS=64 -g -O2 -MT lib/bfd.lo -MD -MP
	-MF lib/.deps/bfd.Tpo -c ../lib/bfd.c -o lib/bfd.o
../lib/bfd.c: note: in included file (through
	/usr/lib/gcc/x86_64-redhat-linux/12//include/immintrin.h,
	/usr/lib/gcc/x86_64-redhat-linux/12//include/x86intrin.h, ...):
/usr/lib/gcc/x86_64-redhat-linux/12//include/avx512fp16intrin.h:38:9:
	error: '_Float16' has implicit type
/usr/lib/gcc/x86_64-redhat-linux/12//include/avx512fp16intrin.h:38:18:
	error: Expected ; at end of declaration
/usr/lib/gcc/x86_64-redhat-linux/12//include/avx512fp16intrin.h:38:18:
	error: got __v8hf
/usr/lib/gcc/x86_64-redhat-linux/12//include/avx512fp16intrin.h:62:41:
	error: Expected ; at end of statement
/usr/lib/gcc/x86_64-redhat-linux/12//include/avx512fp16intrin.h:62:41:
	error: got {
/usr/lib/gcc/x86_64-redhat-linux/12//include/avx512fp16intrin.h:420:32:
	error: Expected ) in expression
/usr/lib/gcc/x86_64-redhat-linux/12//include/avx512fp16intrin.h:420:32:
	error: got __A
/usr/lib/gcc/x86_64-redhat-linux/12//include/avx512fp16intrin.h:2271:61:
	error: Expected ) in function call
/usr/lib/gcc/x86_64-redhat-linux/12//include/avx512fp16intrin.h:2271:61:
	error: got __A
/usr/lib/gcc/x86_64-redhat-linux/12//include/avx512fp16intrin.h:2279:61:
	error: Expected ) in function call
/usr/lib/gcc/x86_64-redhat-linux/12//include/avx512fp16intrin.h:2279:61:
	error: got __A
/usr/lib/gcc/x86_64-redhat-linux/12//include/avx512fp16intrin.h:2328:50:
	error: Expected ) in function call
[...]

Besides, the list of headers by rte_memcpy.h is now out of sync with DPDK.
OVS takes care to include the right headers in its sources.
Simply make this header self-sufficient.

1: https://gcc.gnu.org/git/?p=gcc.git;a=commit;h=a68412117fa4

Signed-off-by: David Marchand <david.marchand@redhat.com>
---
Changes since v1:
- fixed header includes so that this fake rte_memcpy.h is
  self-sufficient,

---
 include/sparse/rte_memcpy.h | 5 +----
 1 file changed, 1 insertion(+), 4 deletions(-)

Comments

Ilya Maximets Feb. 10, 2023, 7:27 p.m. UTC | #1
On 2/9/23 13:57, David Marchand wrote:
> rte_vect.h pulls some AVX512 instrinsics headers added in GCC 12 [1]
> trigger a lot of warnings:
> 
> libtool: compile:  env "REAL_CC=ccache gcc" "CHECK=sparse -Wsparse-error
> 	-I ../include/sparse -I ../include -m64 -I /usr/local/include
> 	" cgcc -target=x86_64 -target=host_os_specs -D__MMX__=1
> 	-D__MMX_WITH_SSE__=1 -D__SSE2_MATH__=1 -D__SSE_MATH__=1
> 	-D__SSE__=1 -D__SSE2__=1 -DHAVE_CONFIG_H -I. -I.. -I ../include
> 	-I ./include -I ../lib -I ./lib -Wstrict-prototypes -Wall
> 	-Wextra -Wno-sign-compare -Wpointer-arith -Wformat
> 	-Wformat-security -Wswitch-enum -Wunused-parameter
> 	-Wbad-function-cast -Wcast-align -Wstrict-prototypes
> 	-Wold-style-definition -Wmissing-prototypes
> 	-Wmissing-field-initializers -fno-strict-aliasing
> 	-Wswitch-bool -Wlogical-not-parentheses -Wsizeof-array-argument
> 	-Wbool-compare -Wshift-negative-value -Wduplicated-cond -Wshadow
> 	-Wmultistatement-macros -Wcast-align=strict -mssse3
> 	-I/home/dmarchan/git/pub/dpdk.org/22.11/install/include
> 	-include rte_config.h -I/usr/local/include -Werror
> 	-D_FILE_OFFSET_BITS=64 -g -O2 -MT lib/bfd.lo -MD -MP
> 	-MF lib/.deps/bfd.Tpo -c ../lib/bfd.c -o lib/bfd.o
> ../lib/bfd.c: note: in included file (through
> 	/usr/lib/gcc/x86_64-redhat-linux/12//include/immintrin.h,
> 	/usr/lib/gcc/x86_64-redhat-linux/12//include/x86intrin.h, ...):
> /usr/lib/gcc/x86_64-redhat-linux/12//include/avx512fp16intrin.h:38:9:
> 	error: '_Float16' has implicit type
> /usr/lib/gcc/x86_64-redhat-linux/12//include/avx512fp16intrin.h:38:18:
> 	error: Expected ; at end of declaration
> /usr/lib/gcc/x86_64-redhat-linux/12//include/avx512fp16intrin.h:38:18:
> 	error: got __v8hf
> /usr/lib/gcc/x86_64-redhat-linux/12//include/avx512fp16intrin.h:62:41:
> 	error: Expected ; at end of statement
> /usr/lib/gcc/x86_64-redhat-linux/12//include/avx512fp16intrin.h:62:41:
> 	error: got {
> /usr/lib/gcc/x86_64-redhat-linux/12//include/avx512fp16intrin.h:420:32:
> 	error: Expected ) in expression
> /usr/lib/gcc/x86_64-redhat-linux/12//include/avx512fp16intrin.h:420:32:
> 	error: got __A
> /usr/lib/gcc/x86_64-redhat-linux/12//include/avx512fp16intrin.h:2271:61:
> 	error: Expected ) in function call
> /usr/lib/gcc/x86_64-redhat-linux/12//include/avx512fp16intrin.h:2271:61:
> 	error: got __A
> /usr/lib/gcc/x86_64-redhat-linux/12//include/avx512fp16intrin.h:2279:61:
> 	error: Expected ) in function call
> /usr/lib/gcc/x86_64-redhat-linux/12//include/avx512fp16intrin.h:2279:61:
> 	error: got __A
> /usr/lib/gcc/x86_64-redhat-linux/12//include/avx512fp16intrin.h:2328:50:
> 	error: Expected ) in function call
> [...]
> 
> Besides, the list of headers by rte_memcpy.h is now out of sync with DPDK.
> OVS takes care to include the right headers in its sources.
> Simply make this header self-sufficient.
> 
> 1: https://gcc.gnu.org/git/?p=gcc.git;a=commit;h=a68412117fa4
> 
> Signed-off-by: David Marchand <david.marchand@redhat.com>
> ---
> Changes since v1:
> - fixed header includes so that this fake rte_memcpy.h is
>   self-sufficient,
> 
> ---
>  include/sparse/rte_memcpy.h | 5 +----
>  1 file changed, 1 insertion(+), 4 deletions(-)

Thanks!  Applied and backpotred down to 2.17.

Best regards, Ilya Maximets.
diff mbox series

Patch

diff --git a/include/sparse/rte_memcpy.h b/include/sparse/rte_memcpy.h
index 5cd3f013ea..ec88500242 100644
--- a/include/sparse/rte_memcpy.h
+++ b/include/sparse/rte_memcpy.h
@@ -20,11 +20,8 @@ 
 #error "Use this header only with sparse.  It is not a correct implementation."
 #endif
 
-/* Include the same headers as the real rte_memcpy(). */
-#include <stdio.h>
+#include <stddef.h>
 #include <stdint.h>
-#include <string.h>
-#include <rte_vect.h>
 
 /* Declare the same functions as the real rte_memcpy.h, without defining them.
  * This gives sparse the information it needs without provoking sparse's