From mboxrd@z Thu Jan 1 00:00:00 1970 Return-Path: Received: from mails.dpdk.org (mails.dpdk.org [217.70.189.124]) by inbox.dpdk.org (Postfix) with ESMTP id 38BC145BCD for ; Wed, 30 Oct 2024 07:00:32 +0100 (CET) Received: from mails.dpdk.org (localhost [127.0.0.1]) by mails.dpdk.org (Postfix) with ESMTP id 36E7342FB9; Wed, 30 Oct 2024 07:00:32 +0100 (CET) Received: from mail.loongson.cn (mail.loongson.cn [114.242.206.163]) by mails.dpdk.org (Postfix) with ESMTP id A6EA542EC5 for ; Wed, 30 Oct 2024 07:00:28 +0100 (CET) Received: from loongson.cn (unknown [10.40.64.71]) by gateway (Coremail) with SMTP id _____8CxPuN4yyFnDZodAA--.61061S3; Wed, 30 Oct 2024 14:00:24 +0800 (CST) Received: from localhost.localdomain (unknown [10.40.64.71]) by front1 (Coremail) with SMTP id qMiowMBxP+F1yyFnWacoAA--.1488S3; Wed, 30 Oct 2024 14:00:21 +0800 (CST) Received: from localhost.localdomain (localhost.localdomain [127.0.0.1]) by localhost.localdomain (8.15.2/8.15.2) with ESMTPS id 49U5R1RI1786914 (version=TLSv1.3 cipher=TLS_AES_256_GCM_SHA384 bits=256 verify=NOT); Wed, 30 Oct 2024 13:27:01 +0800 Received: (from root@localhost) by localhost.localdomain (8.15.2/8.15.2/Submit) id 49U5QuPZ1786913; Wed, 30 Oct 2024 13:26:56 +0800 Date: Wed, 30 Oct 2024 13:26:56 +0800 From: qemudev@loongson.cn Message-Id: <202410300526.49U5QuPZ1786913@localhost.localdomain> Content-Type: text/plain; charset="utf-8" Subject: |FAILURE| pw147707 [PATCH v1] net/macb: add new driver In-Reply-To: <1730267479-473022-1-git-send-email-liwencheng@phytium.com.cn> References: <1730267479-473022-1-git-send-email-liwencheng@phytium.com.cn> To: test-report@dpdk.org Cc: liwencheng , zhoumin@loongson.cn X-CM-TRANSID: qMiowMBxP+F1yyFnWacoAA--.1488S3 X-CM-SenderInfo: pthp3vthy6z05rqj20fqof0/1tbiAgEGD2chbE8GyAACsj X-Coremail-Antispam: 1Uk129KBj9fXoWfWrykWrWUXr1DGw4UAFW5urX_yoW5Cry7Ko WxZ3W8Aay5Gr1xAr4q9a97uasxJrZ8trn8G3W3AFs8uFWxJFW3KryUJF1fJa1aya1fAa4k uay7JrsxJr12qFy8l-sFpf9Il3svdjkaLaAFLSUrUUUUUb8apTn2vfkv8UJUUUU8wcxFpf 9Il3svdxBIdaVrn0xqx4xG64xvF2IEw4CE5I8CrVC2j2Jv73VFW2AGmfu7bjvjm3AaLaJ3 UjIYCTnIWjp_UUUYb7kC6x804xWl14x267AKxVWUJVW8JwAFc2x0x2IEx4CE42xK8VAvwI 8IcIk0rVWrJVCq3wAFIxvE14AKwVWUGVWUXwA2ocxC64kIII0Yj41l84x0c7CEw4AK67xG Y2AK021l84ACjcxK6xIIjxv20xvE14v26r1I6r4UM28EF7xvwVC0I7IYx2IY6xkF7I0E14 v26r1j6r4UM28EF7xvwVC2z280aVAFwI0_Gr1j6F4UJwA2z4x0Y4vEx4A2jsIEc7CjxVAF wI0_Gr1j6F4UJwAS0I0E0xvYzxvE52x082IY62kv0487Mc804VCY07AIYIkI8VC2zVCFFI 0UMc02F40EFcxC0VAKzVAqx4xG6I80ewAv7VC0I7IYx2IY67AKxVWUXVWUAwAv7VC2z280 aVAFwI0_Gr0_Cr1lOx8S6xCaFVCjc4AY6r1j6r4UM4kE6xkIj40Ew7xC0wCF04k20xvY0x 0EwIxGrwCFx2IqxVCFs4IE7xkEbVWUJVW8JwC20s026c02F40E14v26r1j6r18MI8I3I0E 7480Y4vE14v26r106r1rMI8E67AF67kF1VAFwI0_Jrv_JF1lIxkGc2Ij64vIr41lIxAIcV C0I7IYx2IY67AKxVWUJVWUCwCI42IY6xIIjxv20xvEc7CjxVAFwI0_Jr0_Gr1lIxAIcVCF 04k26cxKx2IYs7xG6r1j6r1xMIIF0xvEx4A2jsIE14v26r4j6F4UMIIF0xvEx4A2jsIEc7 CjxVAFwI0_Gr0_Gr1UYxBIdaVFxhVjvjDU0xZFpf9x07jO6pPUUUUU= X-BeenThere: test-report@dpdk.org X-Mailman-Version: 2.1.29 Precedence: list List-Id: automatic DPDK test reports List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , Errors-To: test-report-bounces@dpdk.org Test-Label: loongarch-compilation Test-Status: FAILURE http://dpdk.org/patch/147707 _ninja build failure_ Submitter: liwencheng 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------------------------------