Test-Label: Intel-compilation Test-Status: FAILURE http://dpdk.org/patch/120522 _Compilation issues_ Submitter: Morten Brørup Date: 2022-12-07 07:35:44 Reply_mail: <20221207073544.82950-1-mb@smartsharesystems.com> DPDK git baseline: Repo:dpdk, CommitID: 6c8aed5ab7f6dbed8e71199504fa227f5f60c6fd Meson Build Summary: 25 Builds Done, 0 Successful, 25 Failures, 0 Blocked +--------------+------------+--------------+------------+------------+-----------+----------+------------+ | os | gcc-static | clang-static | icc-static | gcc-shared | gcc-debug | document | gcc-16byte | +--------------+------------+--------------+------------+------------+-----------+----------+------------+ | FC36-64 | fail | fail | | | | | | | FreeBSD13-64 | fail | fail | | fail | fail | | | | RHEL86-64 | fail | fail | | fail | fail | | | | SUSE15-64 | fail | fail | | | | | | | RHEL90-64 | fail | | | | | | | | UB2004-64 | fail | fail | | | | fail | | | UB2204-32 | fail | | | | | | | | UB2204-64 | fail | fail | | | | fail | fail | | CentOS79-64 | fail | | | | | | | | RHEL86-64Rt | fail | | | | | | | | UB2210-64 | fail | | | | | | | | FC37-64 | fail | | | | | | | +--------------+------------+--------------+------------+------------+-----------+----------+------------+ Comments: Because of DPDK bug (https://bugs.dpdk.org/show_bug.cgi?id=928), All the dpdk-next-* branch add `Ddisable_drivers=event/cnxk` option when build with ICC complier. Test environment and configuration as below: OS: FC36-64 Kernel Version: 5.17.7-300.fc36.x86_64 GCC Version: gcc (GCC) 12.1.1 20220507 (Red Hat 12.1.1-1) Clang Version: 14.0.0 (Fedora 14.0.0-1.fc36) x86_64-native-linuxapp-gcc x86_64-native-linuxapp-clang OS: FreeBSD13-64 Kernel Version: 13.1-RELEASE GCC Version: gcc (FreeBSD Ports Collection) 10.3.0 Clang Version: 13.0.0 (git@github.com:llvm/llvm-project.git llvmorg-13.0.0-0-gd7b669b3a303) x86_64-native-bsdapp-gcc x86_64-native-bsdapp-clang x86_64-native-bsdapp-gcc+shared x86_64-native-bsdapp-gcc+debug OS: RHEL86-64 Kernel Version: 4.18.0-372.9.1.el8.x86_64 GCC Version: gcc (GCC) 8.5.0 20210514 (Red Hat 8.5.0-13) Clang Version: 14.0.0 (Red Hat 14.0.0-1.module_el8.7.0+1142+5343df54) x86_64-native-linuxapp-gcc x86_64-native-linuxapp-clang x86_64-native-linuxapp-gcc+shared x86_64-native-linuxapp-gcc+debug OS: SUSE15-64 Kernel Version: 5.14.21-150400.22-default GCC Version: gcc (SUSE Linux) 7.5.0 Clang Version: 11.0.1 x86_64-native-linuxapp-clang x86_64-native-linuxapp-gcc OS: RHEL90-64 Kernel Version: 5.14.0-70.13.1.el9_0.x86_64 GCC Version: gcc (GCC) 11.2.1 20220127 (Red Hat 11.2.1-9) Clang Version: 13.0.1 (Red Hat 13.0.1-1.el9) x86_64-native-linuxapp-gcc OS: UB2004-64 Kernel Version: 5.8.0-48-generic GCC Version: gcc (Ubuntu 10.3.0-1ubuntu1~20.04) 10.3.0 Clang Version: 10.0.0-4ubuntu1 x86_64-native-linuxapp-clang x86_64-native-linuxapp-gcc x86_64-native-linuxapp-doc OS: UB2204-32 Kernel Version: 5.15.0-25-generic GCC Version: gcc (Ubuntu 11.2.0-19ubuntu1) 11.2.0 Clang Version: NA i686-native-linuxapp-gcc OS: UB2204-64 Kernel Version: 5.15.0-25-generic GCC Version: gcc (Ubuntu 11.2.0-19ubuntu1) 11.2.0 Clang Version: 14.0.0-1ubuntu1 x86_64-native-linuxapp-gcc+16byte x86_64-native-linuxapp-gcc x86_64-native-linuxapp-clang x86_64-native-linuxapp-doc OS: CentOS79-64 Kernel Version: 3.10.0-1160.76.1.el7.x86_64 GCC Version: gcc (GCC) 4.8.5 20150623 (Red Hat 4.8.5-44) Clang Version: 3.4.2 (tags/RELEASE_34/dot2-final) x86_64-native-linuxapp-gcc OS: RHEL86-64Rt Kernel Version: 4.18.0-372.9.1.rt7.166.el8.x86_64 GCC Version: gcc (GCC) 8.5.0 20210514 (Red Hat 8.5.0-13) Clang Version: 14.0.0 (Red Hat 14.0.0-1.module_el8.7.0+1142+5343df54) x86_64-native-linuxapp-gcc OS: UB2210-64 Kernel Version: 5.19.0-21-generic GCC Version: gcc (Ubuntu 12.2.0-3ubuntu1) 12.2.0 Clang Version: 15.0.2-1 x86_64-native-linuxapp-gcc OS: FC37-64 Kernel Version: 6.0.7-301.fc37.x86_64 GCC Version: gcc (GCC) 12.2.1 20220819 (Red Hat 12.2.1-2) Clang Version: 15.0.4 (Fedora 15.0.4-1.fc37) x86_64-native-linuxapp-gcc *Build Failed #1: OS: FC36-64 Target: x86_64-native-linuxapp-gcc FAILED: drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o gcc -Idrivers/net/i40e/libi40e_avx512_lib.a.p -Idrivers/net/i40e -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/linux/include -I../lib/eal/linux/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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fdiagnostics-color=always -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O3 -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-address-of-packed-member -Wno-packed-not-aligned -Wno-missing-field-initializers -Wno-zero-length-bounds -D_GNU_SOURCE -fPIC -march=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -Wno-format-truncation -DPF_DRIVER -DVF_DRIVER -DINTEGRATED_VF -DX722_A0_SUPPORT -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -MF drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o.d -o drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -c ../drivers/net/i40e/i40e_rxtx_vec_avx512.c In file included from ../lib/eal/include/dev_driver.h:12, from ../lib/ethdev/ethdev_driver.h:22, from ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:6: ../drivers/net/i40e/i40e_rxtx_common_avx.h: In function ‘i40e_rxq_rearm_common’: ../drivers/net/i40e/i40e_rxtx_common_avx.h:61:34: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 61 | RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != | ^~~~~~~~ ../lib/eal/include/rte_common.h:417:65: note: in definition of macro ‘RTE_BUILD_BUG_ON’ 417 | #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) | ^~~~~~~~~ In file included from /usr/include/bits/socket.h:27, from /usr/include/sys/socket.h:33, from ../lib/net/rte_ip.h:23, from ../lib/ethdev/rte_flow.h:24, from ../lib/ethdev/rte_eth_ctrl.h:11, from ../lib/ethdev/rte_ethdev.h:1419, from ../lib/ethdev/ethdev_driver.h:24: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘i40e_rxq_rearm’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:76:18: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 76 | (offsetof(struct rte_mbuf, buf_iova)); | ^~~~~~~~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘vtx1’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:997:36: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 997 | pkt->buf_iova + pkt->data_off); | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘vtx’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1028:40: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1028 | (hi_qw3, pkt[3]->buf_iova + pkt[3]->data_off, | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1029:39: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1029 | hi_qw2, pkt[2]->buf_iova + pkt[2]->data_off, | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1030:39: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1030 | hi_qw1, pkt[1]->buf_iova + pkt[1]->data_off, | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1031:39: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1031 | hi_qw0, pkt[0]->buf_iova + pkt[0]->data_off); | ^~ [920/2072] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_dcb.c.o [921/2072] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_lan_hmc.c.o [922/2072] Compiling C object drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o FAILED: drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o gcc -Idrivers/net/iavf/libiavf_avx512_lib.a.p -Idrivers/net/iavf -I../drivers/net/iavf -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/linux/include -I../lib/eal/linux/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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fdiagnostics-color=always -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O3 -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-address-of-packed-member -Wno-packed-not-aligned -Wno-missing-field-initializers -Wno-zero-length-bounds -D_GNU_SOURCE -fPIC -march=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -Wno-format-truncation -Wno-strict-aliasing -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -MF drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o.d -o drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -c ../drivers/net/iavf/iavf_rxtx_vec_avx512.c In file included from ../lib/eal/include/dev_driver.h:12, from ../lib/ethdev/ethdev_driver.h:22, from ../drivers/net/iavf/iavf_rxtx_vec_common.h:8, from ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:5: ../drivers/net/iavf/iavf_rxtx_vec_common.h: In function ‘iavf_rxq_rearm_common’: ../drivers/net/iavf/iavf_rxtx_vec_common.h:425:34: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 425 | RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != | ^~~~~~~~ ../lib/eal/include/rte_common.h:417:65: note: in definition of macro ‘RTE_BUILD_BUG_ON’ 417 | #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) | ^~~~~~~~~ In file included from /usr/include/bits/socket.h:27, from /usr/include/sys/socket.h:33, from ../lib/net/rte_ip.h:23, from ../lib/ethdev/rte_flow.h:24, from ../lib/ethdev/rte_eth_ctrl.h:11, from ../lib/ethdev/rte_ethdev.h:1419, from ../lib/ethdev/ethdev_driver.h:24: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘iavf_rxq_rearm’: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:81:57: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 81 | const __m512i iova_offsets = _mm512_set1_epi64(offsetof | ^~~~~~~~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘iavf_vtx1’: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1900:48: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1900 | pkt->buf_iova + pkt->data_off); | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘iavf_vtx’: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1950:40: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1950 | pkt[3]->buf_iova + pkt[3]->data_off, | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1952:40: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1952 | pkt[2]->buf_iova + pkt[2]->data_off, | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1954:40: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1954 | pkt[1]->buf_iova + pkt[1]->data_off, | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1956:40: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1956 | pkt[0]->buf_iova + pkt[0]->data_off); | ^~ [923/2072] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_nvm.c.o [924/2072] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_controlq.c.o [925/2072] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_common.c.o [926/2072] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_sched.c.o [927/2072] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_common.c.o [928/2072] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_switch.c.o ninja: build stopped *Build Failed #2: OS: FC36-64 Target: x86_64-native-linuxapp-clang FAILED: drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o clang -Idrivers/net/i40e/libi40e_avx512_lib.a.p -Idrivers/net/i40e -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/linux/include -I../lib/eal/linux/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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fcolor-diagnostics -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O3 -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-address-of-packed-member -Wno-missing-field-initializers -D_GNU_SOURCE -fPIC -march=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -DPF_DRIVER -DVF_DRIVER -DINTEGRATED_VF -DX722_A0_SUPPORT -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -MF drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o.d -o drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -c ../drivers/net/i40e/i40e_rxtx_vec_avx512.c In file included from ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:14: ../drivers/net/i40e/i40e_rxtx_common_avx.h:61:20: error: no member named 'buf_iova' in 'rte_mbuf' RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != ^ ~~~~~~~~ /usr/lib64/clang/14.0.0/include/stddef.h:104:24: note: expanded from macro 'offsetof' #define offsetof(t, d) __builtin_offsetof(t, d) ^ ~ ../lib/eal/include/rte_common.h:417:65: note: expanded from macro 'RTE_BUILD_BUG_ON' #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) ^~~~~~~~~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:76:4: error: no member named 'buf_iova' in 'rte_mbuf' (offsetof(struct rte_mbuf, buf_iova)); ^ ~~~~~~~~ /usr/lib64/clang/14.0.0/include/stddef.h:104:24: note: expanded from macro 'offsetof' #define offsetof(t, d) __builtin_offsetof(t, d) ^ ~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:997:10: error: no member named 'buf_iova' in 'struct rte_mbuf' pkt->buf_iova + pkt->data_off); ~~~ ^ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1028:21: error: no member named 'buf_iova' in 'struct rte_mbuf' (hi_qw3, pkt[3]->buf_iova + pkt[3]->data_off, ~~~~~~ ^ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1029:20: error: no member named 'buf_iova' in 'struct rte_mbuf' hi_qw2, pkt[2]->buf_iova + pkt[2]->data_off, ~~~~~~ ^ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1030:20: error: no member named 'buf_iova' in 'struct rte_mbuf' hi_qw1, pkt[1]->buf_iova + pkt[1]->data_off, ~~~~~~ ^ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1031:20: error: no member named 'buf_iova' in 'struct rte_mbuf' hi_qw0, pkt[0]->buf_iova + pkt[0]->data_off); ~~~~~~ ^ 7 errors generated. [924/2058] Compiling C object drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o FAILED: drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o clang -Idrivers/net/iavf/libiavf_avx512_lib.a.p -Idrivers/net/iavf -I../drivers/net/iavf -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/linux/include -I../lib/eal/linux/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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fcolor-diagnostics -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O3 -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-address-of-packed-member -Wno-missing-field-initializers -D_GNU_SOURCE -fPIC -march=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -Wno-strict-aliasing -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -MF drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o.d -o drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -c ../drivers/net/iavf/iavf_rxtx_vec_avx512.c In file included from ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:5: ../drivers/net/iavf/iavf_rxtx_vec_common.h:425:20: error: no member named 'buf_iova' in 'rte_mbuf' RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != ^ ~~~~~~~~ /usr/lib64/clang/14.0.0/include/stddef.h:104:24: note: expanded from macro 'offsetof' #define offsetof(t, d) __builtin_offsetof(t, d) ^ ~ ../lib/eal/include/rte_common.h:417:65: note: expanded from macro 'RTE_BUILD_BUG_ON' #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) ^~~~~~~~~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:81:50: error: no member named 'buf_iova' in 'rte_mbuf' const __m512i iova_offsets = _mm512_set1_epi64(offsetof ^ /usr/lib64/clang/14.0.0/include/stddef.h:104:24: note: expanded from macro 'offsetof' #define offsetof(t, d) __builtin_offsetof(t, d) ^ ~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1900:15: error: no member named 'buf_iova' in 'struct rte_mbuf' pkt->buf_iova + pkt->data_off); ~~~ ^ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1950:14: error: no member named 'buf_iova' in 'struct rte_mbuf' pkt[3]->buf_iova + pkt[3]->data_off, ~~~~~~ ^ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1952:14: error: no member named 'buf_iova' in 'struct rte_mbuf' pkt[2]->buf_iova + pkt[2]->data_off, ~~~~~~ ^ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1954:14: error: no member named 'buf_iova' in 'struct rte_mbuf' pkt[1]->buf_iova + pkt[1]->data_off, ~~~~~~ ^ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1956:14: error: no member named 'buf_iova' in 'struct rte_mbuf' pkt[0]->buf_iova + pkt[0]->data_off); ~~~~~~ ^ 7 errors generated. [925/2058] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_controlq.c.o [926/2058] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_nvm.c.o [927/2058] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_common.c.o [928/2058] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_nvm.c.o [929/2058] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_flex_pipe.c.o [930/2058] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_common.c.o [931/2058] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_sched.c.o [932/2058] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_switch.c.o ninja: build stopped *Build Failed #3: OS: FreeBSD13-64 Target: x86_64-native-bsdapp-gcc FAILED: drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o gcc -Idrivers/net/i40e/libi40e_avx512_lib.a.p -Idrivers/net/i40e -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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fdiagnostics-color=always -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O3 -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-address-of-packed-member -Wno-packed-not-aligned -Wno-missing-field-initializers -Wno-zero-length-bounds -D_GNU_SOURCE -D__BSD_VISIBLE -fPIC -march=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -Wno-format-truncation -DPF_DRIVER -DVF_DRIVER -DINTEGRATED_VF -DX722_A0_SUPPORT -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -MF drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o.d -o drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -c ../drivers/net/i40e/i40e_rxtx_vec_avx512.c In file included from ../lib/eal/include/dev_driver.h:12, from ../lib/ethdev/ethdev_driver.h:22, from ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:6: ../drivers/net/i40e/i40e_rxtx_common_avx.h: In function 'i40e_rxq_rearm_common': ../drivers/net/i40e/i40e_rxtx_common_avx.h:61:20: error: 'struct rte_mbuf' has no member named 'buf_iova' 61 | RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != | ^~~~~~~~ ../lib/eal/include/rte_common.h:417:65: note: in definition of macro 'RTE_BUILD_BUG_ON' 417 | #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) | ^~~~~~~~~ In file included from ../lib/eal/include/rte_uuid.h:18, from ../lib/eal/include/rte_eal.h:20, from ../lib/eal/include/rte_lcore.h:19, from ../lib/eal/include/generic/rte_spinlock.h:21, from ../lib/eal/x86/include/rte_spinlock.h:12, from ../lib/eal/include/generic/rte_power_intrinsics.h:11, from ../lib/eal/x86/include/rte_power_intrinsics.h:14, from ../lib/ethdev/rte_ethdev.h:173, from ../lib/ethdev/ethdev_driver.h:24, from ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:6: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function 'i40e_rxq_rearm': ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:76:4: error: 'struct rte_mbuf' has no member named 'buf_iova' 76 | (offsetof(struct rte_mbuf, buf_iova)); | ^~~~~~~~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function 'vtx1': ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:997:8: error: 'struct rte_mbuf' has no member named 'buf_iova' 997 | pkt->buf_iova + pkt->data_off); | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function 'vtx': ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1028:19: error: 'struct rte_mbuf' has no member named 'buf_iova' 1028 | (hi_qw3, pkt[3]->buf_iova + pkt[3]->data_off, | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1029:18: error: 'struct rte_mbuf' has no member named 'buf_iova' 1029 | hi_qw2, pkt[2]->buf_iova + pkt[2]->data_off, | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1030:18: error: 'struct rte_mbuf' has no member named 'buf_iova' 1030 | hi_qw1, pkt[1]->buf_iova + pkt[1]->data_off, | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1031:18: error: 'struct rte_mbuf' has no member named 'buf_iova' 1031 | hi_qw0, pkt[0]->buf_iova + pkt[0]->data_off); | ^~ [620/1201] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_lan_hmc.c.o [621/1201] Compiling C object drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o FAILED: drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o gcc -Idrivers/net/iavf/libiavf_avx512_lib.a.p -Idrivers/net/iavf -I../drivers/net/iavf -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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fdiagnostics-color=always -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O3 -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-address-of-packed-member -Wno-packed-not-aligned -Wno-missing-field-initializers -Wno-zero-length-bounds -D_GNU_SOURCE -D__BSD_VISIBLE -fPIC -march=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -Wno-format-truncation -Wno-strict-aliasing -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -MF drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o.d -o drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -c ../drivers/net/iavf/iavf_rxtx_vec_avx512.c In file included from ../lib/eal/include/dev_driver.h:12, from ../lib/ethdev/ethdev_driver.h:22, from ../drivers/net/iavf/iavf_rxtx_vec_common.h:8, from ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:5: ../drivers/net/iavf/iavf_rxtx_vec_common.h: In function 'iavf_rxq_rearm_common': ../drivers/net/iavf/iavf_rxtx_vec_common.h:425:20: error: 'struct rte_mbuf' has no member named 'buf_iova' 425 | RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != | ^~~~~~~~ ../lib/eal/include/rte_common.h:417:65: note: in definition of macro 'RTE_BUILD_BUG_ON' 417 | #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) | ^~~~~~~~~ In file included from ../lib/eal/include/rte_uuid.h:18, from ../lib/eal/include/rte_eal.h:20, from ../lib/eal/include/rte_lcore.h:19, from ../lib/eal/include/generic/rte_spinlock.h:21, from ../lib/eal/x86/include/rte_spinlock.h:12, from ../lib/eal/include/generic/rte_power_intrinsics.h:11, from ../lib/eal/x86/include/rte_power_intrinsics.h:14, from ../lib/ethdev/rte_ethdev.h:173, from ../lib/ethdev/ethdev_driver.h:24, from ../drivers/net/iavf/iavf_rxtx_vec_common.h:8, from ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:5: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function 'iavf_rxq_rearm': ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:81:50: error: 'struct rte_mbuf' has no member named 'buf_iova' 81 | const __m512i iova_offsets = _mm512_set1_epi64(offsetof | ^~~~~~~~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function 'iavf_vtx1': ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1900:13: error: 'struct rte_mbuf' has no member named 'buf_iova' 1900 | pkt->buf_iova + pkt->data_off); | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function 'iavf_vtx': ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1950:12: error: 'struct rte_mbuf' has no member named 'buf_iova' 1950 | pkt[3]->buf_iova + pkt[3]->data_off, | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1952:12: error: 'struct rte_mbuf' has no member named 'buf_iova' 1952 | pkt[2]->buf_iova + pkt[2]->data_off, | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1954:12: error: 'struct rte_mbuf' has no member named 'buf_iova' 1954 | pkt[1]->buf_iova + pkt[1]->data_off, | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1956:12: error: 'struct rte_mbuf' has no member named 'buf_iova' 1956 | pkt[0]->buf_iova + pkt[0]->data_off); | ^~ [622/1201] Generating rte_net_bond.sym_chk with a custom command (wrapped by meson to capture output) [623/1201] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_nvm.c.o [624/1201] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_controlq.c.o [625/1201] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_common.c.o [626/1201] Compiling C object lib/librte_pipeline.a.p/pipeline_rte_table_action.c.o [627/1201] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_common.c.o [628/1201] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_sched.c.o ninja: build stopped *Build Failed #4: OS: FreeBSD13-64 Target: x86_64-native-bsdapp-clang FAILED: drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o clang -Idrivers/net/iavf/libiavf_avx512_lib.a.p -Idrivers/net/iavf -I../drivers/net/iavf -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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fcolor-diagnostics -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O3 -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -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=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -Wno-strict-aliasing -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -MF drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o.d -o drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -c ../drivers/net/iavf/iavf_rxtx_vec_avx512.c In file included from ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:5: ../drivers/net/iavf/iavf_rxtx_vec_common.h:425:20: error: no member named 'buf_iova' in 'rte_mbuf' RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != ^ ~~~~~~~~ /usr/include/stddef.h:75:31: note: expanded from macro 'offsetof' #define offsetof(type, field) __offsetof(type, field) ^ ~~~~~ /usr/include/sys/cdefs.h:468:34: note: expanded from macro '__offsetof' #define __offsetof(type, field) __builtin_offsetof(type, field) ^ ~~~~~ ../lib/eal/include/rte_common.h:417:65: note: expanded from macro 'RTE_BUILD_BUG_ON' #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) ^~~~~~~~~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:81:50: error: no member named 'buf_iova' in 'rte_mbuf' const __m512i iova_offsets = _mm512_set1_epi64(offsetof ^ /usr/include/stddef.h:75:31: note: expanded from macro 'offsetof' #define offsetof(type, field) __offsetof(type, field) ^ ~~~~~ /usr/include/sys/cdefs.h:468:34: note: expanded from macro '__offsetof' #define __offsetof(type, field) __builtin_offsetof(type, field) ^ ~~~~~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1900:15: error: no member named 'buf_iova' in 'struct rte_mbuf' pkt->buf_iova + pkt->data_off); ~~~ ^ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1950:14: error: no member named 'buf_iova' in 'struct rte_mbuf' pkt[3]->buf_iova + pkt[3]->data_off, ~~~~~~ ^ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1952:14: error: no member named 'buf_iova' in 'struct rte_mbuf' pkt[2]->buf_iova + pkt[2]->data_off, ~~~~~~ ^ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1954:14: error: no member named 'buf_iova' in 'struct rte_mbuf' pkt[1]->buf_iova + pkt[1]->data_off, ~~~~~~ ^ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1956:14: error: no member named 'buf_iova' in 'struct rte_mbuf' pkt[0]->buf_iova + pkt[0]->data_off); ~~~~~~ ^ 7 errors generated. [852/1187] Compiling C object drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o FAILED: drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o clang -Idrivers/net/i40e/libi40e_avx512_lib.a.p -Idrivers/net/i40e -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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fcolor-diagnostics -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O3 -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -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=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -DPF_DRIVER -DVF_DRIVER -DINTEGRATED_VF -DX722_A0_SUPPORT -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -MF drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o.d -o drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -c ../drivers/net/i40e/i40e_rxtx_vec_avx512.c In file included from ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:14: ../drivers/net/i40e/i40e_rxtx_common_avx.h:61:20: error: no member named 'buf_iova' in 'rte_mbuf' RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != ^ ~~~~~~~~ /usr/include/stddef.h:75:31: note: expanded from macro 'offsetof' #define offsetof(type, field) __offsetof(type, field) ^ ~~~~~ /usr/include/sys/cdefs.h:468:34: note: expanded from macro '__offsetof' #define __offsetof(type, field) __builtin_offsetof(type, field) ^ ~~~~~ ../lib/eal/include/rte_common.h:417:65: note: expanded from macro 'RTE_BUILD_BUG_ON' #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) ^~~~~~~~~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:76:4: error: no member named 'buf_iova' in 'rte_mbuf' (offsetof(struct rte_mbuf, buf_iova)); ^ ~~~~~~~~ /usr/include/stddef.h:75:31: note: expanded from macro 'offsetof' #define offsetof(type, field) __offsetof(type, field) ^ ~~~~~ /usr/include/sys/cdefs.h:468:34: note: expanded from macro '__offsetof' #define __offsetof(type, field) __builtin_offsetof(type, field) ^ ~~~~~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:997:10: error: no member named 'buf_iova' in 'struct rte_mbuf' pkt->buf_iova + pkt->data_off); ~~~ ^ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1028:21: error: no member named 'buf_iova' in 'struct rte_mbuf' (hi_qw3, pkt[3]->buf_iova + pkt[3]->data_off, ~~~~~~ ^ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1029:20: error: no member named 'buf_iova' in 'struct rte_mbuf' hi_qw2, pkt[2]->buf_iova + pkt[2]->data_off, ~~~~~~ ^ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1030:20: error: no member named 'buf_iova' in 'struct rte_mbuf' hi_qw1, pkt[1]->buf_iova + pkt[1]->data_off, ~~~~~~ ^ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1031:20: error: no member named 'buf_iova' in 'struct rte_mbuf' hi_qw0, pkt[0]->buf_iova + pkt[0]->data_off); ~~~~~~ ^ 7 errors generated. [853/1187] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_nvm.c.o [854/1187] Generating rte_net_bond.sym_chk with a custom command (wrapped by meson to capture output) [855/1187] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_common.c.o [856/1187] Generating pipeline.sym_chk with a custom command (wrapped by meson to capture output) [857/1187] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_controlq.c.o [858/1187] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_common.c.o [859/1187] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_sched.c.o [860/1187] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_switch.c.o ninja: build stopped *Build Failed #5: OS: FreeBSD13-64 Target: x86_64-native-bsdapp-gcc+shared FAILED: drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o gcc -Idrivers/net/i40e/libi40e_avx512_lib.a.p -Idrivers/net/i40e -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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fdiagnostics-color=always -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O3 -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-address-of-packed-member -Wno-packed-not-aligned -Wno-missing-field-initializers -Wno-zero-length-bounds -D_GNU_SOURCE -D__BSD_VISIBLE -fPIC -march=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -Wno-format-truncation -DPF_DRIVER -DVF_DRIVER -DINTEGRATED_VF -DX722_A0_SUPPORT -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -MF drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o.d -o drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -c ../drivers/net/i40e/i40e_rxtx_vec_avx512.c In file included from ../lib/eal/include/dev_driver.h:12, from ../lib/ethdev/ethdev_driver.h:22, from ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:6: ../drivers/net/i40e/i40e_rxtx_common_avx.h: In function 'i40e_rxq_rearm_common': ../drivers/net/i40e/i40e_rxtx_common_avx.h:61:20: error: 'struct rte_mbuf' has no member named 'buf_iova' 61 | RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != | ^~~~~~~~ ../lib/eal/include/rte_common.h:417:65: note: in definition of macro 'RTE_BUILD_BUG_ON' 417 | #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) | ^~~~~~~~~ In file included from ../lib/eal/include/rte_uuid.h:18, from ../lib/eal/include/rte_eal.h:20, from ../lib/eal/include/rte_lcore.h:19, from ../lib/eal/include/generic/rte_spinlock.h:21, from ../lib/eal/x86/include/rte_spinlock.h:12, from ../lib/eal/include/generic/rte_power_intrinsics.h:11, from ../lib/eal/x86/include/rte_power_intrinsics.h:14, from ../lib/ethdev/rte_ethdev.h:173, from ../lib/ethdev/ethdev_driver.h:24, from ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:6: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function 'i40e_rxq_rearm': ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:76:4: error: 'struct rte_mbuf' has no member named 'buf_iova' 76 | (offsetof(struct rte_mbuf, buf_iova)); | ^~~~~~~~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function 'vtx1': ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:997:8: error: 'struct rte_mbuf' has no member named 'buf_iova' 997 | pkt->buf_iova + pkt->data_off); | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function 'vtx': ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1028:19: error: 'struct rte_mbuf' has no member named 'buf_iova' 1028 | (hi_qw3, pkt[3]->buf_iova + pkt[3]->data_off, | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1029:18: error: 'struct rte_mbuf' has no member named 'buf_iova' 1029 | hi_qw2, pkt[2]->buf_iova + pkt[2]->data_off, | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1030:18: error: 'struct rte_mbuf' has no member named 'buf_iova' 1030 | hi_qw1, pkt[1]->buf_iova + pkt[1]->data_off, | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1031:18: error: 'struct rte_mbuf' has no member named 'buf_iova' 1031 | hi_qw0, pkt[0]->buf_iova + pkt[0]->data_off); | ^~ [884/1099] Compiling C object drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o FAILED: drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o gcc -Idrivers/net/iavf/libiavf_avx512_lib.a.p -Idrivers/net/iavf -I../drivers/net/iavf -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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fdiagnostics-color=always -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O3 -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-address-of-packed-member -Wno-packed-not-aligned -Wno-missing-field-initializers -Wno-zero-length-bounds -D_GNU_SOURCE -D__BSD_VISIBLE -fPIC -march=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -Wno-format-truncation -Wno-strict-aliasing -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -MF drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o.d -o drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -c ../drivers/net/iavf/iavf_rxtx_vec_avx512.c In file included from ../lib/eal/include/dev_driver.h:12, from ../lib/ethdev/ethdev_driver.h:22, from ../drivers/net/iavf/iavf_rxtx_vec_common.h:8, from ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:5: ../drivers/net/iavf/iavf_rxtx_vec_common.h: In function 'iavf_rxq_rearm_common': ../drivers/net/iavf/iavf_rxtx_vec_common.h:425:20: error: 'struct rte_mbuf' has no member named 'buf_iova' 425 | RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != | ^~~~~~~~ ../lib/eal/include/rte_common.h:417:65: note: in definition of macro 'RTE_BUILD_BUG_ON' 417 | #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) | ^~~~~~~~~ In file included from ../lib/eal/include/rte_uuid.h:18, from ../lib/eal/include/rte_eal.h:20, from ../lib/eal/include/rte_lcore.h:19, from ../lib/eal/include/generic/rte_spinlock.h:21, from ../lib/eal/x86/include/rte_spinlock.h:12, from ../lib/eal/include/generic/rte_power_intrinsics.h:11, from ../lib/eal/x86/include/rte_power_intrinsics.h:14, from ../lib/ethdev/rte_ethdev.h:173, from ../lib/ethdev/ethdev_driver.h:24, from ../drivers/net/iavf/iavf_rxtx_vec_common.h:8, from ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:5: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function 'iavf_rxq_rearm': ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:81:50: error: 'struct rte_mbuf' has no member named 'buf_iova' 81 | const __m512i iova_offsets = _mm512_set1_epi64(offsetof | ^~~~~~~~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function 'iavf_vtx1': ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1900:13: error: 'struct rte_mbuf' has no member named 'buf_iova' 1900 | pkt->buf_iova + pkt->data_off); | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function 'iavf_vtx': ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1950:12: error: 'struct rte_mbuf' has no member named 'buf_iova' 1950 | pkt[3]->buf_iova + pkt[3]->data_off, | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1952:12: error: 'struct rte_mbuf' has no member named 'buf_iova' 1952 | pkt[2]->buf_iova + pkt[2]->data_off, | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1954:12: error: 'struct rte_mbuf' has no member named 'buf_iova' 1954 | pkt[1]->buf_iova + pkt[1]->data_off, | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1956:12: error: 'struct rte_mbuf' has no member named 'buf_iova' 1956 | pkt[0]->buf_iova + pkt[0]->data_off); | ^~ [885/1099] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_lan_hmc.c.o [886/1099] Generating drivers/rte_net_bond.sym_chk with a custom command (wrapped by meson to capture output) [887/1099] Generating lib/pipeline.sym_chk with a custom command (wrapped by meson to capture output) [888/1099] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_controlq.c.o [889/1099] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_nvm.c.o [890/1099] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_common.c.o [891/1099] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_common.c.o [892/1099] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_sched.c.o ninja: build stopped *Build Failed #6: OS: FreeBSD13-64 Target: x86_64-native-bsdapp-gcc+debug FAILED: drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o gcc -Idrivers/net/i40e/libi40e_avx512_lib.a.p -Idrivers/net/i40e -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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fdiagnostics-color=always -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O2 -g -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-address-of-packed-member -Wno-packed-not-aligned -Wno-missing-field-initializers -Wno-zero-length-bounds -D_GNU_SOURCE -D__BSD_VISIBLE -fPIC -march=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -Wno-format-truncation -DPF_DRIVER -DVF_DRIVER -DINTEGRATED_VF -DX722_A0_SUPPORT -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -MF drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o.d -o drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -c ../drivers/net/i40e/i40e_rxtx_vec_avx512.c In file included from ../lib/eal/include/dev_driver.h:12, from ../lib/ethdev/ethdev_driver.h:22, from ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:6: ../drivers/net/i40e/i40e_rxtx_common_avx.h: In function 'i40e_rxq_rearm_common': ../drivers/net/i40e/i40e_rxtx_common_avx.h:61:20: error: 'struct rte_mbuf' has no member named 'buf_iova' 61 | RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != | ^~~~~~~~ ../lib/eal/include/rte_common.h:417:65: note: in definition of macro 'RTE_BUILD_BUG_ON' 417 | #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) | ^~~~~~~~~ In file included from ../lib/eal/include/rte_uuid.h:18, from ../lib/eal/include/rte_eal.h:20, from ../lib/eal/include/rte_lcore.h:19, from ../lib/eal/include/generic/rte_spinlock.h:21, from ../lib/eal/x86/include/rte_spinlock.h:12, from ../lib/eal/include/generic/rte_power_intrinsics.h:11, from ../lib/eal/x86/include/rte_power_intrinsics.h:14, from ../lib/ethdev/rte_ethdev.h:173, from ../lib/ethdev/ethdev_driver.h:24, from ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:6: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function 'i40e_rxq_rearm': ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:76:4: error: 'struct rte_mbuf' has no member named 'buf_iova' 76 | (offsetof(struct rte_mbuf, buf_iova)); | ^~~~~~~~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function 'vtx1': ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:997:8: error: 'struct rte_mbuf' has no member named 'buf_iova' 997 | pkt->buf_iova + pkt->data_off); | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function 'vtx': ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1028:19: error: 'struct rte_mbuf' has no member named 'buf_iova' 1028 | (hi_qw3, pkt[3]->buf_iova + pkt[3]->data_off, | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1029:18: error: 'struct rte_mbuf' has no member named 'buf_iova' 1029 | hi_qw2, pkt[2]->buf_iova + pkt[2]->data_off, | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1030:18: error: 'struct rte_mbuf' has no member named 'buf_iova' 1030 | hi_qw1, pkt[1]->buf_iova + pkt[1]->data_off, | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1031:18: error: 'struct rte_mbuf' has no member named 'buf_iova' 1031 | hi_qw0, pkt[0]->buf_iova + pkt[0]->data_off); | ^~ [874/1201] Compiling C object drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o FAILED: drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o gcc -Idrivers/net/iavf/libiavf_avx512_lib.a.p -Idrivers/net/iavf -I../drivers/net/iavf -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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fdiagnostics-color=always -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O2 -g -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-address-of-packed-member -Wno-packed-not-aligned -Wno-missing-field-initializers -Wno-zero-length-bounds -D_GNU_SOURCE -D__BSD_VISIBLE -fPIC -march=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -Wno-format-truncation -Wno-strict-aliasing -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -MF drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o.d -o drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -c ../drivers/net/iavf/iavf_rxtx_vec_avx512.c In file included from ../lib/eal/include/dev_driver.h:12, from ../lib/ethdev/ethdev_driver.h:22, from ../drivers/net/iavf/iavf_rxtx_vec_common.h:8, from ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:5: ../drivers/net/iavf/iavf_rxtx_vec_common.h: In function 'iavf_rxq_rearm_common': ../drivers/net/iavf/iavf_rxtx_vec_common.h:425:20: error: 'struct rte_mbuf' has no member named 'buf_iova' 425 | RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != | ^~~~~~~~ ../lib/eal/include/rte_common.h:417:65: note: in definition of macro 'RTE_BUILD_BUG_ON' 417 | #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) | ^~~~~~~~~ In file included from ../lib/eal/include/rte_uuid.h:18, from ../lib/eal/include/rte_eal.h:20, from ../lib/eal/include/rte_lcore.h:19, from ../lib/eal/include/generic/rte_spinlock.h:21, from ../lib/eal/x86/include/rte_spinlock.h:12, from ../lib/eal/include/generic/rte_power_intrinsics.h:11, from ../lib/eal/x86/include/rte_power_intrinsics.h:14, from ../lib/ethdev/rte_ethdev.h:173, from ../lib/ethdev/ethdev_driver.h:24, from ../drivers/net/iavf/iavf_rxtx_vec_common.h:8, from ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:5: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function 'iavf_rxq_rearm': ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:81:50: error: 'struct rte_mbuf' has no member named 'buf_iova' 81 | const __m512i iova_offsets = _mm512_set1_epi64(offsetof | ^~~~~~~~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function 'iavf_vtx1': ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1900:13: error: 'struct rte_mbuf' has no member named 'buf_iova' 1900 | pkt->buf_iova + pkt->data_off); | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function 'iavf_vtx': ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1950:12: error: 'struct rte_mbuf' has no member named 'buf_iova' 1950 | pkt[3]->buf_iova + pkt[3]->data_off, | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1952:12: error: 'struct rte_mbuf' has no member named 'buf_iova' 1952 | pkt[2]->buf_iova + pkt[2]->data_off, | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1954:12: error: 'struct rte_mbuf' has no member named 'buf_iova' 1954 | pkt[1]->buf_iova + pkt[1]->data_off, | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1956:12: error: 'struct rte_mbuf' has no member named 'buf_iova' 1956 | pkt[0]->buf_iova + pkt[0]->data_off); | ^~ [875/1201] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_acl.c.o [876/1201] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_dcb.c.o [877/1201] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_common.c.o [878/1201] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_sched.c.o [879/1201] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_flex_pipe.c.o [880/1201] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_fdir.c.o [881/1201] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_switch.c.o [882/1201] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_flow.c.o ninja: build stopped *Build Failed #7: OS: RHEL86-64 Target: x86_64-native-linuxapp-gcc FAILED: drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o gcc -Idrivers/net/i40e/libi40e_avx512_lib.a.p -Idrivers/net/i40e -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/linux/include -I../lib/eal/linux/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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fdiagnostics-color=always -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O3 -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-packed-not-aligned -Wno-missing-field-initializers -D_GNU_SOURCE -fPIC -march=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -Wno-format-truncation -DPF_DRIVER -DVF_DRIVER -DINTEGRATED_VF -DX722_A0_SUPPORT -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -MF drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o.d -o drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -c ../drivers/net/i40e/i40e_rxtx_vec_avx512.c In file included from ../lib/eal/include/dev_driver.h:12, from ../lib/ethdev/ethdev_driver.h:22, from ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:6: ../drivers/net/i40e/i40e_rxtx_common_avx.h: In function ‘i40e_rxq_rearm_common’: ../drivers/net/i40e/i40e_rxtx_common_avx.h:61:46: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != ^~~~~~~~ ../lib/eal/include/rte_common.h:417:65: note: in definition of macro ‘RTE_BUILD_BUG_ON’ #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) ^~~~~~~~~ In file included from /usr/include/bits/socket.h:27, from /usr/include/sys/socket.h:33, from ../lib/net/rte_ip.h:23, from ../lib/ethdev/rte_flow.h:24, from ../lib/ethdev/rte_eth_ctrl.h:11, from ../lib/ethdev/rte_ethdev.h:1419, from ../lib/ethdev/ethdev_driver.h:24, from ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:6: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘i40e_rxq_rearm’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:76:30: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? (offsetof(struct rte_mbuf, buf_iova)); ^~~~~~~~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘vtx1’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:997:10: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? pkt->buf_iova + pkt->data_off); ^~~~~~~~ buf_addr ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘vtx’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1028:21: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? (hi_qw3, pkt[3]->buf_iova + pkt[3]->data_off, ^~~~~~~~ buf_addr ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1029:20: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? hi_qw2, pkt[2]->buf_iova + pkt[2]->data_off, ^~~~~~~~ buf_addr ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1030:20: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? hi_qw1, pkt[1]->buf_iova + pkt[1]->data_off, ^~~~~~~~ buf_addr ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1031:20: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? hi_qw0, pkt[0]->buf_iova + pkt[0]->data_off); ^~~~~~~~ buf_addr [924/2036] Compiling C object drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o FAILED: drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o gcc -Idrivers/net/iavf/libiavf_avx512_lib.a.p -Idrivers/net/iavf -I../drivers/net/iavf -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/linux/include -I../lib/eal/linux/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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fdiagnostics-color=always -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O3 -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-packed-not-aligned -Wno-missing-field-initializers -D_GNU_SOURCE -fPIC -march=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -Wno-format-truncation -Wno-strict-aliasing -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -MF drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o.d -o drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -c ../drivers/net/iavf/iavf_rxtx_vec_avx512.c In file included from ../lib/eal/include/dev_driver.h:12, from ../lib/ethdev/ethdev_driver.h:22, from ../drivers/net/iavf/iavf_rxtx_vec_common.h:8, from ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:5: ../drivers/net/iavf/iavf_rxtx_vec_common.h: In function ‘iavf_rxq_rearm_common’: ../drivers/net/iavf/iavf_rxtx_vec_common.h:425:46: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != ^~~~~~~~ ../lib/eal/include/rte_common.h:417:65: note: in definition of macro ‘RTE_BUILD_BUG_ON’ #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) ^~~~~~~~~ In file included from /usr/include/bits/socket.h:27, from /usr/include/sys/socket.h:33, from ../lib/net/rte_ip.h:23, from ../lib/ethdev/rte_flow.h:24, from ../lib/ethdev/rte_eth_ctrl.h:11, from ../lib/ethdev/rte_ethdev.h:1419, from ../lib/ethdev/ethdev_driver.h:24, from ../drivers/net/iavf/iavf_rxtx_vec_common.h:8, from ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:5: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘iavf_rxq_rearm’: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:82:26: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? (struct rte_mbuf, buf_iova)); ^~~~~~~~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘iavf_vtx1’: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1900:15: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? pkt->buf_iova + pkt->data_off); ^~~~~~~~ buf_addr ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘iavf_vtx’: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1950:14: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? pkt[3]->buf_iova + pkt[3]->data_off, ^~~~~~~~ buf_addr ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1952:14: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? pkt[2]->buf_iova + pkt[2]->data_off, ^~~~~~~~ buf_addr ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1954:14: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? pkt[1]->buf_iova + pkt[1]->data_off, ^~~~~~~~ buf_addr ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1956:14: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? pkt[0]->buf_iova + pkt[0]->data_off); ^~~~~~~~ buf_addr [925/2036] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_nvm.c.o [926/2036] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_controlq.c.o [927/2036] Generating symbol file drivers/librte_net_cnxk.so.23.1.p/librte_net_cnxk.so.23.1.symbols [928/2036] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_nvm.c.o [929/2036] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_common.c.o [930/2036] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_common.c.o [931/2036] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_sched.c.o [932/2036] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_switch.c.o ninja: build stopped *Build Failed #8: OS: RHEL86-64 Target: x86_64-native-linuxapp-clang FAILED: drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o clang -Idrivers/net/i40e/libi40e_avx512_lib.a.p -Idrivers/net/i40e -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/linux/include -I../lib/eal/linux/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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fcolor-diagnostics -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O3 -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-address-of-packed-member -Wno-missing-field-initializers -D_GNU_SOURCE -fPIC -march=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -DPF_DRIVER -DVF_DRIVER -DINTEGRATED_VF -DX722_A0_SUPPORT -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -MF drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o.d -o drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -c ../drivers/net/i40e/i40e_rxtx_vec_avx512.c In file included from ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:14: ../drivers/net/i40e/i40e_rxtx_common_avx.h:61:20: error: no member named 'buf_iova' in 'rte_mbuf' RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != ^ ~~~~~~~~ /usr/lib64/clang/14.0.0/include/stddef.h:104:24: note: expanded from macro 'offsetof' #define offsetof(t, d) __builtin_offsetof(t, d) ^ ~ ../lib/eal/include/rte_common.h:417:65: note: expanded from macro 'RTE_BUILD_BUG_ON' #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) ^~~~~~~~~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:76:4: error: no member named 'buf_iova' in 'rte_mbuf' (offsetof(struct rte_mbuf, buf_iova)); ^ ~~~~~~~~ /usr/lib64/clang/14.0.0/include/stddef.h:104:24: note: expanded from macro 'offsetof' #define offsetof(t, d) __builtin_offsetof(t, d) ^ ~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:997:10: error: no member named 'buf_iova' in 'struct rte_mbuf' pkt->buf_iova + pkt->data_off); ~~~ ^ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1028:21: error: no member named 'buf_iova' in 'struct rte_mbuf' (hi_qw3, pkt[3]->buf_iova + pkt[3]->data_off, ~~~~~~ ^ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1029:20: error: no member named 'buf_iova' in 'struct rte_mbuf' hi_qw2, pkt[2]->buf_iova + pkt[2]->data_off, ~~~~~~ ^ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1030:20: error: no member named 'buf_iova' in 'struct rte_mbuf' hi_qw1, pkt[1]->buf_iova + pkt[1]->data_off, ~~~~~~ ^ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1031:20: error: no member named 'buf_iova' in 'struct rte_mbuf' hi_qw0, pkt[0]->buf_iova + pkt[0]->data_off); ~~~~~~ ^ 7 errors generated. [923/2036] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_lan_hmc.c.o [924/2036] Compiling C object drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o FAILED: drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o clang -Idrivers/net/iavf/libiavf_avx512_lib.a.p -Idrivers/net/iavf -I../drivers/net/iavf -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/linux/include -I../lib/eal/linux/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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fcolor-diagnostics -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O3 -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-address-of-packed-member -Wno-missing-field-initializers -D_GNU_SOURCE -fPIC -march=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -Wno-strict-aliasing -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -MF drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o.d -o drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -c ../drivers/net/iavf/iavf_rxtx_vec_avx512.c In file included from ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:5: ../drivers/net/iavf/iavf_rxtx_vec_common.h:425:20: error: no member named 'buf_iova' in 'rte_mbuf' RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != ^ ~~~~~~~~ /usr/lib64/clang/14.0.0/include/stddef.h:104:24: note: expanded from macro 'offsetof' #define offsetof(t, d) __builtin_offsetof(t, d) ^ ~ ../lib/eal/include/rte_common.h:417:65: note: expanded from macro 'RTE_BUILD_BUG_ON' #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) ^~~~~~~~~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:81:50: error: no member named 'buf_iova' in 'rte_mbuf' const __m512i iova_offsets = _mm512_set1_epi64(offsetof ^ /usr/lib64/clang/14.0.0/include/stddef.h:104:24: note: expanded from macro 'offsetof' #define offsetof(t, d) __builtin_offsetof(t, d) ^ ~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1900:15: error: no member named 'buf_iova' in 'struct rte_mbuf' pkt->buf_iova + pkt->data_off); ~~~ ^ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1950:14: error: no member named 'buf_iova' in 'struct rte_mbuf' pkt[3]->buf_iova + pkt[3]->data_off, ~~~~~~ ^ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1952:14: error: no member named 'buf_iova' in 'struct rte_mbuf' pkt[2]->buf_iova + pkt[2]->data_off, ~~~~~~ ^ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1954:14: error: no member named 'buf_iova' in 'struct rte_mbuf' pkt[1]->buf_iova + pkt[1]->data_off, ~~~~~~ ^ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1956:14: error: no member named 'buf_iova' in 'struct rte_mbuf' pkt[0]->buf_iova + pkt[0]->data_off); ~~~~~~ ^ 7 errors generated. [925/2036] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_nvm.c.o [926/2036] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_controlq.c.o [927/2036] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_common.c.o [928/2036] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_nvm.c.o [929/2036] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_common.c.o [930/2036] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_sched.c.o [931/2036] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_switch.c.o ninja: build stopped *Build Failed #9: OS: RHEL86-64 Target: x86_64-native-linuxapp-gcc+shared FAILED: drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o gcc -Idrivers/net/i40e/libi40e_avx512_lib.a.p -Idrivers/net/i40e -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/linux/include -I../lib/eal/linux/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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fdiagnostics-color=always -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O3 -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-packed-not-aligned -Wno-missing-field-initializers -D_GNU_SOURCE -fPIC -march=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -Wno-format-truncation -DPF_DRIVER -DVF_DRIVER -DINTEGRATED_VF -DX722_A0_SUPPORT -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -MF drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o.d -o drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -c ../drivers/net/i40e/i40e_rxtx_vec_avx512.c In file included from ../lib/eal/include/dev_driver.h:12, from ../lib/ethdev/ethdev_driver.h:22, from ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:6: ../drivers/net/i40e/i40e_rxtx_common_avx.h: In function ‘i40e_rxq_rearm_common’: ../drivers/net/i40e/i40e_rxtx_common_avx.h:61:46: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != ^~~~~~~~ ../lib/eal/include/rte_common.h:417:65: note: in definition of macro ‘RTE_BUILD_BUG_ON’ #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) ^~~~~~~~~ In file included from /usr/include/bits/socket.h:27, from /usr/include/sys/socket.h:33, from ../lib/net/rte_ip.h:23, from ../lib/ethdev/rte_flow.h:24, from ../lib/ethdev/rte_eth_ctrl.h:11, from ../lib/ethdev/rte_ethdev.h:1419, from ../lib/ethdev/ethdev_driver.h:24, from ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:6: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘i40e_rxq_rearm’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:76:30: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? (offsetof(struct rte_mbuf, buf_iova)); ^~~~~~~~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘vtx1’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:997:10: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? pkt->buf_iova + pkt->data_off); ^~~~~~~~ buf_addr ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘vtx’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1028:21: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? (hi_qw3, pkt[3]->buf_iova + pkt[3]->data_off, ^~~~~~~~ buf_addr ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1029:20: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? hi_qw2, pkt[2]->buf_iova + pkt[2]->data_off, ^~~~~~~~ buf_addr ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1030:20: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? hi_qw1, pkt[1]->buf_iova + pkt[1]->data_off, ^~~~~~~~ buf_addr ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1031:20: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? hi_qw0, pkt[0]->buf_iova + pkt[0]->data_off); ^~~~~~~~ buf_addr [951/1894] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_nvm.c.o [952/1894] Compiling C object drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o FAILED: drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o gcc -Idrivers/net/iavf/libiavf_avx512_lib.a.p -Idrivers/net/iavf -I../drivers/net/iavf -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/linux/include -I../lib/eal/linux/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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fdiagnostics-color=always -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O3 -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-packed-not-aligned -Wno-missing-field-initializers -D_GNU_SOURCE -fPIC -march=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -Wno-format-truncation -Wno-strict-aliasing -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -MF drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o.d -o drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -c ../drivers/net/iavf/iavf_rxtx_vec_avx512.c In file included from ../lib/eal/include/dev_driver.h:12, from ../lib/ethdev/ethdev_driver.h:22, from ../drivers/net/iavf/iavf_rxtx_vec_common.h:8, from ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:5: ../drivers/net/iavf/iavf_rxtx_vec_common.h: In function ‘iavf_rxq_rearm_common’: ../drivers/net/iavf/iavf_rxtx_vec_common.h:425:46: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != ^~~~~~~~ ../lib/eal/include/rte_common.h:417:65: note: in definition of macro ‘RTE_BUILD_BUG_ON’ #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) ^~~~~~~~~ In file included from /usr/include/bits/socket.h:27, from /usr/include/sys/socket.h:33, from ../lib/net/rte_ip.h:23, from ../lib/ethdev/rte_flow.h:24, from ../lib/ethdev/rte_eth_ctrl.h:11, from ../lib/ethdev/rte_ethdev.h:1419, from ../lib/ethdev/ethdev_driver.h:24, from ../drivers/net/iavf/iavf_rxtx_vec_common.h:8, from ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:5: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘iavf_rxq_rearm’: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:82:26: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? (struct rte_mbuf, buf_iova)); ^~~~~~~~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘iavf_vtx1’: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1900:15: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? pkt->buf_iova + pkt->data_off); ^~~~~~~~ buf_addr ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘iavf_vtx’: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1950:14: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? pkt[3]->buf_iova + pkt[3]->data_off, ^~~~~~~~ buf_addr ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1952:14: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? pkt[2]->buf_iova + pkt[2]->data_off, ^~~~~~~~ buf_addr ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1954:14: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? pkt[1]->buf_iova + pkt[1]->data_off, ^~~~~~~~ buf_addr ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1956:14: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? pkt[0]->buf_iova + pkt[0]->data_off); ^~~~~~~~ buf_addr [953/1894] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_nvm.c.o [954/1894] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_controlq.c.o [955/1894] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_common.c.o [956/1894] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_flex_pipe.c.o [957/1894] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_common.c.o [958/1894] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_sched.c.o [959/1894] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_switch.c.o ninja: build stopped *Build Failed #10: OS: RHEL86-64 Target: x86_64-native-linuxapp-gcc+debug FAILED: drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o gcc -Idrivers/net/i40e/libi40e_avx512_lib.a.p -Idrivers/net/i40e -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/linux/include -I../lib/eal/linux/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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fdiagnostics-color=always -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O2 -g -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-packed-not-aligned -Wno-missing-field-initializers -D_GNU_SOURCE -fPIC -march=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -Wno-format-truncation -DPF_DRIVER -DVF_DRIVER -DINTEGRATED_VF -DX722_A0_SUPPORT -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -MF drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o.d -o drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -c ../drivers/net/i40e/i40e_rxtx_vec_avx512.c In file included from ../lib/eal/include/dev_driver.h:12, from ../lib/ethdev/ethdev_driver.h:22, from ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:6: ../drivers/net/i40e/i40e_rxtx_common_avx.h: In function ‘i40e_rxq_rearm_common’: ../drivers/net/i40e/i40e_rxtx_common_avx.h:61:46: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != ^~~~~~~~ ../lib/eal/include/rte_common.h:417:65: note: in definition of macro ‘RTE_BUILD_BUG_ON’ #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) ^~~~~~~~~ In file included from /usr/include/bits/socket.h:27, from /usr/include/sys/socket.h:33, from ../lib/net/rte_ip.h:23, from ../lib/ethdev/rte_flow.h:24, from ../lib/ethdev/rte_eth_ctrl.h:11, from ../lib/ethdev/rte_ethdev.h:1419, from ../lib/ethdev/ethdev_driver.h:24, from ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:6: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘i40e_rxq_rearm’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:76:30: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? (offsetof(struct rte_mbuf, buf_iova)); ^~~~~~~~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘vtx1’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:997:10: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? pkt->buf_iova + pkt->data_off); ^~~~~~~~ buf_addr ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘vtx’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1028:21: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? (hi_qw3, pkt[3]->buf_iova + pkt[3]->data_off, ^~~~~~~~ buf_addr ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1029:20: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? hi_qw2, pkt[2]->buf_iova + pkt[2]->data_off, ^~~~~~~~ buf_addr ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1030:20: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? hi_qw1, pkt[1]->buf_iova + pkt[1]->data_off, ^~~~~~~~ buf_addr ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1031:20: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? hi_qw0, pkt[0]->buf_iova + pkt[0]->data_off); ^~~~~~~~ buf_addr [913/2036] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_lan_hmc.c.o [914/2036] Compiling C object drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o FAILED: drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o gcc -Idrivers/net/iavf/libiavf_avx512_lib.a.p -Idrivers/net/iavf -I../drivers/net/iavf -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/linux/include -I../lib/eal/linux/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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fdiagnostics-color=always -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O2 -g -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-packed-not-aligned -Wno-missing-field-initializers -D_GNU_SOURCE -fPIC -march=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -Wno-format-truncation -Wno-strict-aliasing -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -MF drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o.d -o drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -c ../drivers/net/iavf/iavf_rxtx_vec_avx512.c In file included from ../lib/eal/include/dev_driver.h:12, from ../lib/ethdev/ethdev_driver.h:22, from ../drivers/net/iavf/iavf_rxtx_vec_common.h:8, from ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:5: ../drivers/net/iavf/iavf_rxtx_vec_common.h: In function ‘iavf_rxq_rearm_common’: ../drivers/net/iavf/iavf_rxtx_vec_common.h:425:46: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != ^~~~~~~~ ../lib/eal/include/rte_common.h:417:65: note: in definition of macro ‘RTE_BUILD_BUG_ON’ #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) ^~~~~~~~~ In file included from /usr/include/bits/socket.h:27, from /usr/include/sys/socket.h:33, from ../lib/net/rte_ip.h:23, from ../lib/ethdev/rte_flow.h:24, from ../lib/ethdev/rte_eth_ctrl.h:11, from ../lib/ethdev/rte_ethdev.h:1419, from ../lib/ethdev/ethdev_driver.h:24, from ../drivers/net/iavf/iavf_rxtx_vec_common.h:8, from ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:5: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘iavf_rxq_rearm’: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:82:26: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? (struct rte_mbuf, buf_iova)); ^~~~~~~~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘iavf_vtx1’: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1900:15: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? pkt->buf_iova + pkt->data_off); ^~~~~~~~ buf_addr ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘iavf_vtx’: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1950:14: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? pkt[3]->buf_iova + pkt[3]->data_off, ^~~~~~~~ buf_addr ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1952:14: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? pkt[2]->buf_iova + pkt[2]->data_off, ^~~~~~~~ buf_addr ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1954:14: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? pkt[1]->buf_iova + pkt[1]->data_off, ^~~~~~~~ buf_addr ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1956:14: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? pkt[0]->buf_iova + pkt[0]->data_off); ^~~~~~~~ buf_addr [915/2036] Generating rte_net_cnxk.pmd.c with a custom command [916/2036] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_nvm.c.o [917/2036] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_controlq.c.o [918/2036] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_common.c.o [919/2036] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_common.c.o [920/2036] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_sched.c.o [921/2036] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_switch.c.o ninja: build stopped *Build Failed #11: OS: SUSE15-64 Target: x86_64-native-linuxapp-clang FAILED: drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o clang -Idrivers/net/i40e/libi40e_avx512_lib.a.p -Idrivers/net/i40e -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/linux/include -I../lib/eal/linux/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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fcolor-diagnostics -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O3 -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-address-of-packed-member -Wno-missing-field-initializers -D_GNU_SOURCE -fPIC -march=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -DPF_DRIVER -DVF_DRIVER -DINTEGRATED_VF -DX722_A0_SUPPORT -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -MF drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o.d -o drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -c ../drivers/net/i40e/i40e_rxtx_vec_avx512.c In file included from ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:14: ../drivers/net/i40e/i40e_rxtx_common_avx.h:61:20: error: no member named 'buf_iova' in 'rte_mbuf' RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != ^ ~~~~~~~~ /usr/lib64/clang/11.0.1/include/stddef.h:104:24: note: expanded from macro 'offsetof' #define offsetof(t, d) __builtin_offsetof(t, d) ^ ~ ../lib/eal/include/rte_common.h:417:65: note: expanded from macro 'RTE_BUILD_BUG_ON' #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) ^~~~~~~~~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:76:4: error: no member named 'buf_iova' in 'rte_mbuf' (offsetof(struct rte_mbuf, buf_iova)); ^ ~~~~~~~~ /usr/lib64/clang/11.0.1/include/stddef.h:104:24: note: expanded from macro 'offsetof' #define offsetof(t, d) __builtin_offsetof(t, d) ^ ~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:997:10: error: no member named 'buf_iova' in 'struct rte_mbuf' pkt->buf_iova + pkt->data_off); ~~~ ^ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1028:21: error: no member named 'buf_iova' in 'struct rte_mbuf' (hi_qw3, pkt[3]->buf_iova + pkt[3]->data_off, ~~~~~~ ^ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1029:20: error: no member named 'buf_iova' in 'struct rte_mbuf' hi_qw2, pkt[2]->buf_iova + pkt[2]->data_off, ~~~~~~ ^ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1030:20: error: no member named 'buf_iova' in 'struct rte_mbuf' hi_qw1, pkt[1]->buf_iova + pkt[1]->data_off, ~~~~~~ ^ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1031:20: error: no member named 'buf_iova' in 'struct rte_mbuf' hi_qw0, pkt[0]->buf_iova + pkt[0]->data_off); ~~~~~~ ^ 7 errors generated. [920/2053] Compiling C object drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o FAILED: drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o clang -Idrivers/net/iavf/libiavf_avx512_lib.a.p -Idrivers/net/iavf -I../drivers/net/iavf -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/linux/include -I../lib/eal/linux/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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fcolor-diagnostics -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O3 -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-address-of-packed-member -Wno-missing-field-initializers -D_GNU_SOURCE -fPIC -march=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -Wno-strict-aliasing -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -MF drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o.d -o drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -c ../drivers/net/iavf/iavf_rxtx_vec_avx512.c In file included from ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:5: ../drivers/net/iavf/iavf_rxtx_vec_common.h:425:20: error: no member named 'buf_iova' in 'rte_mbuf' RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != ^ ~~~~~~~~ /usr/lib64/clang/11.0.1/include/stddef.h:104:24: note: expanded from macro 'offsetof' #define offsetof(t, d) __builtin_offsetof(t, d) ^ ~ ../lib/eal/include/rte_common.h:417:65: note: expanded from macro 'RTE_BUILD_BUG_ON' #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) ^~~~~~~~~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:81:50: error: no member named 'buf_iova' in 'rte_mbuf' const __m512i iova_offsets = _mm512_set1_epi64(offsetof ^ /usr/lib64/clang/11.0.1/include/stddef.h:104:24: note: expanded from macro 'offsetof' #define offsetof(t, d) __builtin_offsetof(t, d) ^ ~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1900:15: error: no member named 'buf_iova' in 'struct rte_mbuf' pkt->buf_iova + pkt->data_off); ~~~ ^ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1950:14: error: no member named 'buf_iova' in 'struct rte_mbuf' pkt[3]->buf_iova + pkt[3]->data_off, ~~~~~~ ^ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1952:14: error: no member named 'buf_iova' in 'struct rte_mbuf' pkt[2]->buf_iova + pkt[2]->data_off, ~~~~~~ ^ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1954:14: error: no member named 'buf_iova' in 'struct rte_mbuf' pkt[1]->buf_iova + pkt[1]->data_off, ~~~~~~ ^ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1956:14: error: no member named 'buf_iova' in 'struct rte_mbuf' pkt[0]->buf_iova + pkt[0]->data_off); ~~~~~~ ^ 7 errors generated. [921/2053] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_nvm.c.o [922/2053] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_controlq.c.o [923/2053] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_common.c.o [924/2053] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_nvm.c.o [925/2053] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_common.c.o [926/2053] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_sched.c.o [927/2053] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_flex_pipe.c.o [928/2053] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_switch.c.o ninja: build stopped *Build Failed #12: OS: SUSE15-64 Target: x86_64-native-linuxapp-gcc FAILED: drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o gcc -Idrivers/net/iavf/libiavf_avx512_lib.a.p -Idrivers/net/iavf -I../drivers/net/iavf -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/linux/include -I../lib/eal/linux/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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fdiagnostics-color=always -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O3 -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-missing-field-initializers -D_GNU_SOURCE -fPIC -march=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -Wno-format-truncation -Wno-strict-aliasing -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -MF drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o.d -o drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -c ../drivers/net/iavf/iavf_rxtx_vec_avx512.c In file included from ../lib/eal/include/dev_driver.h:12:0, from ../lib/ethdev/ethdev_driver.h:22, from ../drivers/net/iavf/iavf_rxtx_vec_common.h:8, from ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:5: ../drivers/net/iavf/iavf_rxtx_vec_common.h: In function ‘iavf_rxq_rearm_common’: ../drivers/net/iavf/iavf_rxtx_vec_common.h:425:46: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != ^ ../lib/eal/include/rte_common.h:417:65: note: in definition of macro ‘RTE_BUILD_BUG_ON’ #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) ^~~~~~~~~ In file included from /usr/include/bits/socket.h:27:0, from /usr/include/sys/socket.h:33, from ../lib/net/rte_ip.h:23, from ../lib/ethdev/rte_flow.h:24, from ../lib/ethdev/rte_eth_ctrl.h:11, from ../lib/ethdev/rte_ethdev.h:1419, from ../lib/ethdev/ethdev_driver.h:24, from ../drivers/net/iavf/iavf_rxtx_vec_common.h:8, from ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:5: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘iavf_rxq_rearm’: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:82:26: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? (struct rte_mbuf, buf_iova)); ^ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘iavf_vtx1’: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1900:15: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? pkt->buf_iova + pkt->data_off); ^~~~~~~~ buf_addr ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘iavf_vtx’: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1950:14: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? pkt[3]->buf_iova + pkt[3]->data_off, ^~~~~~~~ buf_addr ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1952:14: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? pkt[2]->buf_iova + pkt[2]->data_off, ^~~~~~~~ buf_addr ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1954:14: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? pkt[1]->buf_iova + pkt[1]->data_off, ^~~~~~~~ buf_addr ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1956:14: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? pkt[0]->buf_iova + pkt[0]->data_off); ^~~~~~~~ buf_addr [911/2051] Compiling C object drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o FAILED: drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o gcc -Idrivers/net/i40e/libi40e_avx512_lib.a.p -Idrivers/net/i40e -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/linux/include -I../lib/eal/linux/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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fdiagnostics-color=always -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O3 -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-missing-field-initializers -D_GNU_SOURCE -fPIC -march=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -Wno-format-truncation -DPF_DRIVER -DVF_DRIVER -DINTEGRATED_VF -DX722_A0_SUPPORT -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -MF drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o.d -o drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -c ../drivers/net/i40e/i40e_rxtx_vec_avx512.c In file included from ../lib/eal/include/dev_driver.h:12:0, from ../lib/ethdev/ethdev_driver.h:22, from ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:6: ../drivers/net/i40e/i40e_rxtx_common_avx.h: In function ‘i40e_rxq_rearm_common’: ../drivers/net/i40e/i40e_rxtx_common_avx.h:61:46: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != ^ ../lib/eal/include/rte_common.h:417:65: note: in definition of macro ‘RTE_BUILD_BUG_ON’ #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) ^~~~~~~~~ In file included from /usr/include/bits/socket.h:27:0, from /usr/include/sys/socket.h:33, from ../lib/net/rte_ip.h:23, from ../lib/ethdev/rte_flow.h:24, from ../lib/ethdev/rte_eth_ctrl.h:11, from ../lib/ethdev/rte_ethdev.h:1419, from ../lib/ethdev/ethdev_driver.h:24, from ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:6: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘i40e_rxq_rearm’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:76:30: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? (offsetof(struct rte_mbuf, buf_iova)); ^ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘vtx1’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:997:10: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? pkt->buf_iova + pkt->data_off); ^~~~~~~~ buf_addr ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘vtx’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1028:21: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? (hi_qw3, pkt[3]->buf_iova + pkt[3]->data_off, ^~~~~~~~ buf_addr ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1029:20: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? hi_qw2, pkt[2]->buf_iova + pkt[2]->data_off, ^~~~~~~~ buf_addr ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1030:20: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? hi_qw1, pkt[1]->buf_iova + pkt[1]->data_off, ^~~~~~~~ buf_addr ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1031:20: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? hi_qw0, pkt[0]->buf_iova + pkt[0]->data_off); ^~~~~~~~ buf_addr [912/2051] Compiling C object app/dpdk-testpmd.p/test-pmd_noisy_vnf.c.o [913/2051] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_controlq.c.o [914/2051] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_nvm.c.o [915/2051] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_common.c.o [916/2051] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_common.c.o [917/2051] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_sched.c.o [918/2051] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_switch.c.o [919/2051] Generating drivers/rte_common_cnxk.sym_chk with a custom command (wrapped by meson to capture output) ninja: build stopped *Build Failed #13: OS: RHEL90-64 Target: x86_64-native-linuxapp-gcc FAILED: drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o gcc -Idrivers/net/i40e/libi40e_avx512_lib.a.p -Idrivers/net/i40e -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/linux/include -I../lib/eal/linux/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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fdiagnostics-color=always -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O3 -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-address-of-packed-member -Wno-packed-not-aligned -Wno-missing-field-initializers -Wno-zero-length-bounds -D_GNU_SOURCE -fPIC -march=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -Wno-format-truncation -DPF_DRIVER -DVF_DRIVER -DINTEGRATED_VF -DX722_A0_SUPPORT -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -MF drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o.d -o drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -c ../drivers/net/i40e/i40e_rxtx_vec_avx512.c In file included from ../lib/eal/include/dev_driver.h:12, from ../lib/ethdev/ethdev_driver.h:22, from ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:6: ../drivers/net/i40e/i40e_rxtx_common_avx.h: In function ‘i40e_rxq_rearm_common’: ../drivers/net/i40e/i40e_rxtx_common_avx.h:61:34: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 61 | RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != | ^~~~~~~~ ../lib/eal/include/rte_common.h:417:65: note: in definition of macro ‘RTE_BUILD_BUG_ON’ 417 | #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) | ^~~~~~~~~ In file included from /usr/include/bits/socket.h:27, from /usr/include/sys/socket.h:33, from ../lib/net/rte_ip.h:23, from ../lib/ethdev/rte_flow.h:24, from ../lib/ethdev/rte_eth_ctrl.h:11, from ../lib/ethdev/rte_ethdev.h:1419, from ../lib/ethdev/ethdev_driver.h:24, from ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:6: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘i40e_rxq_rearm’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:76:18: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 76 | (offsetof(struct rte_mbuf, buf_iova)); | ^~~~~~~~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘vtx1’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:997:36: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 997 | pkt->buf_iova + pkt->data_off); | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘vtx’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1028:40: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1028 | (hi_qw3, pkt[3]->buf_iova + pkt[3]->data_off, | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1029:39: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1029 | hi_qw2, pkt[2]->buf_iova + pkt[2]->data_off, | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1030:39: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1030 | hi_qw1, pkt[1]->buf_iova + pkt[1]->data_off, | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1031:39: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1031 | hi_qw0, pkt[0]->buf_iova + pkt[0]->data_off); | ^~ [916/2031] Compiling C object drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o FAILED: drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o gcc -Idrivers/net/iavf/libiavf_avx512_lib.a.p -Idrivers/net/iavf -I../drivers/net/iavf -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/linux/include -I../lib/eal/linux/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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fdiagnostics-color=always -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O3 -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-address-of-packed-member -Wno-packed-not-aligned -Wno-missing-field-initializers -Wno-zero-length-bounds -D_GNU_SOURCE -fPIC -march=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -Wno-format-truncation -Wno-strict-aliasing -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -MF drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o.d -o drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -c ../drivers/net/iavf/iavf_rxtx_vec_avx512.c In file included from ../lib/eal/include/dev_driver.h:12, from ../lib/ethdev/ethdev_driver.h:22, from ../drivers/net/iavf/iavf_rxtx_vec_common.h:8, from ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:5: ../drivers/net/iavf/iavf_rxtx_vec_common.h: In function ‘iavf_rxq_rearm_common’: ../drivers/net/iavf/iavf_rxtx_vec_common.h:425:34: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 425 | RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != | ^~~~~~~~ ../lib/eal/include/rte_common.h:417:65: note: in definition of macro ‘RTE_BUILD_BUG_ON’ 417 | #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) | ^~~~~~~~~ In file included from /usr/include/bits/socket.h:27, from /usr/include/sys/socket.h:33, from ../lib/net/rte_ip.h:23, from ../lib/ethdev/rte_flow.h:24, from ../lib/ethdev/rte_eth_ctrl.h:11, from ../lib/ethdev/rte_ethdev.h:1419, from ../lib/ethdev/ethdev_driver.h:24, from ../drivers/net/iavf/iavf_rxtx_vec_common.h:8, from ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:5: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘iavf_rxq_rearm’: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:81:57: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 81 | const __m512i iova_offsets = _mm512_set1_epi64(offsetof | ^~~~~~~~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘iavf_vtx1’: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1900:48: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1900 | pkt->buf_iova + pkt->data_off); | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘iavf_vtx’: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1950:40: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1950 | pkt[3]->buf_iova + pkt[3]->data_off, | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1952:40: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1952 | pkt[2]->buf_iova + pkt[2]->data_off, | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1954:40: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1954 | pkt[1]->buf_iova + pkt[1]->data_off, | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1956:40: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1956 | pkt[0]->buf_iova + pkt[0]->data_off); | ^~ [917/2031] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_adminq.c.o [918/2031] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_controlq.c.o [919/2031] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_lan_hmc.c.o [920/2031] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_nvm.c.o [921/2031] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_common.c.o [922/2031] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_common.c.o [923/2031] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_sched.c.o [924/2031] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_switch.c.o ninja: build stopped *Build Failed #14: OS: UB2004-64 Target: x86_64-native-linuxapp-clang FAILED: kernel/linux/kni/rte_kni.ko /usr/bin/make -j4 -C /lib/modules/5.8.0-48-generic/build M=/root/UB2004-64_K5.8.0_Clang10.0.0/x86_64-native-linuxapp-clang/26028/dpdk/x86_64-native-linuxapp-clang/kernel/linux/kni src=/root/UB2004-64_K5.8.0_Clang10.0.0/x86_64-native-linuxapp-clang/26028/dpdk/kernel/linux/kni 'MODULE_CFLAGS= -include /root/UB2004-64_K5.8.0_Clang10.0.0/x86_64-native-linuxapp-clang/26028/dpdk/config/rte_config.h -I/root/UB2004-64_K5.8.0_Clang10.0.0/x86_64-native-linuxapp-clang/26028/dpdk/lib/eal/include -I/root/UB2004-64_K5.8.0_Clang10.0.0/x86_64-native-linuxapp-clang/26028/dpdk/lib/kni -I/root/UB2004-64_K5.8.0_Clang10.0.0/x86_64-native-linuxapp-clang/26028/dpdk/x86_64-native-linuxapp-clang -I/root/UB2004-64_K5.8.0_Clang10.0.0/x86_64-native-linuxapp-clang/26028/dpdk/kernel/linux/kni' modules make: Entering directory '/usr/src/linux-headers-5.8.0-48-generic' CC [M] /root/UB2004-64_K5.8.0_Clang10.0.0/x86_64-native-linuxapp-clang/26028/dpdk/x86_64-native-linuxapp-clang/kernel/linux/kni/kni_misc.o CC [M] /root/UB2004-64_K5.8.0_Clang10.0.0/x86_64-native-linuxapp-clang/26028/dpdk/x86_64-native-linuxapp-clang/kernel/linux/kni/kni_net.o /root/UB2004-64_K5.8.0_Clang10.0.0/x86_64-native-linuxapp-clang/26028/dpdk/kernel/linux/kni/kni_net.c: In function ‘iova2data_kva’: /root/UB2004-64_K5.8.0_Clang10.0.0/x86_64-native-linuxapp-clang/26028/dpdk/kernel/linux/kni/kni_net.c:51:50: error: ‘struct rte_kni_mbuf’ has no member named ‘buf_iova’ 51 | return phys_to_virt(iova_to_phys(kni->usr_tsk, m->buf_iova) + | ^~ /root/UB2004-64_K5.8.0_Clang10.0.0/x86_64-native-linuxapp-clang/26028/dpdk/kernel/linux/kni/kni_net.c: In function ‘pa2va’: /root/UB2004-64_K5.8.0_Clang10.0.0/x86_64-native-linuxapp-clang/26028/dpdk/kernel/linux/kni/kni_net.c:71:20: error: ‘struct rte_kni_mbuf’ has no member named ‘buf_iova’ 71 | (unsigned long)m->buf_iova); | ^~ /root/UB2004-64_K5.8.0_Clang10.0.0/x86_64-native-linuxapp-clang/26028/dpdk/kernel/linux/kni/kni_net.c: In function ‘kva2data_kva’: /root/UB2004-64_K5.8.0_Clang10.0.0/x86_64-native-linuxapp-clang/26028/dpdk/kernel/linux/kni/kni_net.c:79:23: error: ‘struct rte_kni_mbuf’ has no member named ‘buf_iova’ 79 | return phys_to_virt(m->buf_iova + m->data_off); | ^~ /root/UB2004-64_K5.8.0_Clang10.0.0/x86_64-native-linuxapp-clang/26028/dpdk/kernel/linux/kni/kni_net.c: In function ‘iova2data_kva’: /root/UB2004-64_K5.8.0_Clang10.0.0/x86_64-native-linuxapp-clang/26028/dpdk/kernel/linux/kni/kni_net.c:53:1: warning: control reaches end of non-void function [-Wreturn-type] 53 | } | ^ /root/UB2004-64_K5.8.0_Clang10.0.0/x86_64-native-linuxapp-clang/26028/dpdk/kernel/linux/kni/kni_net.c: In function ‘kva2data_kva’: /root/UB2004-64_K5.8.0_Clang10.0.0/x86_64-native-linuxapp-clang/26028/dpdk/kernel/linux/kni/kni_net.c:80:1: warning: control reaches end of non-void function [-Wreturn-type] 80 | } | ^ make[1]: *** [scripts/Makefile.build:286: /root/UB2004-64_K5.8.0_Clang10.0.0/x86_64-native-linuxapp-clang/26028/dpdk/x86_64-native-linuxapp-clang/kernel/linux/kni/kni_net.o] Error 1 make[1]: *** Waiting for unfinished jobs.... make: *** [Makefile:1783: /root/UB2004-64_K5.8.0_Clang10.0.0/x86_64-native-linuxapp-clang/26028/dpdk/x86_64-native-linuxapp-clang/kernel/linux/kni] Error 2 make: Leaving directory '/usr/src/linux-headers-5.8.0-48-generic' [510/2053] Compiling C object drivers/libtmp_rte_common_cnxk.a.p/common_cnxk_roc_dev.c.o [511/2053] Compiling C object drivers/libtmp_rte_common_cnxk.a.p/common_cnxk_roc_hash.c.o [512/2053] Compiling C object drivers/libtmp_rte_common_cnxk.a.p/common_cnxk_roc_idev.c.o [513/2053] Compiling C object drivers/libtmp_rte_common_cnxk.a.p/common_cnxk_roc_ie_ot.c.o [514/2053] Compiling C object lib/librte_pipeline.a.p/pipeline_rte_swx_pipeline.c.o [515/2053] Compiling C object drivers/libtmp_rte_common_cnxk.a.p/common_cnxk_roc_irq.c.o [516/2053] Compiling C object drivers/libtmp_rte_common_cnxk.a.p/common_cnxk_roc_mbox.c.o [517/2053] Generating vhost.sym_chk with a custom command (wrapped by meson to capture output) [518/2053] Compiling C object lib/librte_pipeline.a.p/pipeline_rte_table_action.c.o ninja: build stopped *Build Failed #15: OS: UB2004-64 Target: x86_64-native-linuxapp-gcc FAILED: drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o gcc -Idrivers/net/iavf/libiavf_avx512_lib.a.p -Idrivers/net/iavf -I../drivers/net/iavf -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/linux/include -I../lib/eal/linux/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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fdiagnostics-color=always -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O3 -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-address-of-packed-member -Wno-packed-not-aligned -Wno-missing-field-initializers -Wno-zero-length-bounds -D_GNU_SOURCE -fPIC -march=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -Wno-format-truncation -Wno-strict-aliasing -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -MF drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o.d -o drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -c ../drivers/net/iavf/iavf_rxtx_vec_avx512.c In file included from ../lib/eal/include/dev_driver.h:12, from ../lib/ethdev/ethdev_driver.h:22, from ../drivers/net/iavf/iavf_rxtx_vec_common.h:8, from ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:5: ../drivers/net/iavf/iavf_rxtx_vec_common.h: In function ‘iavf_rxq_rearm_common’: ../drivers/net/iavf/iavf_rxtx_vec_common.h:425:20: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 425 | RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != | ^~~~~~~~ ../lib/eal/include/rte_common.h:417:65: note: in definition of macro ‘RTE_BUILD_BUG_ON’ 417 | #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) | ^~~~~~~~~ In file included from /usr/include/x86_64-linux-gnu/bits/socket.h:27, from /usr/include/x86_64-linux-gnu/sys/socket.h:33, from ../lib/net/rte_ip.h:23, from ../lib/ethdev/rte_flow.h:24, from ../lib/ethdev/rte_eth_ctrl.h:11, from ../lib/ethdev/rte_ethdev.h:1419, from ../lib/ethdev/ethdev_driver.h:24, from ../drivers/net/iavf/iavf_rxtx_vec_common.h:8, from ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:5: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘iavf_rxq_rearm’: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:81:50: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 81 | const __m512i iova_offsets = _mm512_set1_epi64(offsetof | ^~~~~~~~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘iavf_vtx1’: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1900:13: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1900 | pkt->buf_iova + pkt->data_off); | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘iavf_vtx’: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1950:12: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1950 | pkt[3]->buf_iova + pkt[3]->data_off, | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1952:12: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1952 | pkt[2]->buf_iova + pkt[2]->data_off, | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1954:12: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1954 | pkt[1]->buf_iova + pkt[1]->data_off, | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1956:12: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1956 | pkt[0]->buf_iova + pkt[0]->data_off); | ^~ [922/2053] Compiling C object drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o FAILED: drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o gcc -Idrivers/net/i40e/libi40e_avx512_lib.a.p -Idrivers/net/i40e -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/linux/include -I../lib/eal/linux/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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fdiagnostics-color=always -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O3 -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-address-of-packed-member -Wno-packed-not-aligned -Wno-missing-field-initializers -Wno-zero-length-bounds -D_GNU_SOURCE -fPIC -march=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -Wno-format-truncation -DPF_DRIVER -DVF_DRIVER -DINTEGRATED_VF -DX722_A0_SUPPORT -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -MF drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o.d -o drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -c ../drivers/net/i40e/i40e_rxtx_vec_avx512.c In file included from ../lib/eal/include/dev_driver.h:12, from ../lib/ethdev/ethdev_driver.h:22, from ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:6: ../drivers/net/i40e/i40e_rxtx_common_avx.h: In function ‘i40e_rxq_rearm_common’: ../drivers/net/i40e/i40e_rxtx_common_avx.h:61:20: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 61 | RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != | ^~~~~~~~ ../lib/eal/include/rte_common.h:417:65: note: in definition of macro ‘RTE_BUILD_BUG_ON’ 417 | #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) | ^~~~~~~~~ In file included from /usr/include/x86_64-linux-gnu/bits/socket.h:27, from /usr/include/x86_64-linux-gnu/sys/socket.h:33, from ../lib/net/rte_ip.h:23, from ../lib/ethdev/rte_flow.h:24, from ../lib/ethdev/rte_eth_ctrl.h:11, from ../lib/ethdev/rte_ethdev.h:1419, from ../lib/ethdev/ethdev_driver.h:24, from ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:6: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘i40e_rxq_rearm’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:76:4: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 76 | (offsetof(struct rte_mbuf, buf_iova)); | ^~~~~~~~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘vtx1’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:997:8: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 997 | pkt->buf_iova + pkt->data_off); | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘vtx’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1028:19: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1028 | (hi_qw3, pkt[3]->buf_iova + pkt[3]->data_off, | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1029:18: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1029 | hi_qw2, pkt[2]->buf_iova + pkt[2]->data_off, | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1030:18: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1030 | hi_qw1, pkt[1]->buf_iova + pkt[1]->data_off, | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1031:18: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1031 | hi_qw0, pkt[0]->buf_iova + pkt[0]->data_off); | ^~ [923/2053] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_nvm.c.o [924/2053] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_controlq.c.o [925/2053] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_nvm.c.o [926/2053] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_common.c.o [927/2053] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_common.c.o [928/2053] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_flex_pipe.c.o [929/2053] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_sched.c.o [930/2053] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_switch.c.o ninja: build stopped *Build Failed #16: OS: UB2204-32 Target: i686-native-linuxapp-gcc FAILED: drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o gcc -Idrivers/net/i40e/libi40e_avx512_lib.a.p -Idrivers/net/i40e -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/linux/include -I../lib/eal/linux/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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fdiagnostics-color=always -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O3 -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-address-of-packed-member -Wno-packed-not-aligned -Wno-missing-field-initializers -Wno-zero-length-bounds -Wno-pointer-to-int-cast -D_GNU_SOURCE -m32 -fPIC -march=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -Wno-format-truncation -DPF_DRIVER -DVF_DRIVER -DINTEGRATED_VF -DX722_A0_SUPPORT -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -MF drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o.d -o drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -c ../drivers/net/i40e/i40e_rxtx_vec_avx512.c In file included from ../lib/eal/include/dev_driver.h:12, from ../lib/ethdev/ethdev_driver.h:22, from ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:6: ../drivers/net/i40e/i40e_rxtx_common_avx.h: In function ‘i40e_rxq_rearm_common’: ../drivers/net/i40e/i40e_rxtx_common_avx.h:61:34: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 61 | RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != | ^~~~~~~~ ../lib/eal/include/rte_common.h:417:65: note: in definition of macro ‘RTE_BUILD_BUG_ON’ 417 | #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) | ^~~~~~~~~ In file included from /usr/include/i386-linux-gnu/bits/socket.h:27, from /usr/include/i386-linux-gnu/sys/socket.h:33, from ../lib/net/rte_ip.h:23, from ../lib/ethdev/rte_flow.h:24, from ../lib/ethdev/rte_eth_ctrl.h:11, from ../lib/ethdev/rte_ethdev.h:1419, from ../lib/ethdev/ethdev_driver.h:24, from ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:6: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘i40e_rxq_rearm’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:76:18: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 76 | (offsetof(struct rte_mbuf, buf_iova)); | ^~~~~~~~ In file included from ../lib/eal/include/dev_driver.h:12, from ../lib/ethdev/ethdev_driver.h:22, from ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:6: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘_recv_raw_pkts_vec_avx512’: ../lib/eal/include/rte_common.h:417:55: error: size of unnamed array is negative 417 | #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) | ^ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:686:17: note: in expansion of macro ‘RTE_BUILD_BUG_ON’ 686 | RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, rearm_data) != | ^~~~~~~~~~~~~~~~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘vtx1’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:997:36: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 997 | pkt->buf_iova + pkt->data_off); | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘vtx’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1028:40: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1028 | (hi_qw3, pkt[3]->buf_iova + pkt[3]->data_off, | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1029:39: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1029 | hi_qw2, pkt[2]->buf_iova + pkt[2]->data_off, | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1030:39: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1030 | hi_qw1, pkt[1]->buf_iova + pkt[1]->data_off, | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1031:39: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1031 | hi_qw0, pkt[0]->buf_iova + pkt[0]->data_off); | ^~ [592/1224] Compiling C object drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o FAILED: drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o gcc -Idrivers/net/iavf/libiavf_avx512_lib.a.p -Idrivers/net/iavf -I../drivers/net/iavf -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/linux/include -I../lib/eal/linux/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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fdiagnostics-color=always -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O3 -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-address-of-packed-member -Wno-packed-not-aligned -Wno-missing-field-initializers -Wno-zero-length-bounds -Wno-pointer-to-int-cast -D_GNU_SOURCE -m32 -fPIC -march=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -Wno-format-truncation -Wno-strict-aliasing -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -MF drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o.d -o drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -c ../drivers/net/iavf/iavf_rxtx_vec_avx512.c In file included from ../lib/eal/include/dev_driver.h:12, from ../lib/ethdev/ethdev_driver.h:22, from ../drivers/net/iavf/iavf_rxtx_vec_common.h:8, from ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:5: ../drivers/net/iavf/iavf_rxtx_vec_common.h: In function ‘iavf_rxq_rearm_common’: ../drivers/net/iavf/iavf_rxtx_vec_common.h:425:34: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 425 | RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != | ^~~~~~~~ ../lib/eal/include/rte_common.h:417:65: note: in definition of macro ‘RTE_BUILD_BUG_ON’ 417 | #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) | ^~~~~~~~~ In file included from /usr/include/i386-linux-gnu/bits/socket.h:27, from /usr/include/i386-linux-gnu/sys/socket.h:33, from ../lib/net/rte_ip.h:23, from ../lib/ethdev/rte_flow.h:24, from ../lib/ethdev/rte_eth_ctrl.h:11, from ../lib/ethdev/rte_ethdev.h:1419, from ../lib/ethdev/ethdev_driver.h:24, from ../drivers/net/iavf/iavf_rxtx_vec_common.h:8, from ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:5: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘iavf_rxq_rearm’: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:81:57: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 81 | const __m512i iova_offsets = _mm512_set1_epi64(offsetof | ^~~~~~~~ In file included from ../lib/eal/include/dev_driver.h:12, from ../lib/ethdev/ethdev_driver.h:22, from ../drivers/net/iavf/iavf_rxtx_vec_common.h:8, from ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:5: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘_iavf_recv_raw_pkts_vec_avx512’: ../lib/eal/include/rte_common.h:417:55: error: size of unnamed array is negative 417 | #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) | ^ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:540:17: note: in expansion of macro ‘RTE_BUILD_BUG_ON’ 540 | RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, rearm_data) != | ^~~~~~~~~~~~~~~~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘_iavf_recv_raw_pkts_vec_avx512_flex_rxd’: ../lib/eal/include/rte_common.h:417:55: error: size of unnamed array is negative 417 | #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) | ^ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1421:17: note: in expansion of macro ‘RTE_BUILD_BUG_ON’ 1421 | RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, rearm_data) != | ^~~~~~~~~~~~~~~~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘iavf_vtx1’: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1900:48: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1900 | pkt->buf_iova + pkt->data_off); | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘iavf_vtx’: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1950:40: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1950 | pkt[3]->buf_iova + pkt[3]->data_off, | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1952:40: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1952 | pkt[2]->buf_iova + pkt[2]->data_off, | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1954:40: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1954 | pkt[1]->buf_iova + pkt[1]->data_off, | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1956:40: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1956 | pkt[0]->buf_iova + pkt[0]->data_off); | ^~ [593/1224] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_controlq.c.o [594/1224] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_nvm.c.o [595/1224] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_sched.c.o [596/1224] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_common.c.o [597/1224] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_common.c.o [598/1224] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_switch.c.o [599/1224] Compiling C object lib/librte_pipeline.a.p/pipeline_rte_table_action.c.o [600/1224] Generating lib/vhost.sym_chk with a custom command (wrapped by meson to capture output) ninja: build stopped *Build Failed #17: OS: UB2004-64 Target: x86_64-native-linuxapp-doc FAILED: drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o gcc -Idrivers/net/iavf/libiavf_avx512_lib.a.p -Idrivers/net/iavf -I../drivers/net/iavf -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/linux/include -I../lib/eal/linux/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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fdiagnostics-color=always -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O3 -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-address-of-packed-member -Wno-packed-not-aligned -Wno-missing-field-initializers -Wno-zero-length-bounds -D_GNU_SOURCE -fPIC -march=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -Wno-format-truncation -Wno-strict-aliasing -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -MF drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o.d -o drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -c ../drivers/net/iavf/iavf_rxtx_vec_avx512.c In file included from ../lib/eal/include/dev_driver.h:12, from ../lib/ethdev/ethdev_driver.h:22, from ../drivers/net/iavf/iavf_rxtx_vec_common.h:8, from ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:5: ../drivers/net/iavf/iavf_rxtx_vec_common.h: In function ‘iavf_rxq_rearm_common’: ../drivers/net/iavf/iavf_rxtx_vec_common.h:425:20: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 425 | RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != | ^~~~~~~~ ../lib/eal/include/rte_common.h:417:65: note: in definition of macro ‘RTE_BUILD_BUG_ON’ 417 | #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) | ^~~~~~~~~ In file included from /usr/include/x86_64-linux-gnu/bits/socket.h:27, from /usr/include/x86_64-linux-gnu/sys/socket.h:33, from ../lib/net/rte_ip.h:23, from ../lib/ethdev/rte_flow.h:24, from ../lib/ethdev/rte_eth_ctrl.h:11, from ../lib/ethdev/rte_ethdev.h:1419, from ../lib/ethdev/ethdev_driver.h:24, from ../drivers/net/iavf/iavf_rxtx_vec_common.h:8, from ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:5: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘iavf_rxq_rearm’: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:81:50: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 81 | const __m512i iova_offsets = _mm512_set1_epi64(offsetof | ^~~~~~~~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘iavf_vtx1’: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1900:13: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1900 | pkt->buf_iova + pkt->data_off); | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘iavf_vtx’: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1950:12: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1950 | pkt[3]->buf_iova + pkt[3]->data_off, | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1952:12: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1952 | pkt[2]->buf_iova + pkt[2]->data_off, | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1954:12: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1954 | pkt[1]->buf_iova + pkt[1]->data_off, | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1956:12: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1956 | pkt[0]->buf_iova + pkt[0]->data_off); | ^~ [915/1865] Compiling C object drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o FAILED: drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o gcc -Idrivers/net/i40e/libi40e_avx512_lib.a.p -Idrivers/net/i40e -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/linux/include -I../lib/eal/linux/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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fdiagnostics-color=always -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O3 -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-address-of-packed-member -Wno-packed-not-aligned -Wno-missing-field-initializers -Wno-zero-length-bounds -D_GNU_SOURCE -fPIC -march=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -Wno-format-truncation -DPF_DRIVER -DVF_DRIVER -DINTEGRATED_VF -DX722_A0_SUPPORT -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -MF drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o.d -o drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -c ../drivers/net/i40e/i40e_rxtx_vec_avx512.c In file included from ../lib/eal/include/dev_driver.h:12, from ../lib/ethdev/ethdev_driver.h:22, from ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:6: ../drivers/net/i40e/i40e_rxtx_common_avx.h: In function ‘i40e_rxq_rearm_common’: ../drivers/net/i40e/i40e_rxtx_common_avx.h:61:20: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 61 | RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != | ^~~~~~~~ ../lib/eal/include/rte_common.h:417:65: note: in definition of macro ‘RTE_BUILD_BUG_ON’ 417 | #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) | ^~~~~~~~~ In file included from /usr/include/x86_64-linux-gnu/bits/socket.h:27, from /usr/include/x86_64-linux-gnu/sys/socket.h:33, from ../lib/net/rte_ip.h:23, from ../lib/ethdev/rte_flow.h:24, from ../lib/ethdev/rte_eth_ctrl.h:11, from ../lib/ethdev/rte_ethdev.h:1419, from ../lib/ethdev/ethdev_driver.h:24, from ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:6: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘i40e_rxq_rearm’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:76:4: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 76 | (offsetof(struct rte_mbuf, buf_iova)); | ^~~~~~~~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘vtx1’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:997:8: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 997 | pkt->buf_iova + pkt->data_off); | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘vtx’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1028:19: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1028 | (hi_qw3, pkt[3]->buf_iova + pkt[3]->data_off, | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1029:18: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1029 | hi_qw2, pkt[2]->buf_iova + pkt[2]->data_off, | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1030:18: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1030 | hi_qw1, pkt[1]->buf_iova + pkt[1]->data_off, | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1031:18: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1031 | hi_qw0, pkt[0]->buf_iova + pkt[0]->data_off); | ^~ [916/1865] Linking target drivers/librte_net_failsafe.so.23.1 [917/1865] Generating rte_net_cnxk.sym_chk with a custom command (wrapped by meson to capture output) [918/1865] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_nvm.c.o [919/1865] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_controlq.c.o [920/1865] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_common.c.o [921/1865] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_common.c.o [922/1865] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_sched.c.o [923/1865] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_switch.c.o ninja: build stopped *Build Failed #18: OS: UB2204-64 Target: x86_64-native-linuxapp-gcc+16byte FAILED: drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o gcc -Idrivers/net/iavf/libiavf_avx512_lib.a.p -Idrivers/net/iavf -I../drivers/net/iavf -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/linux/include -I../lib/eal/linux/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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fdiagnostics-color=always -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O3 -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-address-of-packed-member -Wno-packed-not-aligned -Wno-missing-field-initializers -Wno-zero-length-bounds -D_GNU_SOURCE -DRTE_LIBRTE_I40E_16BYTE_RX_DESC -DRTE_LIBRTE_ICE_16BYTE_RX_DESC -fPIC -march=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -Wno-format-truncation -Wno-strict-aliasing -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -MF drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o.d -o drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -c ../drivers/net/iavf/iavf_rxtx_vec_avx512.c In file included from ../lib/eal/include/dev_driver.h:12, from ../lib/ethdev/ethdev_driver.h:22, from ../drivers/net/iavf/iavf_rxtx_vec_common.h:8, from ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:5: ../drivers/net/iavf/iavf_rxtx_vec_common.h: In function ‘iavf_rxq_rearm_common’: ../drivers/net/iavf/iavf_rxtx_vec_common.h:425:34: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 425 | RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != | ^~~~~~~~ ../lib/eal/include/rte_common.h:417:65: note: in definition of macro ‘RTE_BUILD_BUG_ON’ 417 | #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) | ^~~~~~~~~ In file included from /usr/include/x86_64-linux-gnu/bits/socket.h:27, from /usr/include/x86_64-linux-gnu/sys/socket.h:33, from ../lib/net/rte_ip.h:23, from ../lib/ethdev/rte_flow.h:24, from ../lib/ethdev/rte_eth_ctrl.h:11, from ../lib/ethdev/rte_ethdev.h:1419, from ../lib/ethdev/ethdev_driver.h:24, from ../drivers/net/iavf/iavf_rxtx_vec_common.h:8, from ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:5: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘iavf_rxq_rearm’: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:81:57: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 81 | const __m512i iova_offsets = _mm512_set1_epi64(offsetof | ^~~~~~~~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘iavf_vtx1’: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1900:48: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1900 | pkt->buf_iova + pkt->data_off); | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘iavf_vtx’: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1950:40: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1950 | pkt[3]->buf_iova + pkt[3]->data_off, | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1952:40: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1952 | pkt[2]->buf_iova + pkt[2]->data_off, | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1954:40: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1954 | pkt[1]->buf_iova + pkt[1]->data_off, | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1956:40: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1956 | pkt[0]->buf_iova + pkt[0]->data_off); | ^~ [920/2053] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_diag.c.o [921/2053] Compiling C object drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o FAILED: drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o gcc -Idrivers/net/i40e/libi40e_avx512_lib.a.p -Idrivers/net/i40e -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/linux/include -I../lib/eal/linux/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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fdiagnostics-color=always -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O3 -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-address-of-packed-member -Wno-packed-not-aligned -Wno-missing-field-initializers -Wno-zero-length-bounds -D_GNU_SOURCE -DRTE_LIBRTE_I40E_16BYTE_RX_DESC -DRTE_LIBRTE_ICE_16BYTE_RX_DESC -fPIC -march=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -Wno-format-truncation -DPF_DRIVER -DVF_DRIVER -DINTEGRATED_VF -DX722_A0_SUPPORT -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -MF drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o.d -o drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -c ../drivers/net/i40e/i40e_rxtx_vec_avx512.c In file included from ../lib/eal/include/dev_driver.h:12, from ../lib/ethdev/ethdev_driver.h:22, from ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:6: ../drivers/net/i40e/i40e_rxtx_common_avx.h: In function ‘i40e_rxq_rearm_common’: ../drivers/net/i40e/i40e_rxtx_common_avx.h:104:42: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 104 | RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != | ^~~~~~~~ ../lib/eal/include/rte_common.h:417:65: note: in definition of macro ‘RTE_BUILD_BUG_ON’ 417 | #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) | ^~~~~~~~~ ../drivers/net/i40e/i40e_rxtx_common_avx.h:168:42: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 168 | RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != | ^~~~~~~~ ../lib/eal/include/rte_common.h:417:65: note: in definition of macro ‘RTE_BUILD_BUG_ON’ 417 | #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) | ^~~~~~~~~ In file included from /usr/include/x86_64-linux-gnu/bits/socket.h:27, from /usr/include/x86_64-linux-gnu/sys/socket.h:33, from ../lib/net/rte_ip.h:23, from ../lib/ethdev/rte_flow.h:24, from ../lib/ethdev/rte_eth_ctrl.h:11, from ../lib/ethdev/rte_ethdev.h:1419, from ../lib/ethdev/ethdev_driver.h:24, from ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:6: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘i40e_rxq_rearm’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:76:18: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 76 | (offsetof(struct rte_mbuf, buf_iova)); | ^~~~~~~~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘vtx1’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:997:36: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 997 | pkt->buf_iova + pkt->data_off); | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘vtx’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1028:40: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1028 | (hi_qw3, pkt[3]->buf_iova + pkt[3]->data_off, | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1029:39: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1029 | hi_qw2, pkt[2]->buf_iova + pkt[2]->data_off, | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1030:39: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1030 | hi_qw1, pkt[1]->buf_iova + pkt[1]->data_off, | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1031:39: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1031 | hi_qw0, pkt[0]->buf_iova + pkt[0]->data_off); | ^~ [922/2053] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_dcb.c.o [923/2053] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_lan_hmc.c.o [924/2053] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_nvm.c.o [925/2053] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_controlq.c.o [926/2053] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_common.c.o [927/2053] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_common.c.o [928/2053] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_sched.c.o ninja: build stopped *Build Failed #19: OS: UB2204-64 Target: x86_64-native-linuxapp-gcc FAILED: drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o gcc -Idrivers/net/i40e/libi40e_avx512_lib.a.p -Idrivers/net/i40e -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/linux/include -I../lib/eal/linux/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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fdiagnostics-color=always -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O3 -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-address-of-packed-member -Wno-packed-not-aligned -Wno-missing-field-initializers -Wno-zero-length-bounds -D_GNU_SOURCE -fPIC -march=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -Wno-format-truncation -DPF_DRIVER -DVF_DRIVER -DINTEGRATED_VF -DX722_A0_SUPPORT -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -MF drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o.d -o drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -c ../drivers/net/i40e/i40e_rxtx_vec_avx512.c In file included from ../lib/eal/include/dev_driver.h:12, from ../lib/ethdev/ethdev_driver.h:22, from ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:6: ../drivers/net/i40e/i40e_rxtx_common_avx.h: In function ‘i40e_rxq_rearm_common’: ../drivers/net/i40e/i40e_rxtx_common_avx.h:61:34: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 61 | RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != | ^~~~~~~~ ../lib/eal/include/rte_common.h:417:65: note: in definition of macro ‘RTE_BUILD_BUG_ON’ 417 | #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) | ^~~~~~~~~ In file included from /usr/include/x86_64-linux-gnu/bits/socket.h:27, from /usr/include/x86_64-linux-gnu/sys/socket.h:33, from ../lib/net/rte_ip.h:23, from ../lib/ethdev/rte_flow.h:24, from ../lib/ethdev/rte_eth_ctrl.h:11, from ../lib/ethdev/rte_ethdev.h:1419, from ../lib/ethdev/ethdev_driver.h:24, from ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:6: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘i40e_rxq_rearm’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:76:18: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 76 | (offsetof(struct rte_mbuf, buf_iova)); | ^~~~~~~~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘vtx1’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:997:36: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 997 | pkt->buf_iova + pkt->data_off); | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘vtx’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1028:40: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1028 | (hi_qw3, pkt[3]->buf_iova + pkt[3]->data_off, | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1029:39: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1029 | hi_qw2, pkt[2]->buf_iova + pkt[2]->data_off, | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1030:39: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1030 | hi_qw1, pkt[1]->buf_iova + pkt[1]->data_off, | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1031:39: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1031 | hi_qw0, pkt[0]->buf_iova + pkt[0]->data_off); | ^~ [920/2053] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_dcb.c.o [921/2053] Compiling C object app/dpdk-testpmd.p/test-pmd_config.c.o [922/2053] Compiling C object drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o FAILED: drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o gcc -Idrivers/net/iavf/libiavf_avx512_lib.a.p -Idrivers/net/iavf -I../drivers/net/iavf -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/linux/include -I../lib/eal/linux/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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fdiagnostics-color=always -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O3 -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-address-of-packed-member -Wno-packed-not-aligned -Wno-missing-field-initializers -Wno-zero-length-bounds -D_GNU_SOURCE -fPIC -march=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -Wno-format-truncation -Wno-strict-aliasing -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -MF drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o.d -o drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -c ../drivers/net/iavf/iavf_rxtx_vec_avx512.c In file included from ../lib/eal/include/dev_driver.h:12, from ../lib/ethdev/ethdev_driver.h:22, from ../drivers/net/iavf/iavf_rxtx_vec_common.h:8, from ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:5: ../drivers/net/iavf/iavf_rxtx_vec_common.h: In function ‘iavf_rxq_rearm_common’: ../drivers/net/iavf/iavf_rxtx_vec_common.h:425:34: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 425 | RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != | ^~~~~~~~ ../lib/eal/include/rte_common.h:417:65: note: in definition of macro ‘RTE_BUILD_BUG_ON’ 417 | #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) | ^~~~~~~~~ In file included from /usr/include/x86_64-linux-gnu/bits/socket.h:27, from /usr/include/x86_64-linux-gnu/sys/socket.h:33, from ../lib/net/rte_ip.h:23, from ../lib/ethdev/rte_flow.h:24, from ../lib/ethdev/rte_eth_ctrl.h:11, from ../lib/ethdev/rte_ethdev.h:1419, from ../lib/ethdev/ethdev_driver.h:24, from ../drivers/net/iavf/iavf_rxtx_vec_common.h:8, from ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:5: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘iavf_rxq_rearm’: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:81:57: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 81 | const __m512i iova_offsets = _mm512_set1_epi64(offsetof | ^~~~~~~~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘iavf_vtx1’: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1900:48: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1900 | pkt->buf_iova + pkt->data_off); | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘iavf_vtx’: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1950:40: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1950 | pkt[3]->buf_iova + pkt[3]->data_off, | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1952:40: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1952 | pkt[2]->buf_iova + pkt[2]->data_off, | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1954:40: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1954 | pkt[1]->buf_iova + pkt[1]->data_off, | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1956:40: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1956 | pkt[0]->buf_iova + pkt[0]->data_off); | ^~ [923/2053] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_nvm.c.o [924/2053] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_controlq.c.o [925/2053] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_common.c.o [926/2053] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_common.c.o [927/2053] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_switch.c.o [928/2053] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_sched.c.o ninja: build stopped *Build Failed #20: OS: UB2204-64 Target: x86_64-native-linuxapp-clang FAILED: drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o clang -Idrivers/net/i40e/libi40e_avx512_lib.a.p -Idrivers/net/i40e -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/linux/include -I../lib/eal/linux/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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fcolor-diagnostics -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O3 -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-address-of-packed-member -Wno-missing-field-initializers -D_GNU_SOURCE -fPIC -march=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -DPF_DRIVER -DVF_DRIVER -DINTEGRATED_VF -DX722_A0_SUPPORT -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -MF drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o.d -o drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -c ../drivers/net/i40e/i40e_rxtx_vec_avx512.c In file included from ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:14: ../drivers/net/i40e/i40e_rxtx_common_avx.h:61:20: error: no member named 'buf_iova' in 'rte_mbuf' RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != ^ ~~~~~~~~ /usr/lib/llvm-14/lib/clang/14.0.0/include/stddef.h:104:24: note: expanded from macro 'offsetof' #define offsetof(t, d) __builtin_offsetof(t, d) ^ ~ ../lib/eal/include/rte_common.h:417:65: note: expanded from macro 'RTE_BUILD_BUG_ON' #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) ^~~~~~~~~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:76:4: error: no member named 'buf_iova' in 'rte_mbuf' (offsetof(struct rte_mbuf, buf_iova)); ^ ~~~~~~~~ /usr/lib/llvm-14/lib/clang/14.0.0/include/stddef.h:104:24: note: expanded from macro 'offsetof' #define offsetof(t, d) __builtin_offsetof(t, d) ^ ~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:997:10: error: no member named 'buf_iova' in 'struct rte_mbuf' pkt->buf_iova + pkt->data_off); ~~~ ^ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1028:21: error: no member named 'buf_iova' in 'struct rte_mbuf' (hi_qw3, pkt[3]->buf_iova + pkt[3]->data_off, ~~~~~~ ^ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1029:20: error: no member named 'buf_iova' in 'struct rte_mbuf' hi_qw2, pkt[2]->buf_iova + pkt[2]->data_off, ~~~~~~ ^ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1030:20: error: no member named 'buf_iova' in 'struct rte_mbuf' hi_qw1, pkt[1]->buf_iova + pkt[1]->data_off, ~~~~~~ ^ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1031:20: error: no member named 'buf_iova' in 'struct rte_mbuf' hi_qw0, pkt[0]->buf_iova + pkt[0]->data_off); ~~~~~~ ^ 7 errors generated. [923/2053] Compiling C object drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o FAILED: drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o clang -Idrivers/net/iavf/libiavf_avx512_lib.a.p -Idrivers/net/iavf -I../drivers/net/iavf -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/linux/include -I../lib/eal/linux/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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fcolor-diagnostics -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O3 -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-address-of-packed-member -Wno-missing-field-initializers -D_GNU_SOURCE -fPIC -march=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -Wno-strict-aliasing -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -MF drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o.d -o drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -c ../drivers/net/iavf/iavf_rxtx_vec_avx512.c In file included from ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:5: ../drivers/net/iavf/iavf_rxtx_vec_common.h:425:20: error: no member named 'buf_iova' in 'rte_mbuf' RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != ^ ~~~~~~~~ /usr/lib/llvm-14/lib/clang/14.0.0/include/stddef.h:104:24: note: expanded from macro 'offsetof' #define offsetof(t, d) __builtin_offsetof(t, d) ^ ~ ../lib/eal/include/rte_common.h:417:65: note: expanded from macro 'RTE_BUILD_BUG_ON' #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) ^~~~~~~~~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:81:50: error: no member named 'buf_iova' in 'rte_mbuf' const __m512i iova_offsets = _mm512_set1_epi64(offsetof ^ /usr/lib/llvm-14/lib/clang/14.0.0/include/stddef.h:104:24: note: expanded from macro 'offsetof' #define offsetof(t, d) __builtin_offsetof(t, d) ^ ~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1900:15: error: no member named 'buf_iova' in 'struct rte_mbuf' pkt->buf_iova + pkt->data_off); ~~~ ^ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1950:14: error: no member named 'buf_iova' in 'struct rte_mbuf' pkt[3]->buf_iova + pkt[3]->data_off, ~~~~~~ ^ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1952:14: error: no member named 'buf_iova' in 'struct rte_mbuf' pkt[2]->buf_iova + pkt[2]->data_off, ~~~~~~ ^ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1954:14: error: no member named 'buf_iova' in 'struct rte_mbuf' pkt[1]->buf_iova + pkt[1]->data_off, ~~~~~~ ^ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1956:14: error: no member named 'buf_iova' in 'struct rte_mbuf' pkt[0]->buf_iova + pkt[0]->data_off); ~~~~~~ ^ 7 errors generated. [924/2053] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_nvm.c.o [925/2053] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_controlq.c.o [926/2053] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_nvm.c.o [927/2053] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_common.c.o [928/2053] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_sched.c.o [929/2053] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_common.c.o [930/2053] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_flex_pipe.c.o [931/2053] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_switch.c.o ninja: build stopped *Build Failed #21: OS: UB2204-64 Target: x86_64-native-linuxapp-doc FAILED: drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o gcc -Idrivers/net/iavf/libiavf_avx512_lib.a.p -Idrivers/net/iavf -I../drivers/net/iavf -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/linux/include -I../lib/eal/linux/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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fdiagnostics-color=always -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O3 -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-address-of-packed-member -Wno-packed-not-aligned -Wno-missing-field-initializers -Wno-zero-length-bounds -D_GNU_SOURCE -fPIC -march=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -Wno-format-truncation -Wno-strict-aliasing -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -MF drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o.d -o drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -c ../drivers/net/iavf/iavf_rxtx_vec_avx512.c In file included from ../lib/eal/include/dev_driver.h:12, from ../lib/ethdev/ethdev_driver.h:22, from ../drivers/net/iavf/iavf_rxtx_vec_common.h:8, from ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:5: ../drivers/net/iavf/iavf_rxtx_vec_common.h: In function ‘iavf_rxq_rearm_common’: ../drivers/net/iavf/iavf_rxtx_vec_common.h:425:34: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 425 | RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != | ^~~~~~~~ ../lib/eal/include/rte_common.h:417:65: note: in definition of macro ‘RTE_BUILD_BUG_ON’ 417 | #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) | ^~~~~~~~~ In file included from /usr/include/x86_64-linux-gnu/bits/socket.h:27, from /usr/include/x86_64-linux-gnu/sys/socket.h:33, from ../lib/net/rte_ip.h:23, from ../lib/ethdev/rte_flow.h:24, from ../lib/ethdev/rte_eth_ctrl.h:11, from ../lib/ethdev/rte_ethdev.h:1419, from ../lib/ethdev/ethdev_driver.h:24, from ../drivers/net/iavf/iavf_rxtx_vec_common.h:8, from ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:5: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘iavf_rxq_rearm’: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:81:57: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 81 | const __m512i iova_offsets = _mm512_set1_epi64(offsetof | ^~~~~~~~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘iavf_vtx1’: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1900:48: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1900 | pkt->buf_iova + pkt->data_off); | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘iavf_vtx’: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1950:40: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1950 | pkt[3]->buf_iova + pkt[3]->data_off, | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1952:40: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1952 | pkt[2]->buf_iova + pkt[2]->data_off, | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1954:40: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1954 | pkt[1]->buf_iova + pkt[1]->data_off, | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1956:40: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1956 | pkt[0]->buf_iova + pkt[0]->data_off); | ^~ [922/1887] Compiling C object drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o FAILED: drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o gcc -Idrivers/net/i40e/libi40e_avx512_lib.a.p -Idrivers/net/i40e -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/linux/include -I../lib/eal/linux/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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fdiagnostics-color=always -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O3 -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-address-of-packed-member -Wno-packed-not-aligned -Wno-missing-field-initializers -Wno-zero-length-bounds -D_GNU_SOURCE -fPIC -march=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -Wno-format-truncation -DPF_DRIVER -DVF_DRIVER -DINTEGRATED_VF -DX722_A0_SUPPORT -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -MF drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o.d -o drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -c ../drivers/net/i40e/i40e_rxtx_vec_avx512.c In file included from ../lib/eal/include/dev_driver.h:12, from ../lib/ethdev/ethdev_driver.h:22, from ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:6: ../drivers/net/i40e/i40e_rxtx_common_avx.h: In function ‘i40e_rxq_rearm_common’: ../drivers/net/i40e/i40e_rxtx_common_avx.h:61:34: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 61 | RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != | ^~~~~~~~ ../lib/eal/include/rte_common.h:417:65: note: in definition of macro ‘RTE_BUILD_BUG_ON’ 417 | #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) | ^~~~~~~~~ In file included from /usr/include/x86_64-linux-gnu/bits/socket.h:27, from /usr/include/x86_64-linux-gnu/sys/socket.h:33, from ../lib/net/rte_ip.h:23, from ../lib/ethdev/rte_flow.h:24, from ../lib/ethdev/rte_eth_ctrl.h:11, from ../lib/ethdev/rte_ethdev.h:1419, from ../lib/ethdev/ethdev_driver.h:24, from ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:6: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘i40e_rxq_rearm’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:76:18: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 76 | (offsetof(struct rte_mbuf, buf_iova)); | ^~~~~~~~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘vtx1’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:997:36: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 997 | pkt->buf_iova + pkt->data_off); | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘vtx’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1028:40: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1028 | (hi_qw3, pkt[3]->buf_iova + pkt[3]->data_off, | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1029:39: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1029 | hi_qw2, pkt[2]->buf_iova + pkt[2]->data_off, | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1030:39: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1030 | hi_qw1, pkt[1]->buf_iova + pkt[1]->data_off, | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1031:39: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1031 | hi_qw0, pkt[0]->buf_iova + pkt[0]->data_off); | ^~ [923/1887] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_nvm.c.o [924/1887] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_nvm.c.o [925/1887] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_controlq.c.o [926/1887] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_common.c.o [927/1887] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_flex_pipe.c.o [928/1887] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_common.c.o [929/1887] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_sched.c.o [930/1887] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_switch.c.o ninja: build stopped *Build Failed #22: OS: CentOS79-64 Target: x86_64-native-linuxapp-gcc FAILED: kernel/linux/kni/rte_kni.ko /usr/bin/make -j4 -C /lib/modules/3.10.0-1160.76.1.el7.x86_64/build M=/root/CentOS79-64_K3.10.0_GCC4.8.5/x86_64-native-linuxapp-gcc/26028/dpdk/x86_64-native-linuxapp-gcc/kernel/linux/kni src=/root/CentOS79-64_K3.10.0_GCC4.8.5/x86_64-native-linuxapp-gcc/26028/dpdk/kernel/linux/kni 'MODULE_CFLAGS= -include /root/CentOS79-64_K3.10.0_GCC4.8.5/x86_64-native-linuxapp-gcc/26028/dpdk/config/rte_config.h -I/root/CentOS79-64_K3.10.0_GCC4.8.5/x86_64-native-linuxapp-gcc/26028/dpdk/lib/eal/include -I/root/CentOS79-64_K3.10.0_GCC4.8.5/x86_64-native-linuxapp-gcc/26028/dpdk/lib/kni -I/root/CentOS79-64_K3.10.0_GCC4.8.5/x86_64-native-linuxapp-gcc/26028/dpdk/x86_64-native-linuxapp-gcc -I/root/CentOS79-64_K3.10.0_GCC4.8.5/x86_64-native-linuxapp-gcc/26028/dpdk/kernel/linux/kni' modules make: Entering directory `/usr/src/kernels/3.10.0-1160.76.1.el7.x86_64' CC [M] /root/CentOS79-64_K3.10.0_GCC4.8.5/x86_64-native-linuxapp-gcc/26028/dpdk/x86_64-native-linuxapp-gcc/kernel/linux/kni/kni_net.o CC [M] /root/CentOS79-64_K3.10.0_GCC4.8.5/x86_64-native-linuxapp-gcc/26028/dpdk/x86_64-native-linuxapp-gcc/kernel/linux/kni/kni_misc.o /root/CentOS79-64_K3.10.0_GCC4.8.5/x86_64-native-linuxapp-gcc/26028/dpdk/kernel/linux/kni/kni_net.c: In function 'pa2va': /root/CentOS79-64_K3.10.0_GCC4.8.5/x86_64-native-linuxapp-gcc/26028/dpdk/kernel/linux/kni/kni_net.c:71:20: error: 'struct rte_kni_mbuf' has no member named 'buf_iova' (unsigned long)m->buf_iova); ^ /root/CentOS79-64_K3.10.0_GCC4.8.5/x86_64-native-linuxapp-gcc/26028/dpdk/kernel/linux/kni/kni_net.c: In function 'kva2data_kva': /root/CentOS79-64_K3.10.0_GCC4.8.5/x86_64-native-linuxapp-gcc/26028/dpdk/kernel/linux/kni/kni_net.c:79:23: error: 'struct rte_kni_mbuf' has no member named 'buf_iova' return phys_to_virt(m->buf_iova + m->data_off); ^ /root/CentOS79-64_K3.10.0_GCC4.8.5/x86_64-native-linuxapp-gcc/26028/dpdk/kernel/linux/kni/kni_net.c:80:1: warning: control reaches end of non-void function [-Wreturn-type] } ^ make[1]: *** [/root/CentOS79-64_K3.10.0_GCC4.8.5/x86_64-native-linuxapp-gcc/26028/dpdk/x86_64-native-linuxapp-gcc/kernel/linux/kni/kni_net.o] Error 1 make[1]: *** Waiting for unfinished jobs.... make: *** [_module_/root/CentOS79-64_K3.10.0_GCC4.8.5/x86_64-native-linuxapp-gcc/26028/dpdk/x86_64-native-linuxapp-gcc/kernel/linux/kni] Error 2 make: Leaving directory `/usr/src/kernels/3.10.0-1160.76.1.el7.x86_64' [1718/2037] Linking target app/dpdk-test-bbdev [1719/2037] Linking target app/dpdk-proc-info [1720/2037] Linking target app/dpdk-test-acl [1721/2037] Linking target app/dpdk-test-cmdline [1722/2037] Linking target app/dpdk-test-crypto-perf [1723/2037] Linking target app/dpdk-test-compress-perf [1724/2037] Linking target app/dpdk-test-eventdev [1725/2037] Linking target app/dpdk-test-fib [1726/2037] Linking target app/dpdk-test-gpudev ninja: build stopped *Build Failed #23: OS: RHEL86-64Rt Target: x86_64-native-linuxapp-gcc FAILED: drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o gcc -Idrivers/net/i40e/libi40e_avx512_lib.a.p -Idrivers/net/i40e -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/linux/include -I../lib/eal/linux/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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fdiagnostics-color=always -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O3 -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-packed-not-aligned -Wno-missing-field-initializers -D_GNU_SOURCE -fPIC -march=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -Wno-format-truncation -DPF_DRIVER -DVF_DRIVER -DINTEGRATED_VF -DX722_A0_SUPPORT -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -MF drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o.d -o drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -c ../drivers/net/i40e/i40e_rxtx_vec_avx512.c In file included from ../lib/eal/include/dev_driver.h:12, from ../lib/ethdev/ethdev_driver.h:22, from ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:6: ../drivers/net/i40e/i40e_rxtx_common_avx.h: In function ‘i40e_rxq_rearm_common’: ../drivers/net/i40e/i40e_rxtx_common_avx.h:61:46: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != ^~~~~~~~ ../lib/eal/include/rte_common.h:417:65: note: in definition of macro ‘RTE_BUILD_BUG_ON’ #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) ^~~~~~~~~ In file included from /usr/include/bits/socket.h:27, from /usr/include/sys/socket.h:33, from ../lib/net/rte_ip.h:23, from ../lib/ethdev/rte_flow.h:24, from ../lib/ethdev/rte_eth_ctrl.h:11, from ../lib/ethdev/rte_ethdev.h:1419, from ../lib/ethdev/ethdev_driver.h:24, from ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:6: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘i40e_rxq_rearm’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:76:30: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? (offsetof(struct rte_mbuf, buf_iova)); ^~~~~~~~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘vtx1’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:997:10: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? pkt->buf_iova + pkt->data_off); ^~~~~~~~ buf_addr ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘vtx’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1028:21: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? (hi_qw3, pkt[3]->buf_iova + pkt[3]->data_off, ^~~~~~~~ buf_addr ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1029:20: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? hi_qw2, pkt[2]->buf_iova + pkt[2]->data_off, ^~~~~~~~ buf_addr ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1030:20: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? hi_qw1, pkt[1]->buf_iova + pkt[1]->data_off, ^~~~~~~~ buf_addr ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1031:20: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? hi_qw0, pkt[0]->buf_iova + pkt[0]->data_off); ^~~~~~~~ buf_addr [922/2036] Compiling C object drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o FAILED: drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o gcc -Idrivers/net/iavf/libiavf_avx512_lib.a.p -Idrivers/net/iavf -I../drivers/net/iavf -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/linux/include -I../lib/eal/linux/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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fdiagnostics-color=always -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O3 -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-packed-not-aligned -Wno-missing-field-initializers -D_GNU_SOURCE -fPIC -march=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -Wno-format-truncation -Wno-strict-aliasing -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -MF drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o.d -o drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -c ../drivers/net/iavf/iavf_rxtx_vec_avx512.c In file included from ../lib/eal/include/dev_driver.h:12, from ../lib/ethdev/ethdev_driver.h:22, from ../drivers/net/iavf/iavf_rxtx_vec_common.h:8, from ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:5: ../drivers/net/iavf/iavf_rxtx_vec_common.h: In function ‘iavf_rxq_rearm_common’: ../drivers/net/iavf/iavf_rxtx_vec_common.h:425:46: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != ^~~~~~~~ ../lib/eal/include/rte_common.h:417:65: note: in definition of macro ‘RTE_BUILD_BUG_ON’ #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) ^~~~~~~~~ In file included from /usr/include/bits/socket.h:27, from /usr/include/sys/socket.h:33, from ../lib/net/rte_ip.h:23, from ../lib/ethdev/rte_flow.h:24, from ../lib/ethdev/rte_eth_ctrl.h:11, from ../lib/ethdev/rte_ethdev.h:1419, from ../lib/ethdev/ethdev_driver.h:24, from ../drivers/net/iavf/iavf_rxtx_vec_common.h:8, from ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:5: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘iavf_rxq_rearm’: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:82:26: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? (struct rte_mbuf, buf_iova)); ^~~~~~~~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘iavf_vtx1’: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1900:15: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? pkt->buf_iova + pkt->data_off); ^~~~~~~~ buf_addr ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘iavf_vtx’: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1950:14: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? pkt[3]->buf_iova + pkt[3]->data_off, ^~~~~~~~ buf_addr ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1952:14: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? pkt[2]->buf_iova + pkt[2]->data_off, ^~~~~~~~ buf_addr ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1954:14: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? pkt[1]->buf_iova + pkt[1]->data_off, ^~~~~~~~ buf_addr ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1956:14: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’; did you mean ‘buf_addr’? pkt[0]->buf_iova + pkt[0]->data_off); ^~~~~~~~ buf_addr [923/2036] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_lan_hmc.c.o [924/2036] Generating symbol file drivers/librte_net_cnxk.so.23.1.p/librte_net_cnxk.so.23.1.symbols [925/2036] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_nvm.c.o [926/2036] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_controlq.c.o [927/2036] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_common.c.o [928/2036] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_sched.c.o [929/2036] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_common.c.o [930/2036] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_switch.c.o ninja: build stopped *Build Failed #24: OS: UB2210-64 Target: x86_64-native-linuxapp-gcc FAILED: drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o gcc -Idrivers/net/i40e/libi40e_avx512_lib.a.p -Idrivers/net/i40e -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/linux/include -I../lib/eal/linux/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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fdiagnostics-color=always -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O3 -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-address-of-packed-member -Wno-packed-not-aligned -Wno-missing-field-initializers -Wno-zero-length-bounds -D_GNU_SOURCE -fPIC -march=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -Wno-format-truncation -DPF_DRIVER -DVF_DRIVER -DINTEGRATED_VF -DX722_A0_SUPPORT -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -MF drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o.d -o drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -c ../drivers/net/i40e/i40e_rxtx_vec_avx512.c In file included from ../lib/eal/include/dev_driver.h:12, from ../lib/ethdev/ethdev_driver.h:22, from ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:6: ../drivers/net/i40e/i40e_rxtx_common_avx.h: In function ‘i40e_rxq_rearm_common’: ../drivers/net/i40e/i40e_rxtx_common_avx.h:61:34: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 61 | RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != | ^~~~~~~~ ../lib/eal/include/rte_common.h:417:65: note: in definition of macro ‘RTE_BUILD_BUG_ON’ 417 | #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) | ^~~~~~~~~ In file included from /usr/include/x86_64-linux-gnu/bits/socket.h:27, from /usr/include/x86_64-linux-gnu/sys/socket.h:33, from ../lib/net/rte_ip.h:23, from ../lib/ethdev/rte_flow.h:24, from ../lib/ethdev/rte_eth_ctrl.h:11, from ../lib/ethdev/rte_ethdev.h:1419, from ../lib/ethdev/ethdev_driver.h:24: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘i40e_rxq_rearm’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:76:18: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 76 | (offsetof(struct rte_mbuf, buf_iova)); | ^~~~~~~~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘vtx1’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:997:36: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 997 | pkt->buf_iova + pkt->data_off); | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘vtx’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1028:40: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1028 | (hi_qw3, pkt[3]->buf_iova + pkt[3]->data_off, | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1029:39: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1029 | hi_qw2, pkt[2]->buf_iova + pkt[2]->data_off, | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1030:39: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1030 | hi_qw1, pkt[1]->buf_iova + pkt[1]->data_off, | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1031:39: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1031 | hi_qw0, pkt[0]->buf_iova + pkt[0]->data_off); | ^~ [910/2053] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_lan_hmc.c.o [911/2053] Compiling C object drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o FAILED: drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o gcc -Idrivers/net/iavf/libiavf_avx512_lib.a.p -Idrivers/net/iavf -I../drivers/net/iavf -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/linux/include -I../lib/eal/linux/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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fdiagnostics-color=always -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O3 -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-address-of-packed-member -Wno-packed-not-aligned -Wno-missing-field-initializers -Wno-zero-length-bounds -D_GNU_SOURCE -fPIC -march=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -Wno-format-truncation -Wno-strict-aliasing -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -MF drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o.d -o drivers/net/iavf/libiavf_avx512_lib.a.p/iavf_rxtx_vec_avx512.c.o -c ../drivers/net/iavf/iavf_rxtx_vec_avx512.c In file included from ../lib/eal/include/dev_driver.h:12, from ../lib/ethdev/ethdev_driver.h:22, from ../drivers/net/iavf/iavf_rxtx_vec_common.h:8, from ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:5: ../drivers/net/iavf/iavf_rxtx_vec_common.h: In function ‘iavf_rxq_rearm_common’: ../drivers/net/iavf/iavf_rxtx_vec_common.h:425:34: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 425 | RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != | ^~~~~~~~ ../lib/eal/include/rte_common.h:417:65: note: in definition of macro ‘RTE_BUILD_BUG_ON’ 417 | #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) | ^~~~~~~~~ In file included from /usr/include/x86_64-linux-gnu/bits/socket.h:27, from /usr/include/x86_64-linux-gnu/sys/socket.h:33, from ../lib/net/rte_ip.h:23, from ../lib/ethdev/rte_flow.h:24, from ../lib/ethdev/rte_eth_ctrl.h:11, from ../lib/ethdev/rte_ethdev.h:1419, from ../lib/ethdev/ethdev_driver.h:24: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘iavf_rxq_rearm’: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:81:57: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 81 | const __m512i iova_offsets = _mm512_set1_epi64(offsetof | ^~~~~~~~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘iavf_vtx1’: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1900:48: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1900 | pkt->buf_iova + pkt->data_off); | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c: In function ‘iavf_vtx’: ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1950:40: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1950 | pkt[3]->buf_iova + pkt[3]->data_off, | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1952:40: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1952 | pkt[2]->buf_iova + pkt[2]->data_off, | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1954:40: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1954 | pkt[1]->buf_iova + pkt[1]->data_off, | ^~ ../drivers/net/iavf/iavf_rxtx_vec_avx512.c:1956:40: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1956 | pkt[0]->buf_iova + pkt[0]->data_off); | ^~ [912/2053] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_nvm.c.o [913/2053] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_controlq.c.o [914/2053] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_nvm.c.o [915/2053] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_common.c.o [916/2053] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_common.c.o [917/2053] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_sched.c.o [918/2053] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_switch.c.o ninja: build stopped *Build Failed #25: OS: FC37-64 Target: x86_64-native-linuxapp-gcc FAILED: drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o gcc -Idrivers/net/i40e/libi40e_avx512_lib.a.p -Idrivers/net/i40e -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/linux/include -I../lib/eal/linux/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 -Ilib/hash -I../lib/hash -Ilib/rcu -I../lib/rcu -fdiagnostics-color=always -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -Werror -O3 -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissing-declarations -Wmissing-prototypes -Wnested-externs -Wold-style-definition -Wpointer-arith -Wsign-compare -Wstrict-prototypes -Wundef -Wwrite-strings -Wno-address-of-packed-member -Wno-packed-not-aligned -Wno-missing-field-initializers -Wno-zero-length-bounds -D_GNU_SOURCE -fPIC -march=native -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -Wno-format-truncation -DPF_DRIVER -DVF_DRIVER -DINTEGRATED_VF -DX722_A0_SUPPORT -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -mavx512f -mavx512bw -march=skylake-avx512 -MD -MQ drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -MF drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o.d -o drivers/net/i40e/libi40e_avx512_lib.a.p/i40e_rxtx_vec_avx512.c.o -c ../drivers/net/i40e/i40e_rxtx_vec_avx512.c In file included from ../lib/eal/include/dev_driver.h:12, from ../lib/ethdev/ethdev_driver.h:22, from ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:6: ../drivers/net/i40e/i40e_rxtx_common_avx.h: In function ‘i40e_rxq_rearm_common’: ../drivers/net/i40e/i40e_rxtx_common_avx.h:61:34: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 61 | RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, buf_iova) != | ^~~~~~~~ ../lib/eal/include/rte_common.h:417:65: note: in definition of macro ‘RTE_BUILD_BUG_ON’ 417 | #define RTE_BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)])) | ^~~~~~~~~ In file included from /usr/include/bits/socket.h:27, from /usr/include/sys/socket.h:33, from ../lib/net/rte_ip.h:23, from ../lib/ethdev/rte_flow.h:24, from ../lib/ethdev/rte_eth_ctrl.h:11, from ../lib/ethdev/rte_ethdev.h:1419, from ../lib/ethdev/ethdev_driver.h:24: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘i40e_rxq_rearm’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:76:18: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 76 | (offsetof(struct rte_mbuf, buf_iova)); | ^~~~~~~~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘vtx1’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:997:36: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 997 | pkt->buf_iova + pkt->data_off); | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c: In function ‘vtx’: ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1028:40: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1028 | (hi_qw3, pkt[3]->buf_iova + pkt[3]->data_off, | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1029:39: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1029 | hi_qw2, pkt[2]->buf_iova + pkt[2]->data_off, | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1030:39: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1030 | hi_qw1, pkt[1]->buf_iova + pkt[1]->data_off, | ^~ ../drivers/net/i40e/i40e_rxtx_vec_avx512.c:1031:39: error: ‘struct rte_mbuf’ has no member named ‘buf_iova’ 1031 | hi_qw0, pkt[0]->buf_iova + pkt[0]->data_off); | ^~ [904/2036] Compiling C object drivers/libtmp_rte_net_failsafe.a.p/net_failsafe_failsafe_ops.c.o [905/2036] Compiling C object drivers/net/hinic/base/libhinic_base.a.p/hinic_pmd_wq.c.o [906/2036] Compiling C object drivers/net/hinic/base/libhinic_base.a.p/hinic_pmd_nicio.c.o [907/2036] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_diag.c.o [908/2036] Compiling C object drivers/net/hinic/base/libhinic_base.a.p/hinic_pmd_mbox.c.o [909/2036] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_dcb.c.o [910/2036] Compiling C object drivers/net/hinic/base/libhinic_base.a.p/hinic_pmd_niccfg.c.o [911/2036] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_hmc.c.o [912/2036] Compiling C object drivers/net/i40e/base/libi40e_base.a.p/i40e_common.c.o ninja: build stopped DPDK STV team