* [dpdk-test-report] |FAILURE| pw(120522) sid(26028) job(PER_PATCH_BUILD5609)[v11] mbuf perf test, please ignore
@ 2022-12-07 14:30 sys_stv
0 siblings, 0 replies; only message in thread
From: sys_stv @ 2022-12-07 14:30 UTC (permalink / raw)
To: test-report, mb
[-- Attachment #1: Type: text/plain, Size: 232680 bytes --]
Test-Label: Intel-compilation
Test-Status: FAILURE
http://dpdk.org/patch/120522
_Compilation issues_
Submitter: Morten Brørup <mb@smartsharesystems.com>
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
^ permalink raw reply [flat|nested] only message in thread
only message in thread, other threads:[~2022-12-07 14:31 UTC | newest]
Thread overview: (only message) (download: mbox.gz / follow: Atom feed)
-- links below jump to the message on this page --
2022-12-07 14:30 [dpdk-test-report] |FAILURE| pw(120522) sid(26028) job(PER_PATCH_BUILD5609)[v11] mbuf perf test, please ignore sys_stv
This is a public inbox, see mirroring instructions
for how to clone and mirror all data and code used for this inbox;
as well as URLs for NNTP newsgroup(s).