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 67CF5A0C43; Tue, 10 Aug 2021 20:27:26 +0200 (CEST) Received: from [217.70.189.124] (localhost [127.0.0.1]) by mails.dpdk.org (Postfix) with ESMTP id 2DCAA40686; Tue, 10 Aug 2021 20:27:25 +0200 (CEST) Received: from inbox.dpdk.org (inbox.dpdk.org [95.142.172.178]) by mails.dpdk.org (Postfix) with ESMTP id 63B0B4014F for ; Tue, 10 Aug 2021 20:27:23 +0200 (CEST) Received: by inbox.dpdk.org (Postfix, from userid 33) id 35EF8A0C47; Tue, 10 Aug 2021 20:27:23 +0200 (CEST) From: bugzilla@dpdk.org To: dev@dpdk.org Date: Tue, 10 Aug 2021 18:27:22 +0000 X-Bugzilla-Reason: AssignedTo X-Bugzilla-Type: new X-Bugzilla-Watch-Reason: None X-Bugzilla-Product: DPDK X-Bugzilla-Component: ethdev X-Bugzilla-Version: 21.08 X-Bugzilla-Keywords: X-Bugzilla-Severity: normal X-Bugzilla-Who: brian90013@gmail.com X-Bugzilla-Status: UNCONFIRMED X-Bugzilla-Resolution: X-Bugzilla-Priority: Normal X-Bugzilla-Assigned-To: dev@dpdk.org X-Bugzilla-Target-Milestone: --- X-Bugzilla-Flags: X-Bugzilla-Changed-Fields: bug_id short_desc product version rep_platform op_sys bug_status bug_severity priority component assigned_to reporter target_milestone Message-ID: Content-Type: text/plain; charset="UTF-8" Content-Transfer-Encoding: quoted-printable X-Bugzilla-URL: http://bugs.dpdk.org/ Auto-Submitted: auto-generated X-Auto-Response-Suppress: All MIME-Version: 1.0 Subject: [dpdk-dev] [Bug 788] i40e: 16BYTE_RX_DESC build broken on FreeBSD-13 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" https://bugs.dpdk.org/show_bug.cgi?id=3D788 Bug ID: 788 Summary: i40e: 16BYTE_RX_DESC build broken on FreeBSD-13 Product: DPDK Version: 21.08 Hardware: x86 OS: FreeBSD Status: UNCONFIRMED Severity: normal Priority: Normal Component: ethdev Assignee: dev@dpdk.org Reporter: brian90013@gmail.com Target Milestone: --- Hello, I just tried compiling DPDK 21.08 and found my configuration no longer buil= ds on FreeBSD-13.0. With version 21.05, I defined RTE_LIBRTE_I40E_16BYTE_RX_DE= SC in rte_config.h as described in section "Use 16 Bytes RX Descriptor Size" of the current i40e PMD documentation. I also defined a similar variable RTE_LIBRTE_ICE_16BYTE_RX_DESC in rte_config.h for the ice PMD. This morning I brought in version 21.08 and watched it compile on FreeBSD-1= 2.2 (clang version 10.0.1) running on an 'Intel(R) Xeon(R) CPU E5-2637 v3'. The= n I tried building it on FreeBSD-13.0 (clang version 11.0.1) on a 'AMD Ryzen Threadripper 3990X 64-Core Processor' but the build died with a number of compilation errors related to avx512f features enabled in functions compiled without support for avx512f. Below I have an edited build log from the FreeBSD-12.2 system that works followed by the log from the FreeBSD-13.0 system that fails. Looking at the 12.2 log, there is a warning =E2=80=9CBinutils error with AVX512 assembly, = disabling AVX512 support=E2=80=9D that might be hiding this issue? Neither system has= hardware support for AVX-512 but it appears that the compiler does. Thank you for yo= ur help! *** FreeBSD-12.2 build that works *** The Meson build system Version: 0.58.1 Build type: native build Program cat found: YES (/bin/cat) Project name: DPDK Project version: 21.08.0 C compiler for the host machine: cc (clang 10.0.1 "FreeBSD clang version 10= .0.1 (git@github.com:llvm/llvm-project.git llvmorg-10.0.1-0-gef32c611aa2)") C linker for the host machine: cc ld.lld 10.0.1 Host machine cpu family: x86_64 Host machine cpu: x86_64 Compiler for C supports arguments -mno-avx512f: YES=20 config/x86/meson.build:9: WARNING: Binutils error with AVX512 assembly, disabling AVX512 support Compiler for C supports arguments -mavx512f: YES=20 Checking if "AVX512 checking" compiles: YES=20 Fetching value of define "__SSE4_2__" : 1=20 Fetching value of define "__AES__" : 1=20 Fetching value of define "__AVX__" : 1=20 Fetching value of define "__AVX2__" : 1=20 Fetching value of define "__AVX512BW__" :=20=20 Fetching value of define "__AVX512CD__" :=20=20 Fetching value of define "__AVX512DQ__" :=20=20 Fetching value of define "__AVX512F__" :=20=20 Fetching value of define "__AVX512VL__" :=20=20 Fetching value of define "__PCLMUL__" : 1=20 Fetching value of define "__RDRND__" : 1=20 Fetching value of define "__RDSEED__" :=20=20 Fetching value of define "__VPCLMULQDQ__" :=20=20 Compiler for C supports arguments -mpclmul: YES=20 Compiler for C supports arguments -maes: YES=20 *** FreeBSD-13.0 system that does not build *** The Meson build system Version: 0.58.1 Build type: native build Program cat found: YES (/bin/cat) Project name: DPDK Project version: 21.08.0 C compiler for the host machine: cc (clang 11.0.1 "FreeBSD clang version 11= .0.1 (git@github.com:llvm/llvm-project.git llvmorg-11.0.1-0-g43ff75f2c3fe)") C linker for the host machine: cc ld.lld 11.0.1 Host machine cpu family: x86_64 Host machine cpu: x86_64 Compiler for C supports arguments -mavx512f: YES=20 Checking if "AVX512 checking" compiles: YES=20 Fetching value of define "__SSE4_2__" : 1=20 Fetching value of define "__AES__" : 1=20 Fetching value of define "__AVX__" : 1=20 Fetching value of define "__AVX2__" : 1=20 Fetching value of define "__AVX512BW__" :=20=20 Fetching value of define "__AVX512CD__" :=20=20 Fetching value of define "__AVX512DQ__" :=20=20 Fetching value of define "__AVX512F__" :=20=20 Fetching value of define "__AVX512VL__" :=20=20 Fetching value of define "__PCLMUL__" : 1=20 Fetching value of define "__RDRND__" : 1=20 Fetching value of define "__RDSEED__" : 1=20 Fetching value of define "__VPCLMULQDQ__" :=20=20 Compiler for C supports arguments -mpclmul: YES=20 Compiler for C supports arguments -maes: YES=20 Compiler for C supports arguments -mavx512f: YES (cached) Compiler for C supports arguments -mavx512bw: YES=20 Compiler for C supports arguments -mavx512dq: YES=20 Compiler for C supports arguments -mavx512vl: YES=20 Compiler for C supports arguments -mvpclmulqdq: YES=20 Compiler for C supports arguments -mavx2: YES=20 Compiler for C supports arguments -mavx: YES=20 Compiler for C supports arguments -mavx512f -mavx512vl -mavx512cd -mavx512b= w: YES=20 Compiler for C supports arguments -mavx512f -mavx512dq: YES=20 FAILED: drivers/libtmp_rte_net_i40e.a.p/net_i40e_i40e_rxtx_vec_avx2.c.o=20 cc -Idrivers/libtmp_rte_net_i40e.a.p -Idrivers -I../drivers -Idrivers/net/i= 40e -I../drivers/net/i40e -Idrivers/net/i40e/base -I../drivers/net/i40e/base -Ilib/ethdev -I../lib/ethdev -I. -I.. -Iconfig -I../config -Ilib/eal/include -I../lib/eal/include -Ilib/eal/freebsd/include -I../lib/eal/freebsd/include -Ilib/eal/x86/include -I../lib/eal/x86/include -Ilib/eal/common -I../lib/eal/common -Ilib/eal -I../lib/eal -Ilib/kvargs -I../lib/kvargs -Ilib/metrics -I../lib/metrics -Ilib/telemetry -I../lib/telemetry -Ilib/net -I../lib/net -Ilib/mbuf -I../lib/mbuf -Ilib/mempool -I../lib/mempool -Ilib/= ring -I../lib/ring -Ilib/meter -I../lib/meter -Idrivers/bus/pci -I../drivers/bus= /pci -I../drivers/bus/pci/bsd -Ilib/pci -I../lib/pci -Idrivers/bus/vdev -I../drivers/bus/vdev -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fcolor-diagnostics -D_FILE_OFFSET_BITS=3D64 -Wall -Winvalid-pch -O3 -inclu= de rte_config.h -Wextra -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-exte= rns -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-address-of-packed-member -Wno-missing-field-initializers -D_GNU_SOURCE -D__BSD_VISIBLE -fPIC -march=3Dnative -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -DPF_DRIVER -DVF_DRIVER -DINTEGRATED_VF -DX722_A0_SUPPORT -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -DRTE_LOG_DEFAULT_LOGTYPE=3Dpmd.net.i40e -MD -MQ drivers/libtmp_rte_net_i40e.a.p/net_i40e_i40e_rxtx_vec_avx2.c.o -MF drivers/libtmp_rte_net_i40e.a.p/net_i40e_i40e_rxtx_vec_avx2.c.o.d -o drivers/libtmp_rte_net_i40e.a.p/net_i40e_i40e_rxtx_vec_avx2.c.o -c ../drivers/net/i40e/i40e_rxtx_vec_avx2.c In file included from ../drivers/net/i40e/i40e_rxtx_vec_avx2.c:13: ../drivers/net/i40e/i40e_rxtx_vec_common.h:337:22: error: always_inline function '_mm512_set1_epi64' requires target feature 'avx512f', but would be inlined into function 'i40e_rxq_rearm_common' that is compiled without supp= ort for 'avx512f' __m512i hdr_room =3D _mm512_set1_epi64(RTE_PKTMBUF_HEADROOM= ); ^ ../drivers/net/i40e/i40e_rxtx_vec_common.h:337:22: error: AVX vector return= of type '__m512i' (vector of 8 'long long' values) without 'avx512f' enabled changes the ABI ../drivers/net/i40e/i40e_rxtx_vec_common.h:385:5: error: '__builtin_ia32_inserti64x4' needs target feature avx512f =20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20= =20=20=20=20=20=20 _mm512_inserti64x4(_mm512_castsi256_si512(vaddr0_1), ^ /usr/lib/clang/11.0.1/include/avx512fintrin.h:7413:12: note: expanded from macro '_mm512_inserti64x4' (__m512i)__builtin_ia32_inserti64x4((__v8di)(__m512i)(A), \ ^ In file included from ../drivers/net/i40e/i40e_rxtx_vec_avx2.c:13: ../drivers/net/i40e/i40e_rxtx_vec_common.h:385:24: error: always_inline function '_mm512_castsi256_si512' requires target feature 'avx512f', but wo= uld be inlined into function 'i40e_rxq_rearm_common' that is compiled without support for 'avx512f' =20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20= =20=20=20=20=20=20 _mm512_inserti64x4(_mm512_castsi256_si512(vaddr0_1), ^ ../drivers/net/i40e/i40e_rxtx_vec_common.h:385:24: error: AVX vector return= of type '__m512i' (vector of 8 'long long' values) without 'avx512f' enabled changes the ABI ../drivers/net/i40e/i40e_rxtx_vec_common.h:388:5: error: '__builtin_ia32_inserti64x4' needs target feature avx512f =20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20= =20=20=20=20=20=20 _mm512_inserti64x4(_mm512_castsi256_si512(vaddr4_5), ^ /usr/lib/clang/11.0.1/include/avx512fintrin.h:7413:12: note: expanded from macro '_mm512_inserti64x4' (__m512i)__builtin_ia32_inserti64x4((__v8di)(__m512i)(A), \ ^ In file included from ../drivers/net/i40e/i40e_rxtx_vec_avx2.c:13: ../drivers/net/i40e/i40e_rxtx_vec_common.h:388:24: error: always_inline function '_mm512_castsi256_si512' requires target feature 'avx512f', but wo= uld be inlined into function 'i40e_rxq_rearm_common' that is compiled without support for 'avx512f' =20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20= =20=20=20=20=20=20 _mm512_inserti64x4(_mm512_castsi256_si512(vaddr4_5), ^ ../drivers/net/i40e/i40e_rxtx_vec_common.h:388:24: error: AVX vector return= of type '__m512i' (vector of 8 'long long' values) without 'avx512f' enabled changes the ABI ../drivers/net/i40e/i40e_rxtx_vec_common.h:392:18: error: always_inline function '_mm512_unpackhi_epi64' requires target feature 'avx512f', but wou= ld be inlined into function 'i40e_rxq_rearm_common' that is compiled without support for 'avx512f' dma_addr0_3 =3D _mm512_unpackhi_epi64(vaddr0_3, vaddr0_3); ^ ../drivers/net/i40e/i40e_rxtx_vec_common.h:392:18: error: AVX vector argume= nt of type '__m512i' (vector of 8 'long long' values) without 'avx512f' enabled changes the ABI ../drivers/net/i40e/i40e_rxtx_vec_common.h:393:18: error: always_inline function '_mm512_unpackhi_epi64' requires target feature 'avx512f', but wou= ld be inlined into function 'i40e_rxq_rearm_common' that is compiled without support for 'avx512f' dma_addr4_7 =3D _mm512_unpackhi_epi64(vaddr4_7, vaddr4_7); ^ ../drivers/net/i40e/i40e_rxtx_vec_common.h:393:18: error: AVX vector argume= nt of type '__m512i' (vector of 8 'long long' values) without 'avx512f' enabled changes the ABI ../drivers/net/i40e/i40e_rxtx_vec_common.h:396:18: error: always_inline function '_mm512_add_epi64' requires target feature 'avx512f', but would be inlined into function 'i40e_rxq_rearm_common' that is compiled without supp= ort for 'avx512f' dma_addr0_3 =3D _mm512_add_epi64(dma_addr0_3, hdr_r= oom); ^ ../drivers/net/i40e/i40e_rxtx_vec_common.h:396:18: error: AVX vector argume= nt of type '__m512i' (vector of 8 'long long' values) without 'avx512f' enabled changes the ABI ../drivers/net/i40e/i40e_rxtx_vec_common.h:397:18: error: always_inline function '_mm512_add_epi64' requires target feature 'avx512f', but would be inlined into function 'i40e_rxq_rearm_common' that is compiled without supp= ort for 'avx512f' dma_addr4_7 =3D _mm512_add_epi64(dma_addr4_7, hdr_r= oom); ^ ../drivers/net/i40e/i40e_rxtx_vec_common.h:397:18: error: AVX vector argume= nt of type '__m512i' (vector of 8 'long long' values) without 'avx512f' enabled changes the ABI ../drivers/net/i40e/i40e_rxtx_vec_common.h:400:4: error: always_inline func= tion '_mm512_store_si512' requires target feature 'avx512f', but would be inlined into function 'i40e_rxq_rearm_common' that is compiled without support for 'avx512f' _mm512_store_si512((__m512i *)&rxdp->read, dma_addr0_3); ^ ../drivers/net/i40e/i40e_rxtx_vec_common.h:400:4: error: AVX vector argumen= t of type '__m512i' (vector of 8 'long long' values) without 'avx512f' enabled changes the ABI ../drivers/net/i40e/i40e_rxtx_vec_common.h:401:4: error: always_inline func= tion '_mm512_store_si512' requires target feature 'avx512f', but would be inlined into function 'i40e_rxq_rearm_common' that is compiled without support for 'avx512f' _mm512_store_si512((__m512i *)&(rxdp + 4)->read, dma_addr4_7); ^ fatal error: too many errors emitted, stopping now [-ferror-limit=3D] 20 errors generated. [971/1893] Compiling C object drivers/libtmp_rte_net_ice.a.p/net_ice_ice_rxtx_vec_avx2.c.o FAILED: drivers/libtmp_rte_net_ice.a.p/net_ice_ice_rxtx_vec_avx2.c.o=20 cc -Idrivers/libtmp_rte_net_ice.a.p -Idrivers -I../drivers -Idrivers/net/ice -I../drivers/net/ice -Idrivers/net/ice/base -I../drivers/net/ice/base -Idrivers/common/iavf -I../drivers/common/iavf -Ilib/ethdev -I../lib/ethdev= -I. -I.. -Iconfig -I../config -Ilib/eal/include -I../lib/eal/include -Ilib/eal/freebsd/include -I../lib/eal/freebsd/include -Ilib/eal/x86/include -I../lib/eal/x86/include -Ilib/eal/common -I../lib/eal/common -Ilib/eal -I../lib/eal -Ilib/kvargs -I../lib/kvargs -Ilib/metrics -I../lib/metrics -Ilib/telemetry -I../lib/telemetry -Ilib/net -I../lib/net -Ilib/mbuf -I../lib/mbuf -Ilib/mempool -I../lib/mempool -Ilib/ring -I../lib/ring -Ilib/meter -I../lib/meter -Idrivers/bus/pci -I../drivers/bus/pci -I../drivers/bus/pci/bsd -Ilib/pci -I../lib/pci -Idrivers/bus/vdev -I../drivers/bus/vdev -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fcolor-diagnostics -D_FILE_OFFSET_BITS=3D64 -Wall -Winvalid-pch -O3 -inclu= de rte_config.h -Wextra -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-exte= rns -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-address-of-packed-member -Wno-missing-field-initializers -D_GNU_SOURCE -D__BSD_VISIBLE -fPIC -march=3Dnative -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -DCC_AVX2_SUP= PORT -DCC_AVX512_SUPPORT -DRTE_LOG_DEFAULT_LOGTYPE=3Dpmd.net.ice -MD -MQ drivers/libtmp_rte_net_ice.a.p/net_ice_ice_rxtx_vec_avx2.c.o -MF drivers/libtmp_rte_net_ice.a.p/net_ice_ice_rxtx_vec_avx2.c.o.d -o drivers/libtmp_rte_net_ice.a.p/net_ice_ice_rxtx_vec_avx2.c.o -c ../drivers/net/ice/ice_rxtx_vec_avx2.c In file included from ../drivers/net/ice/ice_rxtx_vec_avx2.c:5: ../drivers/net/ice/ice_rxtx_vec_common.h:422:22: error: always_inline funct= ion '_mm512_set1_epi64' requires target feature 'avx512f', but would be inlined into function 'ice_rxq_rearm_common' that is compiled without support for 'avx512f' __m512i hdr_room =3D _mm512_set1_epi64(RTE_PKTMBUF_HEADROOM= ); ^ ../drivers/net/ice/ice_rxtx_vec_common.h:422:22: error: AVX vector return of type '__m512i' (vector of 8 'long long' values) without 'avx512f' enabled changes the ABI ../drivers/net/ice/ice_rxtx_vec_common.h:470:5: error: '__builtin_ia32_inserti64x4' needs target feature avx512f =20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20= =20=20=20=20=20=20 _mm512_inserti64x4(_mm512_castsi256_si512(vaddr0_1), ^ /usr/lib/clang/11.0.1/include/avx512fintrin.h:7413:12: note: expanded from macro '_mm512_inserti64x4' (__m512i)__builtin_ia32_inserti64x4((__v8di)(__m512i)(A), \ ^ In file included from ../drivers/net/ice/ice_rxtx_vec_avx2.c:5: ../drivers/net/ice/ice_rxtx_vec_common.h:470:24: error: always_inline funct= ion '_mm512_castsi256_si512' requires target feature 'avx512f', but would be inlined into function 'ice_rxq_rearm_common' that is compiled without suppo= rt for 'avx512f' =20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20= =20=20=20=20=20=20 _mm512_inserti64x4(_mm512_castsi256_si512(vaddr0_1), ^ ../drivers/net/ice/ice_rxtx_vec_common.h:470:24: error: AVX vector return of type '__m512i' (vector of 8 'long long' values) without 'avx512f' enabled changes the ABI ../drivers/net/ice/ice_rxtx_vec_common.h:473:5: error: '__builtin_ia32_inserti64x4' needs target feature avx512f =20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20= =20=20=20=20=20=20 _mm512_inserti64x4(_mm512_castsi256_si512(vaddr4_5), ^ /usr/lib/clang/11.0.1/include/avx512fintrin.h:7413:12: note: expanded from macro '_mm512_inserti64x4' (__m512i)__builtin_ia32_inserti64x4((__v8di)(__m512i)(A), \ ^ In file included from ../drivers/net/ice/ice_rxtx_vec_avx2.c:5: ../drivers/net/ice/ice_rxtx_vec_common.h:473:24: error: always_inline funct= ion '_mm512_castsi256_si512' requires target feature 'avx512f', but would be inlined into function 'ice_rxq_rearm_common' that is compiled without suppo= rt for 'avx512f' =20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20= =20=20=20=20=20=20 _mm512_inserti64x4(_mm512_castsi256_si512(vaddr4_5), ^ ../drivers/net/ice/ice_rxtx_vec_common.h:473:24: error: AVX vector return of type '__m512i' (vector of 8 'long long' values) without 'avx512f' enabled changes the ABI ../drivers/net/ice/ice_rxtx_vec_common.h:477:18: error: always_inline funct= ion '_mm512_unpackhi_epi64' requires target feature 'avx512f', but would be inl= ined into function 'ice_rxq_rearm_common' that is compiled without support for 'avx512f' dma_addr0_3 =3D _mm512_unpackhi_epi64(vaddr0_3, vaddr0_3); ^ ../drivers/net/ice/ice_rxtx_vec_common.h:477:18: error: AVX vector argument= of type '__m512i' (vector of 8 'long long' values) without 'avx512f' enabled changes the ABI ../drivers/net/ice/ice_rxtx_vec_common.h:478:18: error: always_inline funct= ion '_mm512_unpackhi_epi64' requires target feature 'avx512f', but would be inl= ined into function 'ice_rxq_rearm_common' that is compiled without support for 'avx512f' dma_addr4_7 =3D _mm512_unpackhi_epi64(vaddr4_7, vaddr4_7); ^ ../drivers/net/ice/ice_rxtx_vec_common.h:478:18: error: AVX vector argument= of type '__m512i' (vector of 8 'long long' values) without 'avx512f' enabled changes the ABI ../drivers/net/ice/ice_rxtx_vec_common.h:481:18: error: always_inline funct= ion '_mm512_add_epi64' requires target feature 'avx512f', but would be inlined = into function 'ice_rxq_rearm_common' that is compiled without support for 'avx51= 2f' dma_addr0_3 =3D _mm512_add_epi64(dma_addr0_3, hdr_r= oom); ^ ../drivers/net/ice/ice_rxtx_vec_common.h:481:18: error: AVX vector argument= of type '__m512i' (vector of 8 'long long' values) without 'avx512f' enabled changes the ABI ../drivers/net/ice/ice_rxtx_vec_common.h:482:18: error: always_inline funct= ion '_mm512_add_epi64' requires target feature 'avx512f', but would be inlined = into function 'ice_rxq_rearm_common' that is compiled without support for 'avx51= 2f' dma_addr4_7 =3D _mm512_add_epi64(dma_addr4_7, hdr_r= oom); ^ ../drivers/net/ice/ice_rxtx_vec_common.h:482:18: error: AVX vector argument= of type '__m512i' (vector of 8 'long long' values) without 'avx512f' enabled changes the ABI ../drivers/net/ice/ice_rxtx_vec_common.h:485:4: error: always_inline functi= on '_mm512_store_si512' requires target feature 'avx512f', but would be inlined into function 'ice_rxq_rearm_common' that is compiled without support for 'avx512f' _mm512_store_si512((__m512i *)&rxdp->read, dma_addr0_3); ^ ../drivers/net/ice/ice_rxtx_vec_common.h:485:4: error: AVX vector argument = of type '__m512i' (vector of 8 'long long' values) without 'avx512f' enabled changes the ABI ../drivers/net/ice/ice_rxtx_vec_common.h:486:4: error: always_inline functi= on '_mm512_store_si512' requires target feature 'avx512f', but would be inlined into function 'ice_rxq_rearm_common' that is compiled without support for 'avx512f' _mm512_store_si512((__m512i *)&(rxdp + 4)->read, dma_addr4_7); ^ fatal error: too many errors emitted, stopping now [-ferror-limit=3D] 20 errors generated. [998/1893] Compiling C object drivers/libtmp_rte_net_ice.a.p/net_ice_ice_rxtx.c.o ../drivers/net/ice/ice_rxtx.c:129:60: warning: unused parameter 'rxq' [-Wunused-parameter] ice_rxd_to_pkt_fields_by_comms_aux_v1(struct ice_rx_queue *rxq, ^ ../drivers/net/ice/ice_rxtx.c:171:60: warning: unused parameter 'rxq' [-Wunused-parameter] ice_rxd_to_pkt_fields_by_comms_aux_v2(struct ice_rx_queue *rxq, ^ 2 warnings generated. [1006/1893] Compiling C object lib/librte_pipeline.a.p/pipeline_rte_table_action.c.o ninja: build stopped: subcommand failed. [109/890] Compiling C object drivers/libtmp_rte_net_i40e.a.p/net_i40e_i40e_rxtx_vec_avx2.c.o FAILED: drivers/libtmp_rte_net_i40e.a.p/net_i40e_i40e_rxtx_vec_avx2.c.o=20 cc -Idrivers/libtmp_rte_net_i40e.a.p -Idrivers -I../drivers -Idrivers/net/i= 40e -I../drivers/net/i40e -Idrivers/net/i40e/base -I../drivers/net/i40e/base -Ilib/ethdev -I../lib/ethdev -I. -I.. -Iconfig -I../config -Ilib/eal/include -I../lib/eal/include -Ilib/eal/freebsd/include -I../lib/eal/freebsd/include -Ilib/eal/x86/include -I../lib/eal/x86/include -Ilib/eal/common -I../lib/eal/common -Ilib/eal -I../lib/eal -Ilib/kvargs -I../lib/kvargs -Ilib/metrics -I../lib/metrics -Ilib/telemetry -I../lib/telemetry -Ilib/net -I../lib/net -Ilib/mbuf -I../lib/mbuf -Ilib/mempool -I../lib/mempool -Ilib/= ring -I../lib/ring -Ilib/meter -I../lib/meter -Idrivers/bus/pci -I../drivers/bus= /pci -I../drivers/bus/pci/bsd -Ilib/pci -I../lib/pci -Idrivers/bus/vdev -I../drivers/bus/vdev -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fcolor-diagnostics -D_FILE_OFFSET_BITS=3D64 -Wall -Winvalid-pch -O3 -inclu= de rte_config.h -Wextra -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-exte= rns -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-address-of-packed-member -Wno-missing-field-initializers -D_GNU_SOURCE -D__BSD_VISIBLE -fPIC -march=3Dnative -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -DPF_DRIVER -DVF_DRIVER -DINTEGRATED_VF -DX722_A0_SUPPORT -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -DRTE_LOG_DEFAULT_LOGTYPE=3Dpmd.net.i40e -MD -MQ drivers/libtmp_rte_net_i40e.a.p/net_i40e_i40e_rxtx_vec_avx2.c.o -MF drivers/libtmp_rte_net_i40e.a.p/net_i40e_i40e_rxtx_vec_avx2.c.o.d -o drivers/libtmp_rte_net_i40e.a.p/net_i40e_i40e_rxtx_vec_avx2.c.o -c ../drivers/net/i40e/i40e_rxtx_vec_avx2.c In file included from ../drivers/net/i40e/i40e_rxtx_vec_avx2.c:13: ../drivers/net/i40e/i40e_rxtx_vec_common.h:337:22: error: always_inline function '_mm512_set1_epi64' requires target feature 'avx512f', but would be inlined into function 'i40e_rxq_rearm_common' that is compiled without supp= ort for 'avx512f' __m512i hdr_room =3D _mm512_set1_epi64(RTE_PKTMBUF_HEADROOM= ); ^ ../drivers/net/i40e/i40e_rxtx_vec_common.h:337:22: error: AVX vector return= of type '__m512i' (vector of 8 'long long' values) without 'avx512f' enabled changes the ABI ../drivers/net/i40e/i40e_rxtx_vec_common.h:385:5: error: '__builtin_ia32_inserti64x4' needs target feature avx512f =20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20= =20=20=20=20=20=20 _mm512_inserti64x4(_mm512_castsi256_si512(vaddr0_1), ^ /usr/lib/clang/11.0.1/include/avx512fintrin.h:7413:12: note: expanded from macro '_mm512_inserti64x4' (__m512i)__builtin_ia32_inserti64x4((__v8di)(__m512i)(A), \ ^ In file included from ../drivers/net/i40e/i40e_rxtx_vec_avx2.c:13: ../drivers/net/i40e/i40e_rxtx_vec_common.h:385:24: error: always_inline function '_mm512_castsi256_si512' requires target feature 'avx512f', but wo= uld be inlined into function 'i40e_rxq_rearm_common' that is compiled without support for 'avx512f' =20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20= =20=20=20=20=20=20 _mm512_inserti64x4(_mm512_castsi256_si512(vaddr0_1), ^ ../drivers/net/i40e/i40e_rxtx_vec_common.h:385:24: error: AVX vector return= of type '__m512i' (vector of 8 'long long' values) without 'avx512f' enabled changes the ABI ../drivers/net/i40e/i40e_rxtx_vec_common.h:388:5: error: '__builtin_ia32_inserti64x4' needs target feature avx512f =20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20= =20=20=20=20=20=20 _mm512_inserti64x4(_mm512_castsi256_si512(vaddr4_5), ^ /usr/lib/clang/11.0.1/include/avx512fintrin.h:7413:12: note: expanded from macro '_mm512_inserti64x4' (__m512i)__builtin_ia32_inserti64x4((__v8di)(__m512i)(A), \ ^ In file included from ../drivers/net/i40e/i40e_rxtx_vec_avx2.c:13: ../drivers/net/i40e/i40e_rxtx_vec_common.h:388:24: error: always_inline function '_mm512_castsi256_si512' requires target feature 'avx512f', but wo= uld be inlined into function 'i40e_rxq_rearm_common' that is compiled without support for 'avx512f' =20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20= =20=20=20=20=20=20 _mm512_inserti64x4(_mm512_castsi256_si512(vaddr4_5), ^ ../drivers/net/i40e/i40e_rxtx_vec_common.h:388:24: error: AVX vector return= of type '__m512i' (vector of 8 'long long' values) without 'avx512f' enabled changes the ABI ../drivers/net/i40e/i40e_rxtx_vec_common.h:392:18: error: always_inline function '_mm512_unpackhi_epi64' requires target feature 'avx512f', but wou= ld be inlined into function 'i40e_rxq_rearm_common' that is compiled without support for 'avx512f' dma_addr0_3 =3D _mm512_unpackhi_epi64(vaddr0_3, vaddr0_3); ^ ../drivers/net/i40e/i40e_rxtx_vec_common.h:392:18: error: AVX vector argume= nt of type '__m512i' (vector of 8 'long long' values) without 'avx512f' enabled changes the ABI ../drivers/net/i40e/i40e_rxtx_vec_common.h:393:18: error: always_inline function '_mm512_unpackhi_epi64' requires target feature 'avx512f', but wou= ld be inlined into function 'i40e_rxq_rearm_common' that is compiled without support for 'avx512f' dma_addr4_7 =3D _mm512_unpackhi_epi64(vaddr4_7, vaddr4_7); ^ ../drivers/net/i40e/i40e_rxtx_vec_common.h:393:18: error: AVX vector argume= nt of type '__m512i' (vector of 8 'long long' values) without 'avx512f' enabled changes the ABI ../drivers/net/i40e/i40e_rxtx_vec_common.h:396:18: error: always_inline function '_mm512_add_epi64' requires target feature 'avx512f', but would be inlined into function 'i40e_rxq_rearm_common' that is compiled without supp= ort for 'avx512f' dma_addr0_3 =3D _mm512_add_epi64(dma_addr0_3, hdr_r= oom); ^ ../drivers/net/i40e/i40e_rxtx_vec_common.h:396:18: error: AVX vector argume= nt of type '__m512i' (vector of 8 'long long' values) without 'avx512f' enabled changes the ABI ../drivers/net/i40e/i40e_rxtx_vec_common.h:397:18: error: always_inline function '_mm512_add_epi64' requires target feature 'avx512f', but would be inlined into function 'i40e_rxq_rearm_common' that is compiled without supp= ort for 'avx512f' dma_addr4_7 =3D _mm512_add_epi64(dma_addr4_7, hdr_r= oom); ^ ../drivers/net/i40e/i40e_rxtx_vec_common.h:397:18: error: AVX vector argume= nt of type '__m512i' (vector of 8 'long long' values) without 'avx512f' enabled changes the ABI ../drivers/net/i40e/i40e_rxtx_vec_common.h:400:4: error: always_inline func= tion '_mm512_store_si512' requires target feature 'avx512f', but would be inlined into function 'i40e_rxq_rearm_common' that is compiled without support for 'avx512f' _mm512_store_si512((__m512i *)&rxdp->read, dma_addr0_3); ^ ../drivers/net/i40e/i40e_rxtx_vec_common.h:400:4: error: AVX vector argumen= t of type '__m512i' (vector of 8 'long long' values) without 'avx512f' enabled changes the ABI ../drivers/net/i40e/i40e_rxtx_vec_common.h:401:4: error: always_inline func= tion '_mm512_store_si512' requires target feature 'avx512f', but would be inlined into function 'i40e_rxq_rearm_common' that is compiled without support for 'avx512f' _mm512_store_si512((__m512i *)&(rxdp + 4)->read, dma_addr4_7); ^ fatal error: too many errors emitted, stopping now [-ferror-limit=3D] 20 errors generated. [119/890] Compiling C object drivers/libtmp_rte_net_ice.a.p/net_ice_ice_rxtx_vec_avx2.c.o FAILED: drivers/libtmp_rte_net_ice.a.p/net_ice_ice_rxtx_vec_avx2.c.o=20 cc -Idrivers/libtmp_rte_net_ice.a.p -Idrivers -I../drivers -Idrivers/net/ice -I../drivers/net/ice -Idrivers/net/ice/base -I../drivers/net/ice/base -Idrivers/common/iavf -I../drivers/common/iavf -Ilib/ethdev -I../lib/ethdev= -I. -I.. -Iconfig -I../config -Ilib/eal/include -I../lib/eal/include -Ilib/eal/freebsd/include -I../lib/eal/freebsd/include -Ilib/eal/x86/include -I../lib/eal/x86/include -Ilib/eal/common -I../lib/eal/common -Ilib/eal -I../lib/eal -Ilib/kvargs -I../lib/kvargs -Ilib/metrics -I../lib/metrics -Ilib/telemetry -I../lib/telemetry -Ilib/net -I../lib/net -Ilib/mbuf -I../lib/mbuf -Ilib/mempool -I../lib/mempool -Ilib/ring -I../lib/ring -Ilib/meter -I../lib/meter -Idrivers/bus/pci -I../drivers/bus/pci -I../drivers/bus/pci/bsd -Ilib/pci -I../lib/pci -Idrivers/bus/vdev -I../drivers/bus/vdev -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fcolor-diagnostics -D_FILE_OFFSET_BITS=3D64 -Wall -Winvalid-pch -O3 -inclu= de rte_config.h -Wextra -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-exte= rns -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-address-of-packed-member -Wno-missing-field-initializers -D_GNU_SOURCE -D__BSD_VISIBLE -fPIC -march=3Dnative -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -DCC_AVX2_SUP= PORT -DCC_AVX512_SUPPORT -DRTE_LOG_DEFAULT_LOGTYPE=3Dpmd.net.ice -MD -MQ drivers/libtmp_rte_net_ice.a.p/net_ice_ice_rxtx_vec_avx2.c.o -MF drivers/libtmp_rte_net_ice.a.p/net_ice_ice_rxtx_vec_avx2.c.o.d -o drivers/libtmp_rte_net_ice.a.p/net_ice_ice_rxtx_vec_avx2.c.o -c ../drivers/net/ice/ice_rxtx_vec_avx2.c In file included from ../drivers/net/ice/ice_rxtx_vec_avx2.c:5: ../drivers/net/ice/ice_rxtx_vec_common.h:422:22: error: always_inline funct= ion '_mm512_set1_epi64' requires target feature 'avx512f', but would be inlined into function 'ice_rxq_rearm_common' that is compiled without support for 'avx512f' __m512i hdr_room =3D _mm512_set1_epi64(RTE_PKTMBUF_HEADROOM= ); ^ ../drivers/net/ice/ice_rxtx_vec_common.h:422:22: error: AVX vector return of type '__m512i' (vector of 8 'long long' values) without 'avx512f' enabled changes the ABI ../drivers/net/ice/ice_rxtx_vec_common.h:470:5: error: '__builtin_ia32_inserti64x4' needs target feature avx512f =20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20= =20=20=20=20=20=20 _mm512_inserti64x4(_mm512_castsi256_si512(vaddr0_1), ^ /usr/lib/clang/11.0.1/include/avx512fintrin.h:7413:12: note: expanded from macro '_mm512_inserti64x4' (__m512i)__builtin_ia32_inserti64x4((__v8di)(__m512i)(A), \ ^ In file included from ../drivers/net/ice/ice_rxtx_vec_avx2.c:5: ../drivers/net/ice/ice_rxtx_vec_common.h:470:24: error: always_inline funct= ion '_mm512_castsi256_si512' requires target feature 'avx512f', but would be inlined into function 'ice_rxq_rearm_common' that is compiled without suppo= rt for 'avx512f' =20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20= =20=20=20=20=20=20 _mm512_inserti64x4(_mm512_castsi256_si512(vaddr0_1), ^ ../drivers/net/ice/ice_rxtx_vec_common.h:470:24: error: AVX vector return of type '__m512i' (vector of 8 'long long' values) without 'avx512f' enabled changes the ABI ../drivers/net/ice/ice_rxtx_vec_common.h:473:5: error: '__builtin_ia32_inserti64x4' needs target feature avx512f =20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20= =20=20=20=20=20=20 _mm512_inserti64x4(_mm512_castsi256_si512(vaddr4_5), ^ /usr/lib/clang/11.0.1/include/avx512fintrin.h:7413:12: note: expanded from macro '_mm512_inserti64x4' (__m512i)__builtin_ia32_inserti64x4((__v8di)(__m512i)(A), \ ^ In file included from ../drivers/net/ice/ice_rxtx_vec_avx2.c:5: ../drivers/net/ice/ice_rxtx_vec_common.h:473:24: error: always_inline funct= ion '_mm512_castsi256_si512' requires target feature 'avx512f', but would be inlined into function 'ice_rxq_rearm_common' that is compiled without suppo= rt for 'avx512f' =20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20= =20=20=20=20=20=20 _mm512_inserti64x4(_mm512_castsi256_si512(vaddr4_5), ^ ../drivers/net/ice/ice_rxtx_vec_common.h:473:24: error: AVX vector return of type '__m512i' (vector of 8 'long long' values) without 'avx512f' enabled changes the ABI ../drivers/net/ice/ice_rxtx_vec_common.h:477:18: error: always_inline funct= ion '_mm512_unpackhi_epi64' requires target feature 'avx512f', but would be inl= ined into function 'ice_rxq_rearm_common' that is compiled without support for 'avx512f' dma_addr0_3 =3D _mm512_unpackhi_epi64(vaddr0_3, vaddr0_3); ^ ../drivers/net/ice/ice_rxtx_vec_common.h:477:18: error: AVX vector argument= of type '__m512i' (vector of 8 'long long' values) without 'avx512f' enabled changes the ABI ../drivers/net/ice/ice_rxtx_vec_common.h:478:18: error: always_inline funct= ion '_mm512_unpackhi_epi64' requires target feature 'avx512f', but would be inl= ined into function 'ice_rxq_rearm_common' that is compiled without support for 'avx512f' dma_addr4_7 =3D _mm512_unpackhi_epi64(vaddr4_7, vaddr4_7); ^ ../drivers/net/ice/ice_rxtx_vec_common.h:478:18: error: AVX vector argument= of type '__m512i' (vector of 8 'long long' values) without 'avx512f' enabled changes the ABI ../drivers/net/ice/ice_rxtx_vec_common.h:481:18: error: always_inline funct= ion '_mm512_add_epi64' requires target feature 'avx512f', but would be inlined = into function 'ice_rxq_rearm_common' that is compiled without support for 'avx51= 2f' dma_addr0_3 =3D _mm512_add_epi64(dma_addr0_3, hdr_r= oom); ^ ../drivers/net/ice/ice_rxtx_vec_common.h:481:18: error: AVX vector argument= of type '__m512i' (vector of 8 'long long' values) without 'avx512f' enabled changes the ABI ../drivers/net/ice/ice_rxtx_vec_common.h:482:18: error: always_inline funct= ion '_mm512_add_epi64' requires target feature 'avx512f', but would be inlined = into function 'ice_rxq_rearm_common' that is compiled without support for 'avx51= 2f' dma_addr4_7 =3D _mm512_add_epi64(dma_addr4_7, hdr_r= oom); ^ ../drivers/net/ice/ice_rxtx_vec_common.h:482:18: error: AVX vector argument= of type '__m512i' (vector of 8 'long long' values) without 'avx512f' enabled changes the ABI ../drivers/net/ice/ice_rxtx_vec_common.h:485:4: error: always_inline functi= on '_mm512_store_si512' requires target feature 'avx512f', but would be inlined into function 'ice_rxq_rearm_common' that is compiled without support for 'avx512f' _mm512_store_si512((__m512i *)&rxdp->read, dma_addr0_3); ^ ../drivers/net/ice/ice_rxtx_vec_common.h:485:4: error: AVX vector argument = of type '__m512i' (vector of 8 'long long' values) without 'avx512f' enabled changes the ABI ../drivers/net/ice/ice_rxtx_vec_common.h:486:4: error: always_inline functi= on '_mm512_store_si512' requires target feature 'avx512f', but would be inlined into function 'ice_rxq_rearm_common' that is compiled without support for 'avx512f' _mm512_store_si512((__m512i *)&(rxdp + 4)->read, dma_addr4_7); ^ fatal error: too many errors emitted, stopping now [-ferror-limit=3D] 20 errors generated. ninja: build stopped: subcommand failed. --=20 You are receiving this mail because: You are the assignee for the bug.=