From: sys_stv@intel.com
To: test-report@dpdk.org, yuanx.wang@intel.com
Subject: [dpdk-test-report] |FAILURE| pw(114905) sid(24291) job(PER_PATCH_BUILD3818)[4/4] net/ice: support buffer split in Rx path
Date: 12 Aug 2022 03:55:03 -0700 [thread overview]
Message-ID: <11ab82$jqu0nh@fmsmga008-auth.fm.intel.com> (raw)
[-- Attachment #1: Type: text/plain, Size: 15393 bytes --]
Test-Label: Intel-compilation
Test-Status: FAILURE
http://dpdk.org/patch/114905
_Compilation issues_
Submitter: Yuan Wang <yuanx.wang@intel.com>
Date: 2022-08-12 18:15:52
Reply_mail: <20220812181552.2908067-5-yuanx.wang@intel.com>
DPDK git baseline: Repo:dpdk-next-net, CommitID: 72206323a5dd3182b13f61b25a64abdddfee595c
Meson Build Summary: 22 Builds Done, 21 Successful, 1 Failures, 0 Blocked
+--------------+------------+--------------+------------+------------+-----------+----------+------------+
| os | gcc-static | clang-static | icc-static | gcc-shared | gcc-debug | document | gcc-16byte |
+--------------+------------+--------------+------------+------------+-----------+----------+------------+
| FC36-64 | fail | pass | | | | | |
| FreeBSD13-64 | pass | pass | | pass | pass | | |
| RHEL86-64 | pass | pass | | pass | pass | | |
| SUSE15-64 | pass | pass | | | | | |
| UB2004-32 | pass | | | | | | |
| UB2004-64 | pass | pass | | | | pass | |
| UB2204-32 | pass | | | | | | |
| UB2204-64 | pass | pass | | | | pass | pass |
| CentOS79-64 | pass | | | | | | |
+--------------+------------+--------------+------------+------------+-----------+----------+------------+
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.3.18-57-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: UB2004-32
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
i686-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.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
*Build Failed #1:
OS: FC36-64
Target: x86_64-native-linuxapp-gcc
FAILED: drivers/libtmp_rte_net_ice.a.p/net_ice_ice_rxtx.c.o
gcc -Idrivers/libtmp_rte_net_ice.a.p -Idrivers -I../drivers -Idrivers/net/ice -I../drivers/net/ice -Idrivers/net/ice/base -I../drivers/net/ice/base -Idrivers/common/iavf -I../drivers/common/iavf -Ilib/ethdev -I../lib/ethdev -I. -I.. -Iconfig -I../config -Ilib/eal/include -I../lib/eal/include -Ilib/eal/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 -Idrivers/bus/pci -I../drivers/bus/pci -I../drivers/bus/pci/linux -Ilib/pci -I../lib/pci -Idrivers/bus/vdev -I../drivers/bus/vdev -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 -DCC_AVX2_SUPPORT -DCC_AVX512_SUPPORT -DRTE_LOG_DEFAULT_LOGTYPE=pmd.net.ice -MD -MQ drivers/libtmp_rte_net_ice.a.p/net_ice_ice_rxtx.c.o -MF drivers/libtmp_rte_net_ice.a.p/net_ice_ice_rxtx.c.o.d -o drivers/libtmp_rte_net_ice.a.p/net_ice_ice_rxtx.c.o -c ../drivers/net/ice/ice_rxtx.c
In file included from /usr/lib/gcc/x86_64-redhat-linux/12/include/immintrin.h:43,
from /usr/lib/gcc/x86_64-redhat-linux/12/include/x86intrin.h:32,
from ../lib/eal/x86/include/rte_vect.h:31,
from ../lib/eal/x86/include/rte_memcpy.h:17,
from ../lib/mempool/rte_mempool.h:46,
from ../lib/mbuf/rte_mbuf.h:38,
from ../lib/net/rte_ether.h:22,
from ../lib/ethdev/rte_eth_ctrl.h:10,
from ../lib/ethdev/rte_ethdev.h:1508,
from ../lib/ethdev/ethdev_driver.h:22,
from ../drivers/net/ice/ice_rxtx.c:5:
In function ‘_mm256_storeu_si256’,
inlined from ‘rte_mov32’ at ../lib/eal/x86/include/rte_memcpy.h:347:2,
inlined from ‘rte_mov128’ at ../lib/eal/x86/include/rte_memcpy.h:370:2,
inlined from ‘rte_memcpy_generic’ at ../lib/eal/x86/include/rte_memcpy.h:445:4,
inlined from ‘rte_memcpy’ at ../lib/eal/x86/include/rte_memcpy.h:851:10,
inlined from ‘ice_rx_queue_setup’ at ../drivers/net/ice/ice_rxtx.c:1186:3:
/usr/lib/gcc/x86_64-redhat-linux/12/include/avxintrin.h:935:8: error: array subscript 28 is outside array bounds of ‘struct ice_rx_queue[1]’ [-Werror=array-bounds]
935 | *__P = __A;
| ~~~~~^~~~~
../drivers/net/ice/ice_rxtx.c: In function ‘ice_rx_queue_setup’:
../drivers/net/ice/ice_rxtx.c:1173:15: note: at offset 896 into object of size 896 allocated by ‘rte_zmalloc_socket’
1173 | rxq = rte_zmalloc_socket(NULL,
| ^~~~~~~~~~~~~~~~~~~~~~~~
1174 | sizeof(struct ice_rx_queue),
| ~~~~~~~~~~~~~~~~~~~~~~~~~~~~
1175 | RTE_CACHE_LINE_SIZE,
| ~~~~~~~~~~~~~~~~~~~~
1176 | socket_id);
| ~~~~~~~~~~
In function ‘_mm256_storeu_si256’,
inlined from ‘rte_mov32’ at ../lib/eal/x86/include/rte_memcpy.h:347:2,
inlined from ‘rte_mov128’ at ../lib/eal/x86/include/rte_memcpy.h:371:2,
inlined from ‘rte_memcpy_generic’ at ../lib/eal/x86/include/rte_memcpy.h:445:4,
inlined from ‘rte_memcpy’ at ../lib/eal/x86/include/rte_memcpy.h:851:10,
inlined from ‘ice_rx_queue_setup’ at ../drivers/net/ice/ice_rxtx.c:1186:3:
/usr/lib/gcc/x86_64-redhat-linux/12/include/avxintrin.h:935:8: error: array subscript 29 is outside array bounds of ‘struct ice_rx_queue[1]’ [-Werror=array-bounds]
935 | *__P = __A;
| ~~~~~^~~~~
../drivers/net/ice/ice_rxtx.c: In function ‘ice_rx_queue_setup’:
../drivers/net/ice/ice_rxtx.c:1173:15: note: at offset 928 into object of size 896 allocated by ‘rte_zmalloc_socket’
1173 | rxq = rte_zmalloc_socket(NULL,
| ^~~~~~~~~~~~~~~~~~~~~~~~
1174 | sizeof(struct ice_rx_queue),
| ~~~~~~~~~~~~~~~~~~~~~~~~~~~~
1175 | RTE_CACHE_LINE_SIZE,
| ~~~~~~~~~~~~~~~~~~~~
1176 | socket_id);
| ~~~~~~~~~~
In function ‘_mm256_storeu_si256’,
inlined from ‘rte_mov32’ at ../lib/eal/x86/include/rte_memcpy.h:347:2,
inlined from ‘rte_memcpy_generic’ at ../lib/eal/x86/include/rte_memcpy.h:457:4,
inlined from ‘rte_memcpy’ at ../lib/eal/x86/include/rte_memcpy.h:851:10,
inlined from ‘ice_rx_queue_setup’ at ../drivers/net/ice/ice_rxtx.c:1186:3:
/usr/lib/gcc/x86_64-redhat-linux/12/include/avxintrin.h:935:8: error: array subscript 28 is outside array bounds of ‘void[896]’ [-Werror=array-bounds]
935 | *__P = __A;
| ~~~~~^~~~~
In file included from ../drivers/net/ice/ice_rxtx.c:10:
../drivers/net/ice/ice_rxtx.h: In function ‘ice_rx_queue_setup’:
../drivers/net/ice/ice_rxtx.h:115:36: note: at offset [832, 896] into object ‘rxseg’ of size 32
115 | struct rte_eth_rxseg_split rxseg[ICE_RX_MAX_NSEG];
| ^~~~~
../drivers/net/ice/ice_rxtx.h:115:36: note: at offset [833, 927] into object ‘rxseg’ of size 32
../drivers/net/ice/ice_rxtx.c:1173:15: note: at offset [1792, 1856] into object of size 896 allocated by ‘rte_zmalloc_socket’
1173 | rxq = rte_zmalloc_socket(NULL,
| ^~~~~~~~~~~~~~~~~~~~~~~~
1174 | sizeof(struct ice_rx_queue),
| ~~~~~~~~~~~~~~~~~~~~~~~~~~~~
1175 | RTE_CACHE_LINE_SIZE,
| ~~~~~~~~~~~~~~~~~~~~
1176 | socket_id);
| ~~~~~~~~~~
../drivers/net/ice/ice_rxtx.h:115:36: note: at offset [832, 896] into object ‘rxseg’ of size 32
115 | struct rte_eth_rxseg_split rxseg[ICE_RX_MAX_NSEG];
| ^~~~~
../drivers/net/ice/ice_rxtx.h:115:36: note: at offset [833, 927] into object ‘rxseg’ of size 32
../drivers/net/ice/ice_rxtx.c:1173:15: note: at offset [1792, 1856] into object of size 896 allocated by ‘rte_zmalloc_socket’
1173 | rxq = rte_zmalloc_socket(NULL,
| ^~~~~~~~~~~~~~~~~~~~~~~~
1174 | sizeof(struct ice_rx_queue),
| ~~~~~~~~~~~~~~~~~~~~~~~~~~~~
1175 | RTE_CACHE_LINE_SIZE,
| ~~~~~~~~~~~~~~~~~~~~
1176 | socket_id);
| ~~~~~~~~~~
../drivers/net/ice/ice_rxtx.h:115:36: note: at offset [832, 896] into object ‘rxseg’ of size 32
115 | struct rte_eth_rxseg_split rxseg[ICE_RX_MAX_NSEG];
| ^~~~~
In function ‘_mm256_storeu_si256’,
inlined from ‘rte_mov32’ at ../lib/eal/x86/include/rte_memcpy.h:347:2,
inlined from ‘rte_memcpy_generic’ at ../lib/eal/x86/include/rte_memcpy.h:458:4,
inlined from ‘rte_memcpy’ at ../lib/eal/x86/include/rte_memcpy.h:851:10,
inlined from ‘ice_rx_queue_setup’ at ../drivers/net/ice/ice_rxtx.c:1186:3:
/usr/lib/gcc/x86_64-redhat-linux/12/include/avxintrin.h:935:8: error: array subscript [28, 32795] is outside array bounds of ‘void[896]’ [-Werror=array-bounds]
935 | *__P = __A;
| ~~~~~^~~~~
../drivers/net/ice/ice_rxtx.h: In function ‘ice_rx_queue_setup’:
../drivers/net/ice/ice_rxtx.h:115:36: note: at offset [833, 897] into object ‘rxseg’ of size 32
115 | struct rte_eth_rxseg_split rxseg[ICE_RX_MAX_NSEG];
| ^~~~~
../drivers/net/ice/ice_rxtx.h:115:36: note: at offset [834, 928] into object ‘rxseg’ of size 32
../drivers/net/ice/ice_rxtx.c:1173:15: note: at offset [1793, 1857] into object of size 896 allocated by ‘rte_zmalloc_socket’
1173 | rxq = rte_zmalloc_socket(NULL,
| ^~~~~~~~~~~~~~~~~~~~~~~~
1174 | sizeof(struct ice_rx_queue),
| ~~~~~~~~~~~~~~~~~~~~~~~~~~~~
1175 | RTE_CACHE_LINE_SIZE,
| ~~~~~~~~~~~~~~~~~~~~
1176 | socket_id);
| ~~~~~~~~~~
../drivers/net/ice/ice_rxtx.h:115:36: note: at offset [833, 897] into object ‘rxseg’ of size 32
115 | struct rte_eth_rxseg_split rxseg[ICE_RX_MAX_NSEG];
| ^~~~~
../drivers/net/ice/ice_rxtx.h:115:36: note: at offset [834, 928] into object ‘rxseg’ of size 32
../drivers/net/ice/ice_rxtx.c:1173:15: note: at offset [1793, 1857] into object of size 896 allocated by ‘rte_zmalloc_socket’
1173 | rxq = rte_zmalloc_socket(NULL,
| ^~~~~~~~~~~~~~~~~~~~~~~~
1174 | sizeof(struct ice_rx_queue),
| ~~~~~~~~~~~~~~~~~~~~~~~~~~~~
1175 | RTE_CACHE_LINE_SIZE,
| ~~~~~~~~~~~~~~~~~~~~
1176 | socket_id);
| ~~~~~~~~~~
../drivers/net/ice/ice_rxtx.h:115:36: note: at offset [833, 897] into object ‘rxseg’ of size 32
115 | struct rte_eth_rxseg_split rxseg[ICE_RX_MAX_NSEG];
| ^~~~~
cc1: all warnings being treated as errors
[1801/3598] Compiling C object drivers/libtmp_rte_net_igc.a.p/net_igc_igc_flow.c.o
[1802/3598] Compiling C object drivers/libtmp_rte_net_ionic.a.p/net_ionic_ionic_ethdev.c.o
[1803/3598] Compiling C object drivers/libtmp_rte_net_ice.a.p/net_ice_ice_rxtx_vec_avx2.c.o
[1804/3598] Compiling C object drivers/libtmp_rte_net_igc.a.p/net_igc_igc_ethdev.c.o
[1805/3598] Compiling C object drivers/libtmp_rte_net_igc.a.p/net_igc_igc_filter.c.o
[1806/3598] Compiling C object drivers/libtmp_rte_net_ionic.a.p/net_ionic_ionic_rx_filter.c.o
[1807/3598] Compiling C object drivers/libtmp_rte_net_ionic.a.p/net_ionic_ionic_lif.c.o
[1808/3598] Compiling C object drivers/libtmp_rte_net_igc.a.p/net_igc_igc_txrx.c.o
[1809/3598] Compiling C object drivers/libtmp_rte_net_ionic.a.p/net_ionic_ionic_main.c.o
ninja: build stopped
DPDK STV team
reply other threads:[~2022-08-12 10:55 UTC|newest]
Thread overview: [no followups] expand[flat|nested] mbox.gz Atom feed
Reply instructions:
You may reply publicly to this message via plain-text email
using any one of the following methods:
* Save the following mbox file, import it into your mail client,
and reply-to-all from there: mbox
Avoid top-posting and favor interleaved quoting:
https://en.wikipedia.org/wiki/Posting_style#Interleaved_style
* Reply using the --to, --cc, and --in-reply-to
switches of git-send-email(1):
git send-email \
--in-reply-to='11ab82$jqu0nh@fmsmga008-auth.fm.intel.com' \
--to=sys_stv@intel.com \
--cc=test-report@dpdk.org \
--cc=yuanx.wang@intel.com \
/path/to/YOUR_REPLY
https://kernel.org/pub/software/scm/git/docs/git-send-email.html
* If your mail client supports setting the In-Reply-To header
via mailto: links, try the mailto: link
Be sure your reply has a Subject: header at the top and a blank line
before the message body.
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).