* |FAILURE| pw147707 [PATCH v1] net/macb: add new driver
[not found] <1730267479-473022-1-git-send-email-liwencheng@phytium.com.cn>
@ 2024-10-30 5:26 ` qemudev
2024-10-30 5:52 ` |WARNING| " checkpatch
2024-10-30 6:10 ` |FAILURE| pw147707 [PATCH] [v1] " dpdklab
2 siblings, 0 replies; 3+ messages in thread
From: qemudev @ 2024-10-30 5:26 UTC (permalink / raw)
To: test-report; +Cc: liwencheng, zhoumin
Test-Label: loongarch-compilation
Test-Status: FAILURE
http://dpdk.org/patch/147707
_ninja build failure_
Submitter: liwencheng <liwencheng@phytium.com.cn>
Date: Wed, 30 Oct 2024 05:51:19 +0000
DPDK git baseline: Repo:dpdk
Branch: main
CommitID: 6dad0bb5c8621644beca86ff5f4910a943ba604d
147707 --> ninja build failed
Test environment and result as below:
+---------------------+----------------+
| Environment | compilation |
+---------------------+----------------+
| Loongnix-Server 8.3 | FAIL |
+---------------------+----------------+
Loongnix-Server 8.3
Kernel: 4.19.190+
Compiler: gcc 8.3
Ninja build logs:
-------------------------------BEGIN LOGS----------------------------
FAILED: drivers/libtmp_rte_net_macb.a.p/net_macb_macb_rxtx_vec_neon.c.o
cc -Idrivers/libtmp_rte_net_macb.a.p -Idrivers -I../drivers -Idrivers/net/macb -I../drivers/net/macb -Idrivers/net/macb/base -I../drivers/net/macb/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/loongarch/include -I../lib/eal/loongarch/include -Ilib/eal/common -I../lib/eal/common -Ilib/eal -I../lib/eal -Ilib/kvargs -I../lib/kvargs -Ilib/log -I../lib/log -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 -fdiagnostics-color=always -pipe -D_FILE_OFFSET_BITS=64 -Wall -Winvalid-pch -Wextra -std=c11 -O3 -include rte_config.h -Wcast-qual -Wdeprecated -Wformat -Wformat-nonliteral -Wformat-security -Wmissin
g-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=loongarch64 -DALLOW_EXPERIMENTAL_API -DALLOW_INTERNAL_API -Wno-format-truncation -DRTE_LOG_DEFAULT_LOGTYPE=pmd.net.macb -MD -MQ drivers/libtmp_rte_net_macb.a.p/net_macb_macb_rxtx_vec_neon.c.o -MF drivers/libtmp_rte_net_macb.a.p/net_macb_macb_rxtx_vec_neon.c.o.d -o drivers/libtmp_rte_net_macb.a.p/net_macb_macb_rxtx_vec_neon.c.o -c ../drivers/net/macb/macb_rxtx_vec_neon.c
./drivers/net/macb/macb_rxtx_vec_neon.c:50:15: error: unknown type name ‘uint8x8_t’
static inline uint8x8_t macb_mbuf_initializer(struct macb_rx_queue *rxq)
^~~~~~~~~
./drivers/net/macb/macb_rxtx_vec_neon.c: In function ‘macb_mbuf_initializer’:
./drivers/net/macb/macb_rxtx_vec_neon.c:53:2: error: unknown type name ‘uint64x1_t’; did you mean ‘uint64_t’?
uint64x1_t mbuf_initializer;
^~~~~~~~~~
uint64_t
./drivers/net/macb/macb_rxtx_vec_neon.c:54:2: error: unknown type name ‘uint8x8_t’; did you mean ‘uint8_t’?
uint8x8_t rearm_data_vec;
^~~~~~~~~
uint8_t
./drivers/net/macb/macb_rxtx_vec_neon.c:64:3: warning: implicit declaration of function ‘vset_lane_u64’; did you mean ‘rte_log2_u64’? [-Wimplicit-function-declaration]
vset_lane_u64(*(uint64_t *)(&mbuf.rearm_data), mbuf_initializer, 0);
^~~~~~~~~~~~~
rte_log2_u64
./drivers/net/macb/macb_rxtx_vec_neon.c:64:3: warning: nested extern declaration of ‘vset_lane_u64’ [-Wnested-externs]
./drivers/net/macb/macb_rxtx_vec_neon.c:65:19: warning: implicit declaration of function ‘vld1_u8’ [-Wimplicit-function-declaration]
rearm_data_vec = vld1_u8((uint8_t *)&mbuf_initializer);
^~~~~~~
./drivers/net/macb/macb_rxtx_vec_neon.c:65:19: warning: nested extern declaration of ‘vld1_u8’ [-Wnested-externs]
./drivers/net/macb/macb_rxtx_vec_neon.c: In function ‘macb_rxq_rearm’:
./drivers/net/macb/macb_rxtx_vec_neon.c:79:2: error: unknown type name ‘uint32x2_t’; did you mean ‘uint32_t’?
uint32x2_t zero = vdup_n_u32(0);
^~~~~~~~~~
uint32_t
./drivers/net/macb/macb_rxtx_vec_neon.c:79:20: warning: implicit declaration of function ‘vdup_n_u32’ [-Wimplicit-function-declaration]
uint32x2_t zero = vdup_n_u32(0);
^~~~~~~~~~
./drivers/net/macb/macb_rxtx_vec_neon.c:79:20: warning: nested extern declaration of ‘vdup_n_u32’ [-Wnested-externs]
./drivers/net/macb/macb_rxtx_vec_neon.c:80:2: error: unknown type name ‘uint8x8_t’; did you mean ‘uint8_t’?
uint8x8_t rearm_data_vec;
^~~~~~~~~
uint8_t
./drivers/net/macb/macb_rxtx_vec_neon.c:98:5: warning: implicit declaration of function ‘vst1_u32’ [-Wimplicit-function-declaration]
vst1_u32((uint32_t *)&desc[MACB_DESC_ADDR_INTERVAL ABI_VERSION app build buildtools config devtools doc drivers dts examples kernel last_gpr.txt lib license MAINTAINERS Makefile meson.build meson_options.txt README test-report.txt usertools VERSION i], zero);
^~~~~~~~
./drivers/net/macb/macb_rxtx_vec_neon.c:98:5: warning: nested extern declaration of ‘vst1_u32’ [-Wnested-externs]
./drivers/net/macb/macb_rxtx_vec_neon.c:111:3: warning: implicit declaration of function ‘vst1_u8’ [-Wimplicit-function-declaration]
vst1_u8((uint8_t *)&nmb->rearm_data, rearm_data_vec);
^~~~~~~
./drivers/net/macb/macb_rxtx_vec_neon.c:111:3: warning: nested extern declaration of ‘vst1_u8’ [-Wnested-externs]
./drivers/net/macb/macb_rxtx_vec_neon.c: In function ‘macb_recv_raw_pkts_vec’:
./drivers/net/macb/macb_rxtx_vec_neon.c:175:2: error: unknown type name ‘uint8x16_t’; did you mean ‘uint16_t’?
uint8x16_t shuf_msk = {
^~~~~~~~~~
uint16_t
./drivers/net/macb/macb_rxtx_vec_neon.c:176:9: warning: excess elements in scalar initializer
0xFF, 0xFF, 0xFF, 0xFF, 4, 5, 0xFF, 0xFF,
^~~~
./drivers/net/macb/macb_rxtx_vec_neon.c:176:9: note: (near initialization for ‘shuf_msk’)
./drivers/net/macb/macb_rxtx_vec_neon.c:176:15: warning: excess elements in scalar initializer
0xFF, 0xFF, 0xFF, 0xFF, 4, 5, 0xFF, 0xFF,
^~~~
./drivers/net/macb/macb_rxtx_vec_neon.c:176:15: note: (near initialization for ‘shuf_msk’)
./drivers/net/macb/macb_rxtx_vec_neon.c:176:21: warning: excess elements in scalar initializer
0xFF, 0xFF, 0xFF, 0xFF, 4, 5, 0xFF, 0xFF,
^~~~
./drivers/net/macb/macb_rxtx_vec_neon.c:176:21: note: (near initialization for ‘shuf_msk’)
./drivers/net/macb/macb_rxtx_vec_neon.c:176:27: warning: excess elements in scalar initializer
0xFF, 0xFF, 0xFF, 0xFF, 4, 5, 0xFF, 0xFF,
^
./drivers/net/macb/macb_rxtx_vec_neon.c:176:27: note: (near initialization for ‘shuf_msk’)
./drivers/net/macb/macb_rxtx_vec_neon.c:176:32: warning: excess elements in scalar initializer
0xFF, 0xFF, 0xFF, 0xFF, 4, 5, 0xFF, 0xFF,
^
./drivers/net/macb/macb_rxtx_vec_neon.c:176:32: note: (near initialization for ‘shuf_msk’)
./drivers/net/macb/macb_rxtx_vec_neon.c:176:35: warning: excess elements in scalar initializer
0xFF, 0xFF, 0xFF, 0xFF, 4, 5, 0xFF, 0xFF,
^~~~
./drivers/net/macb/macb_rxtx_vec_neon.c:176:35: note: (near initialization for ‘shuf_msk’)
./drivers/net/macb/macb_rxtx_vec_neon.c:176:41: warning: excess elements in scalar initializer
0xFF, 0xFF, 0xFF, 0xFF, 4, 5, 0xFF, 0xFF,
^~~~
./drivers/net/macb/macb_rxtx_vec_neon.c:176:41: note: (near initialization for ‘shuf_msk’)
./drivers/net/macb/macb_rxtx_vec_neon.c:177:3: warning: excess elements in scalar initializer
4, 5, 0xFF, 0xFF, 0xFF, 0xFF, 0xFF, 0xFF,
^
./drivers/net/macb/macb_rxtx_vec_neon.c:177:3: note: (near initialization for ‘shuf_msk’)
./drivers/net/macb/macb_rxtx_vec_neon.c:177:8: warning: excess elements in scalar initializer
4, 5, 0xFF, 0xFF, 0xFF, 0xFF, 0xFF, 0xFF,
^
./drivers/net/macb/macb_rxtx_vec_neon.c:177:8: note: (near initialization for ‘shuf_msk’)
./drivers/net/macb/macb_rxtx_vec_neon.c:177:11: warning: excess elements in scalar initializer
4, 5, 0xFF, 0xFF, 0xFF, 0xFF, 0xFF, 0xFF,
^~~~
./drivers/net/macb/macb_rxtx_vec_neon.c:177:11: note: (near initialization for ‘shuf_msk’)
./drivers/net/macb/macb_rxtx_vec_neon.c:177:17: warning: excess elements in scalar initializer
4, 5, 0xFF, 0xFF, 0xFF, 0xFF, 0xFF, 0xFF,
^~~~
./drivers/net/macb/macb_rxtx_vec_neon.c:177:17: note: (near initialization for ‘shuf_msk’)
./drivers/net/macb/macb_rxtx_vec_neon.c:177:23: warning: excess elements in scalar initializer
4, 5, 0xFF, 0xFF, 0xFF, 0xFF, 0xFF, 0xFF,
^~~~
./drivers/net/macb/macb_rxtx_vec_neon.c:177:23: note: (near initialization for ‘shuf_msk’)
./drivers/net/macb/macb_rxtx_vec_neon.c:177:29: warning: excess elements in scalar initializer
4, 5, 0xFF, 0xFF, 0xFF, 0xFF, 0xFF, 0xFF,
^~~~
./drivers/net/macb/macb_rxtx_vec_neon.c:177:29: note: (near initialization for ‘shuf_msk’)
./drivers/net/macb/macb_rxtx_vec_neon.c:177:35: warning: excess elements in scalar initializer
4, 5, 0xFF, 0xFF, 0xFF, 0xFF, 0xFF, 0xFF,
^~~~
./drivers/net/macb/macb_rxtx_vec_neon.c:177:35: note: (near initialization for ‘shuf_msk’)
./drivers/net/macb/macb_rxtx_vec_neon.c:177:41: warning: excess elements in scalar initializer
4, 5, 0xFF, 0xFF, 0xFF, 0xFF, 0xFF, 0xFF,
^~~~
./drivers/net/macb/macb_rxtx_vec_neon.c:177:41: note: (near initialization for ‘shuf_msk’)
./drivers/net/macb/macb_rxtx_vec_neon.c:179:2: error: unknown type name ‘uint16x8_t’; did you mean ‘uint16_t’?
uint16x8_t crc_adjust = {0, 0, rxq->crc_len, 0, rxq->crc_len, 0, 0, 0};
^~~~~~~~~~
uint16_t
./drivers/net/macb/macb_rxtx_vec_neon.c:179:30: warning: excess elements in scalar initializer
uint16x8_t crc_adjust = {0, 0, rxq->crc_len, 0, rxq->crc_len, 0, 0, 0};
^
./drivers/net/macb/macb_rxtx_vec_neon.c:179:30: note: (near initialization for ‘crc_adjust’)
./drivers/net/macb/macb_rxtx_vec_neon.c:179:33: warning: excess elements in scalar initializer
uint16x8_t crc_adjust = {0, 0, rxq->crc_len, 0, rxq->crc_len, 0, 0, 0};
^~~
./drivers/net/macb/macb_rxtx_vec_neon.c:179:33: note: (near initialization for ‘crc_adjust’)
./drivers/net/macb/macb_rxtx_vec_neon.c:179:47: warning: excess elements in scalar initializer
uint16x8_t crc_adjust = {0, 0, rxq->crc_len, 0, rxq->crc_len, 0, 0, 0};
^
./drivers/net/macb/macb_rxtx_vec_neon.c:179:47: note: (near initialization for ‘crc_adjust’)
./drivers/net/macb/macb_rxtx_vec_neon.c:179:50: warning: excess elements in scalar initializer
uint16x8_t crc_adjust = {0, 0, rxq->crc_len, 0, rxq->crc_len, 0, 0, 0};
^~~
./drivers/net/macb/macb_rxtx_vec_neon.c:179:50: note: (near initialization for ‘crc_adjust’)
./drivers/net/macb/macb_rxtx_vec_neon.c:179:64: warning: excess elements in scalar initializer
uint16x8_t crc_adjust = {0, 0, rxq->crc_len, 0, rxq->crc_len, 0, 0, 0};
^
./drivers/net/macb/macb_rxtx_vec_neon.c:179:64: note: (near initialization for ‘crc_adjust’)
./drivers/net/macb/macb_rxtx_vec_neon.c:179:67: warning: excess elements in scalar initializer
uint16x8_t crc_adjust = {0, 0, rxq->crc_len, 0, rxq->crc_len, 0, 0, 0};
^
./drivers/net/macb/macb_rxtx_vec_neon.c:179:67: note: (near initialization for ‘crc_adjust’)
./drivers/net/macb/macb_rxtx_vec_neon.c:179:70: warning: excess elements in scalar initializer
uint16x8_t crc_adjust = {0, 0, rxq->crc_len, 0, rxq->crc_len, 0, 0, 0};
^
./drivers/net/macb/macb_rxtx_vec_neon.c:179:70: note: (near initialization for ‘crc_adjust’)
./drivers/net/macb/macb_rxtx_vec_neon.c:208:3: error: unknown type name ‘uint64x2_t’; did you mean ‘uint64_t’?
uint64x2_t mbp1, mbp2;
^~~~~~~~~~
uint64_t
./drivers/net/macb/macb_rxtx_vec_neon.c:209:3: error: unknown type name ‘uint64x2_t’; did you mean ‘uint64_t’?
uint64x2_t descs[MACB_DESCS_PER_LOOP];
^~~~~~~~~~
uint64_t
./drivers/net/macb/macb_rxtx_vec_neon.c:210:3: error: unknown type name ‘uint8x16x2_t’; did you mean ‘uint16_t’?
uint8x16x2_t sterr_tmp1, sterr_tmp2;
^~~~~~~~~~~~
uint16_t
./drivers/net/macb/macb_rxtx_vec_neon.c:211:3: error: unknown type name ‘uint8x16_t’; did you mean ‘uint16_t’?
uint8x16_t staterr;
^~~~~~~~~~
uint16_t
./drivers/net/macb/macb_rxtx_vec_neon.c:212:3: error: unknown type name ‘uint8x16_t’; did you mean ‘uint16_t’?
uint8x16_t pkt_mb1, pkt_mb2, pkt_mb3, pkt_mb4;
^~~~~~~~~~
uint16_t
./drivers/net/macb/macb_rxtx_vec_neon.c:213:3: error: unknown type name ‘uint16x8_t’; did you mean ‘uint16_t’?
uint16x8_t pkt_mb_mask;
^~~~~~~~~~
uint16_t
./drivers/net/macb/macb_rxtx_vec_neon.c:214:3: error: unknown type name ‘uint16x8_t’; did you mean ‘uint16_t’?
uint16x8_t tmp;
^~~~~~~~~~
uint16_t
./drivers/net/macb/macb_rxtx_vec_neon.c:221:10: warning: implicit declaration of function ‘vld1q_u64’ [-Wimplicit-function-declaration]
mbp1 = vld1q_u64((uint64_t *)&rx_sw_ring[pos]);
^~~~~~~~~
./drivers/net/macb/macb_rxtx_vec_neon.c:221:10: warning: nested extern declaration of ‘vld1q_u64’ [-Wnested-externs]
./drivers/net/macb/macb_rxtx_vec_neon.c:223:3: warning: implicit declaration of function ‘vst1q_u64’ [-Wimplicit-function-declaration]
vst1q_u64((uint64_t *)&rx_pkts[pos], mbp1);
^~~~~~~~~
./drivers/net/macb/macb_rxtx_vec_neon.c:223:3: warning: nested extern declaration of ‘vst1q_u64’ [-Wnested-externs]
./drivers/net/macb/macb_rxtx_vec_neon.c:251:13: warning: implicit declaration of function ‘vqtbl1q_u8’ [-Wimplicit-function-declaration]
pkt_mb1 = vqtbl1q_u8(vreinterpretq_u8_u64(descs[0]), shuf_msk);
^~~~~~~~~~
./drivers/net/macb/macb_rxtx_vec_neon.c:251:13: warning: nested extern declaration of ‘vqtbl1q_u8’ [-Wnested-externs]
./drivers/net/macb/macb_rxtx_vec_neon.c:251:24: warning: implicit declaration of function ‘vreinterpretq_u8_u64’ [-Wimplicit-function-declaration]
pkt_mb1 = vqtbl1q_u8(vreinterpretq_u8_u64(descs[0]), shuf_msk);
^~~~~~~~~~~~~~~~~~~~
./drivers/net/macb/macb_rxtx_vec_neon.c:251:24: warning: nested extern declaration of ‘vreinterpretq_u8_u64’ [-Wnested-externs]
./drivers/net/macb/macb_rxtx_vec_neon.c:258:18: warning: implicit declaration of function ‘vdupq_n_u16’ [-Wimplicit-function-declaration]
pkt_mb_mask = vdupq_n_u16(MACB_RX_JFRMLEN_MASK);
^~~~~~~~~~~
./drivers/net/macb/macb_rxtx_vec_neon.c:258:18: warning: nested extern declaration of ‘vdupq_n_u16’ [-Wnested-externs]
./drivers/net/macb/macb_rxtx_vec_neon.c:262:9: warning: implicit declaration of function ‘vsubq_u16’ [-Wimplicit-function-declaration]
tmp = vsubq_u16(vandq_u16(vreinterpretq_u16_u8(pkt_mb1), pkt_mb_mask), crc_adjust);
^~~~~~~~~
./drivers/net/macb/macb_rxtx_vec_neon.c:262:9: warning: nested extern declaration of ‘vsubq_u16’ [-Wnested-externs]
./drivers/net/macb/macb_rxtx_vec_neon.c:262:19: warning: implicit declaration of function ‘vandq_u16’ [-Wimplicit-function-declaration]
tmp = vsubq_u16(vandq_u16(vreinterpretq_u16_u8(pkt_mb1), pkt_mb_mask), crc_adjust);
^~~~~~~~~
./drivers/net/macb/macb_rxtx_vec_neon.c:262:19: warning: nested extern declaration of ‘vandq_u16’ [-Wnested-externs]
./drivers/net/macb/macb_rxtx_vec_neon.c:262:29: warning: implicit declaration of function ‘vreinterpretq_u16_u8’ [-Wimplicit-function-declaration]
tmp = vsubq_u16(vandq_u16(vreinterpretq_u16_u8(pkt_mb1), pkt_mb_mask), crc_adjust);
^~~~~~~~~~~~~~~~~~~~
./drivers/net/macb/macb_rxtx_vec_neon.c:262:29: warning: nested extern declaration of ‘vreinterpretq_u16_u8’ [-Wnested-externs]
./drivers/net/macb/macb_rxtx_vec_neon.c:263:13: warning: implicit declaration of function ‘vreinterpretq_u8_u16’ [-Wimplicit-function-declaration]
pkt_mb1 = vreinterpretq_u8_u16(tmp);
^~~~~~~~~~~~~~~~~~~~
./drivers/net/macb/macb_rxtx_vec_neon.c:263:13: warning: nested extern declaration of ‘vreinterpretq_u8_u16’ [-Wnested-externs]
./drivers/net/macb/macb_rxtx_vec_neon.c:264:22: warning: implicit declaration of function ‘vgetq_lane_u16’ [-Wimplicit-function-declaration]
cur_bytes_len[0] = vgetq_lane_u16(tmp, 2);
^~~~~~~~~~~~~~
./drivers/net/macb/macb_rxtx_vec_neon.c:264:22: warning: nested extern declaration of ‘vgetq_lane_u16’ [-Wnested-externs]
./drivers/net/macb/macb_rxtx_vec_neon.c:270:3: warning: implicit declaration of function ‘vst1q_u8’ [-Wimplicit-function-declaration]
vst1q_u8((uint8_t *)&rx_pkts[pos]->rx_descriptor_fields1, pkt_mb1);
^~~~~~~~
./drivers/net/macb/macb_rxtx_vec_neon.c:270:3: warning: nested extern declaration of ‘vst1q_u8’ [-Wnested-externs]
./drivers/net/macb/macb_rxtx_vec_neon.c:286:16: warning: implicit declaration of function ‘vzipq_u8’ [-Wimplicit-function-declaration]
sterr_tmp1 = vzipq_u8(vreinterpretq_u8_u64(descs[0]),
^~~~~~~~
./drivers/net/macb/macb_rxtx_vec_neon.c:286:16: warning: nested extern declaration of ‘vzipq_u8’ [-Wnested-externs]
./drivers/net/macb/macb_rxtx_vec_neon.c:293:4: error: unknown type name ‘uint8x16_t’; did you mean ‘uint16_t’?
uint8x16_t eof;
^~~~~~~~~~
uint16_t
./drivers/net/macb/macb_rxtx_vec_neon.c:295:29: error: request for member ‘val’ in something not a structure or union
eof = vzipq_u8(sterr_tmp1.val[0], sterr_tmp2.val[0]).val[1];
^
./drivers/net/macb/macb_rxtx_vec_neon.c:295:48: error: request for member ‘val’ in something not a structure or union
eof = vzipq_u8(sterr_tmp1.val[0], sterr_tmp2.val[0]).val[1];
^
./drivers/net/macb/macb_rxtx_vec_neon.c:296:11: warning: implicit declaration of function ‘vgetq_lane_u32’; did you mean ‘rte_log2_u32’? [-Wimplicit-function-declaration]
stat = vgetq_lane_u32(vreinterpretq_u32_u8(eof), 1);
^~~~~~~~~~~~~~
rte_log2_u32
./drivers/net/macb/macb_rxtx_vec_neon.c:296:11: warning: nested extern declaration of ‘vgetq_lane_u32’ [-Wnested-externs]
./drivers/net/macb/macb_rxtx_vec_neon.c:296:26: warning: implicit declaration of function ‘vreinterpretq_u32_u8’ [-Wimplicit-function-declaration]
stat = vgetq_lane_u32(vreinterpretq_u32_u8(eof), 1);
^~~~~~~~~~~~~~~~~~~~
./drivers/net/macb/macb_rxtx_vec_neon.c:296:26: warning: nested extern declaration of ‘vreinterpretq_u32_u8’ [-Wnested-externs]
./drivers/net/macb/macb_rxtx_vec_neon.c:304:32: error: request for member ‘val’ in something not a structure or union
staterr = vzipq_u8(sterr_tmp1.val[0], sterr_tmp2.val[0]).val[0];
^
./drivers/net/macb/macb_rxtx_vec_neon.c:304:51: error: request for member ‘val’ in something not a structure or union
staterr = vzipq_u8(sterr_tmp1.val[0], sterr_tmp2.val[0]).val[0];
^
./drivers/net/macb/macb_rxtx_vec_neon.c:307:13: warning: implicit declaration of function ‘vshlq_n_u8’ [-Wimplicit-function-declaration]
staterr = vshlq_n_u8(staterr, MACB_UINT8_BIT - 1);
^~~~~~~~~~
./drivers/net/macb/macb_rxtx_vec_neon.c:307:13: warning: nested extern declaration of ‘vshlq_n_u8’ [-Wnested-externs]
./drivers/net/macb/macb_rxtx_vec_neon.c:308:13: warning: implicit declaration of function ‘vreinterpretq_u8_s8’ [-Wimplicit-function-declaration]
staterr = vreinterpretq_u8_s8(vshrq_n_s8(vreinterpretq_s8_u8(staterr),
^~~~~~~~~~~~~~~~~~~
./drivers/net/macb/macb_rxtx_vec_neon.c:308:13: warning: nested extern declaration of ‘vreinterpretq_u8_s8’ [-Wnested-externs]
./drivers/net/macb/macb_rxtx_vec_neon.c:308:33: warning: implicit declaration of function ‘vshrq_n_s8’ [-Wimplicit-function-declaration]
staterr = vreinterpretq_u8_s8(vshrq_n_s8(vreinterpretq_s8_u8(staterr),
^~~~~~~~~~
./drivers/net/macb/macb_rxtx_vec_neon.c:308:33: warning: nested extern declaration of ‘vshrq_n_s8’ [-Wnested-externs]
./drivers/net/macb/macb_rxtx_vec_neon.c:308:44: warning: implicit declaration of function ‘vreinterpretq_s8_u8’ [-Wimplicit-function-declaration]
staterr = vreinterpretq_u8_s8(vshrq_n_s8(vreinterpretq_s8_u8(staterr),
^~~~~~~~~~~~~~~~~~~
./drivers/net/macb/macb_rxtx_vec_neon.c:308:44: warning: nested extern declaration of ‘vreinterpretq_s8_u8’ [-Wnested-externs]
./drivers/net/macb/macb_rxtx_vec_neon.c:326:5: error: unknown type name ‘uint8x16_t’; did you mean ‘uint16_t’?
uint8x16_t sof_eof;
^~~~~~~~~~
uint16_t
./drivers/net/macb/macb_rxtx_vec_neon.c:328:34: error: request for member ‘val’ in something not a structure or union
sof_eof = vzipq_u8(sterr_tmp1.val[0], sterr_tmp2.val[0]).val[1];
^
./drivers/net/macb/macb_rxtx_vec_neon.c:328:53: error: request for member ‘val’ in something not a structure or union
sof_eof = vzipq_u8(sterr_tmp1.val[0], sterr_tmp2.val[0]).val[1];
^
./drivers/net/macb/macb_rxtx_vec_neon.c:210:28: warning: variable ‘sterr_tmp2’ set but not used [-Wunused-but-set-variable]
uint8x16x2_t sterr_tmp1, sterr_tmp2;
^~~~~~~~~~
./drivers/net/macb/macb_rxtx_vec_neon.c:210:16: warning: variable ‘sterr_tmp1’ set but not used [-Wunused-but-set-variable]
uint8x16x2_t sterr_tmp1, sterr_tmp2;
^~~~~~~~~~
./drivers/net/macb/macb_rxtx_vec_neon.c: In function ‘macb_set_txdesc’:
./drivers/net/macb/macb_rxtx_vec_neon.c:520:2: error: unknown type name ‘uint32x4_t’; did you mean ‘uint32_t’?
uint32x4_t ctrl_v = vdupq_n_u32(0);
^~~~~~~~~~
uint32_t
./drivers/net/macb/macb_rxtx_vec_neon.c:520:22: warning: implicit declaration of function ‘vdupq_n_u32’ [-Wimplicit-function-declaration]
uint32x4_t ctrl_v = vdupq_n_u32(0);
^~~~~~~~~~~
./drivers/net/macb/macb_rxtx_vec_neon.c:520:22: warning: nested extern declaration of ‘vdupq_n_u32’ [-Wnested-externs]
./drivers/net/macb/macb_rxtx_vec_neon.c:521:2: error: unknown type name ‘uint32x4_t’; did you mean ‘uint32_t’?
uint32x4_t data_len_v = vdupq_n_u32(0);
^~~~~~~~~~
uint32_t
./drivers/net/macb/macb_rxtx_vec_neon.c:522:2: error: unknown type name ‘uint32x4_t’; did you mean ‘uint32_t’?
uint32x4_t BIT_TX_USED = vdupq_n_u32(MACB_BIT(TX_USED));
^~~~~~~~~~
uint32_t
./drivers/net/macb/macb_rxtx_vec_neon.c:523:2: error: unknown type name ‘uint32x4_t’; did you mean ‘uint32_t’?
uint32x4_t BIT_TX_LAST = vdupq_n_u32(MACB_BIT(TX_LAST));
^~~~~~~~~~
uint32_t
./drivers/net/macb/macb_rxtx_vec_neon.c:524:2: error: unknown type name ‘uint32x4_t’; did you mean ‘uint32_t’?
uint32x4_t BIT_TX_WARP = vdupq_n_u32(0);
^~~~~~~~~~
uint32_t
./drivers/net/macb/macb_rxtx_vec_neon.c:525:2: error: unknown type name ‘uint32x4_t’; did you mean ‘uint32_t’?
uint32x4_t BIT_TX_UNUSED = vdupq_n_u32(~MACB_BIT(TX_USED));
^~~~~~~~~~
uint32_t
./drivers/net/macb/macb_rxtx_vec_neon.c:529:3: warning: implicit declaration of function ‘vsetq_lane_u32’; did you mean ‘rte_log2_u32’? [-Wimplicit-function-declaration]
vsetq_lane_u32((uint32_t)(tx_pkts[0]->data_len), data_len_v, 0);
^~~~~~~~~~~~~~
rte_log2_u32
./drivers/net/macb/macb_rxtx_vec_neon.c:529:3: warning: nested extern declaration of ‘vsetq_lane_u32’ [-Wnested-externs]
./drivers/net/macb/macb_rxtx_vec_neon.c:537:11: warning: implicit declaration of function ‘vorrq_u32’ [-Wimplicit-function-declaration]
ctrl_v = vorrq_u32(vorrq_u32(data_len_v, BIT_TX_USED), BIT_TX_LAST);
^~~~~~~~~
./drivers/net/macb/macb_rxtx_vec_neon.c:537:11: warning: nested extern declaration of ‘vorrq_u32’ [-Wnested-externs]
./drivers/net/macb/macb_rxtx_vec_neon.c:556:11: warning: implicit declaration of function ‘vandq_u32’ [-Wimplicit-function-declaration]
ctrl_v = vandq_u32(ctrl_v, BIT_TX_UNUSED);
^~~~~~~~~
./drivers/net/macb/macb_rxtx_vec_neon.c:556:11: warning: nested extern declaration of ‘vandq_u32’ [-Wnested-externs]
./drivers/net/macb/macb_rxtx_vec_neon.c: In function ‘macb_xmit_pkts_vec’:
./drivers/net/macb/macb_rxtx_vec_neon.c:577:2: error: unknown type name ‘uint64x2_t’; did you mean ‘uint64_t’?
uint64x2_t mbp1, mbp2;
^~~~~~~~~~
uint64_t
./drivers/net/macb/macb_rxtx_vec_neon.c:578:2: error: unknown type name ‘uint16x4_t’; did you mean ‘uint64_t’?
uint16x4_t nb_segs_v = vdup_n_u16(0);
^~~~~~~~~~
uint64_t
./drivers/net/macb/macb_rxtx_vec_neon.c:578:25: warning: implicit declaration of function ‘vdup_n_u16’ [-Wimplicit-function-declaration]
uint16x4_t nb_segs_v = vdup_n_u16(0);
^~~~~~~~~~
./drivers/net/macb/macb_rxtx_vec_neon.c:578:25: warning: nested extern declaration of ‘vdup_n_u16’ [-Wnested-externs]
./drivers/net/macb/macb_rxtx_vec_neon.c:592:15: warning: implicit declaration of function ‘vset_lane_u16’; did you mean ‘setlinebuf’? [-Wimplicit-function-declaration]
nb_segs_v = vset_lane_u16(tx_pkts[nb_tx]->nb_segs, nb_segs_v, 0);
^~~~~~~~~~~~~
setlinebuf
./drivers/net/macb/macb_rxtx_vec_neon.c:592:15: warning: nested extern declaration of ‘vset_lane_u16’ [-Wnested-externs]
./drivers/net/macb/macb_rxtx_vec_neon.c:596:7: warning: implicit declaration of function ‘vmaxv_u16’ [-Wimplicit-function-declaration]
if (vmaxv_u16(nb_segs_v) > 1) {
^~~~~~~~~
./drivers/net/macb/macb_rxtx_vec_neon.c:596:7: warning: nested extern declaration of ‘vmaxv_u16’ [-Wnested-externs]
[1485/2553] Linking static target drivers/net/macb/base/libmacb_base.a
[1486/2553] Compiling C object drivers/libtmp_rte_net_igc.a.p/net_igc_igc_txrx.c.o
[1487/2553] Compiling C object drivers/net/ice/base/libice_base.a.p/ice_switch.c.o
[1488/2553] Compiling C object drivers/net/ixgbe/base/libixgbe_base.a.p/ixgbe_phy.c.o
[1489/2553] Compiling C object drivers/libtmp_rte_net_netvsc.a.p/net_netvsc_hn_nvs.c.o
[1490/2553] Generating rte_net_ionic.pmd.c with a custom command
[1491/2553] Compiling C object drivers/libtmp_rte_net_ixgbe.a.p/net_ixgbe_rte_pmd_ixgbe.c.o
[1492/2553] Compiling C object drivers/libtmp_rte_net_netvsc.a.p/net_netvsc_hn_rndis.c.o
[1493/2553] Compiling C object drivers/libtmp_rte_net_macb.a.p/net_macb_macb_ethdev.c.o
[1494/2553] Generating rte_net_ipn3ke.pmd.c with a custom command
[1495/2553] Compiling C object drivers/libtmp_rte_net_memif.a.p/net_memif_memif_socket.c.o
[1496/2553] Compiling C object drivers/libtmp_rte_net_netvsc.a.p/net_netvsc_hn_vf.c.o
[1497/2553] Compiling C object drivers/libtmp_rte_net_netvsc.a.p/net_netvsc_hn_ethdev.c.o
[1498/2553] Compiling C object drivers/net/ixgbe/base/libixgbe_base.a.p/ixgbe_e610.c.o
[1499/2553] Compiling C object drivers/libtmp_rte_net_ice.a.p/net_ice_ice_rxtx.c.o
[1500/2553] Compiling C object drivers/libtmp_rte_net_nfp.a.p/net_nfp_flower_nfp_flower.c.o
[1501/2553] Compiling C object drivers/libtmp_rte_net_ice.a.p/net_ice_ice_ethdev.c.o
[1502/2553] Compiling C object drivers/libtmp_rte_net_ixgbe.a.p/net_ixgbe_ixgbe_flow.c.o
[1503/2553] Compiling C object drivers/libtmp_rte_net_nfp.a.p/net_nfp_flower_nfp_flower_cmsg.c.o
[1504/2553] Compiling C object drivers/libtmp_rte_net_nfp.a.p/net_nfp_flower_nfp_flower_ctrl.c.o
[1505/2553] Compiling C object drivers/net/ixgbe/base/libixgbe_base.a.p/ixgbe_common.c.o
[1506/2553] Compiling C object drivers/net/ixgbe/base/libixgbe_base.a.p/ixgbe_x550.c.o
[1507/2553] Compiling C object drivers/libtmp_rte_net_nfp.a.p/net_nfp_flower_nfp_flower_representor.c.o
[1508/2553] Compiling C object drivers/libtmp_rte_net_macb.a.p/net_macb_macb_rxtx.c.o
[1509/2553] Generating rte_net_iavf.pmd.c with a custom command
[1510/2553] Compiling C object drivers/libtmp_rte_net_nfp.a.p/net_nfp_flower_nfp_conntrack.c.o
[1511/2553] Compiling C object drivers/libtmp_rte_net_netvsc.a.p/net_netvsc_hn_rxtx.c.o
[1512/2553] Compiling C object drivers/libtmp_rte_net_memif.a.p/net_memif_rte_eth_memif.c.o
[1513/2553] Compiling C object drivers/libtmp_rte_net_ixgbe.a.p/net_ixgbe_ixgbe_ethdev.c.o
[1514/2553] Compiling C object drivers/libtmp_rte_net_nfp.a.p/net_nfp_flower_nfp_flower_flow.c.o
[1515/2553] Compiling C object drivers/libtmp_rte_net_ixgbe.a.p/net_ixgbe_ixgbe_rxtx.c.o
[1516/2553] Compiling C object drivers/libtmp_rte_crypto_cnxk.a.p/crypto_cnxk_cn10k_cryptodev_ops.c.o
[1517/2553] Generating rte_common_cnxk.sym_chk with a custom command (wrapped by meson to capture output)
ninja: build stopped: subcommand failed.
-------------------------------END LOGS------------------------------
^ permalink raw reply [flat|nested] 3+ messages in thread