From: kernel test robot <lkp@intel.com>
To: oe-kbuild@lists.linux.dev
Cc: lkp@intel.com
Subject: Re: [PATCH 4/5] lib/crc: arm64: Simplify intrinsics implementation
Date: Wed, 1 Apr 2026 05:56:44 +0800 [thread overview]
Message-ID: <202604010522.5iUE599X-lkp@intel.com> (raw)
::::::
:::::: Manual check reason: "low confidence static check warning: lib/crc/arm64/crc64-neon-inner.c:29:9: sparse: sparse: Trying to use reserved word 'return' as identifier"
::::::
BCC: lkp@intel.com
CC: oe-kbuild-all@lists.linux.dev
In-Reply-To: <20260330144630.33026-11-ardb@kernel.org>
References: <20260330144630.33026-11-ardb@kernel.org>
TO: Ard Biesheuvel <ardb@kernel.org>
TO: linux-crypto@vger.kernel.org
CC: linux-arm-kernel@lists.infradead.org
CC: Ard Biesheuvel <ardb@kernel.org>
CC: Demian Shulhan <demyansh@gmail.com>
CC: Eric Biggers <ebiggers@kernel.org>
Hi Ard,
kernel test robot noticed the following build warnings:
[auto build test WARNING on 63432fd625372a0e79fb00a4009af204f4edc013]
url: https://github.com/intel-lab-lkp/linux/commits/Ard-Biesheuvel/lib-crc-arm64-Drop-unnecessary-chunking-logic-from-crc64/20260331-150617
base: 63432fd625372a0e79fb00a4009af204f4edc013
patch link: https://lore.kernel.org/r/20260330144630.33026-11-ardb%40kernel.org
patch subject: [PATCH 4/5] lib/crc: arm64: Simplify intrinsics implementation
:::::: branch date: 15 hours ago
:::::: commit date: 15 hours ago
config: arm64-randconfig-r134-20260401 (https://download.01.org/0day-ci/archive/20260401/202604010522.5iUE599X-lkp@intel.com/config)
compiler: clang version 20.1.8 (https://github.com/llvm/llvm-project 87f0227cb60147a26a1eeb4fb06e3b505e9c7261)
rustc: rustc 1.88.0 (6b00bc388 2025-06-23)
sparse: v0.6.5-rc1
reproduce (this is a W=1 build): (https://download.01.org/0day-ci/archive/20260401/202604010522.5iUE599X-lkp@intel.com/reproduce)
If you fix the issue in a separate patch/commit (i.e. not just a new version of
the same patch/commit), kindly add following tags
| Reported-by: kernel test robot <lkp@intel.com>
| Closes: https://lore.kernel.org/r/202604010522.5iUE599X-lkp@intel.com/
sparse warnings: (new ones prefixed by >>)
lib/crc/arm64/crc64-neon-inner.c: note: in included file (through arch/arm64/include/asm/neon-intrinsics.h):
/opt/cross/clang-87f0227cb6/lib/clang/20/include/arm_neon.h:28:2: sparse: sparse: "NEON intrinsics not available with the soft-float ABI. Please use -mfloat-abi=softfp or -mfloat-abi=hard"
lib/crc/arm64/crc64-neon-inner.c:18:26: sparse: sparse: Expected ; at end of declaration
lib/crc/arm64/crc64-neon-inner.c:18:26: sparse: sparse: got pmull64
lib/crc/arm64/crc64-neon-inner.c:22:1: sparse: sparse: Expected ; at the end of type declaration
lib/crc/arm64/crc64-neon-inner.c:22:1: sparse: sparse: got }
lib/crc/arm64/crc64-neon-inner.c:27:20: sparse: sparse: Expected ; at end of declaration
lib/crc/arm64/crc64-neon-inner.c:27:20: sparse: sparse: got m
>> lib/crc/arm64/crc64-neon-inner.c:29:9: sparse: sparse: Trying to use reserved word 'return' as identifier
lib/crc/arm64/crc64-neon-inner.c:29:16: sparse: sparse: Expected ; at end of declaration
lib/crc/arm64/crc64-neon-inner.c:29:16: sparse: sparse: got vreinterpretq_u64_p128
lib/crc/arm64/crc64-neon-inner.c:30:1: sparse: sparse: Expected ; at the end of type declaration
lib/crc/arm64/crc64-neon-inner.c:30:1: sparse: sparse: got }
lib/crc/arm64/crc64-neon-inner.c:36:1: sparse: sparse: Expected ; at the end of type declaration
lib/crc/arm64/crc64-neon-inner.c:36:1: sparse: sparse: got }
lib/crc/arm64/crc64-neon-inner.c:41:20: sparse: sparse: Expected ; at end of declaration
lib/crc/arm64/crc64-neon-inner.c:41:20: sparse: sparse: got v0
lib/crc/arm64/crc64-neon-inner.c:42:20: sparse: sparse: Expected ; at end of declaration
lib/crc/arm64/crc64-neon-inner.c:42:20: sparse: sparse: got zero
lib/crc/arm64/crc64-neon-inner.c:44:14: sparse: sparse: Expected ) in function declarator
lib/crc/arm64/crc64-neon-inner.c:44:14: sparse: sparse: got ;
>> lib/crc/arm64/crc64-neon-inner.c:44:9: sparse: sparse: Trying to use reserved word 'for' as identifier
lib/crc/arm64/crc64-neon-inner.c:44:16: sparse: sparse: Expected ; at the end of type declaration
lib/crc/arm64/crc64-neon-inner.c:44:16: sparse: sparse: got )
lib/crc/arm64/crc64-neon-inner.c:47:19: sparse: sparse: Expected ; at end of declaration
lib/crc/arm64/crc64-neon-inner.c:47:19: sparse: sparse: got +=
lib/crc/arm64/crc64-neon-inner.c:48:21: sparse: sparse: Expected ; at end of declaration
lib/crc/arm64/crc64-neon-inner.c:48:21: sparse: sparse: got -=
lib/crc/arm64/crc64-neon-inner.c:49:25: sparse: sparse: Expected ) in function declarator
lib/crc/arm64/crc64-neon-inner.c:49:25: sparse: sparse: got <
>> lib/crc/arm64/crc64-neon-inner.c:49:17: sparse: sparse: Trying to use reserved word 'if' as identifier
lib/crc/arm64/crc64-neon-inner.c:53:9: sparse: sparse: Expected ; at the end of type declaration
lib/crc/arm64/crc64-neon-inner.c:53:9: sparse: sparse: got }
lib/crc/arm64/crc64-neon-inner.c:59:20: sparse: sparse: Expected ; at end of declaration
lib/crc/arm64/crc64-neon-inner.c:59:20: sparse: sparse: got bconsts
lib/crc/arm64/crc64-neon-inner.c:60:20: sparse: sparse: Expected ; at end of declaration
lib/crc/arm64/crc64-neon-inner.c:60:20: sparse: sparse: got final
lib/crc/arm64/crc64-neon-inner.c:62:12: sparse: sparse: Expected ; at end of declaration
lib/crc/arm64/crc64-neon-inner.c:62:12: sparse: sparse: got ^=
lib/crc/arm64/crc64-neon-inner.c:64:9: sparse: sparse: Trying to use reserved word 'return' as identifier
lib/crc/arm64/crc64-neon-inner.c:64:16: sparse: sparse: Expected ; at end of declaration
lib/crc/arm64/crc64-neon-inner.c:64:16: sparse: sparse: got vgetq_lane_u64
lib/crc/arm64/crc64-neon-inner.c:65:1: sparse: sparse: Expected ; at the end of type declaration
lib/crc/arm64/crc64-neon-inner.c:65:1: sparse: sparse: got }
lib/crc/arm64/crc64-neon-inner.c:52:22: sparse: sparse: undefined identifier 'pmull64'
lib/crc/arm64/crc64-neon-inner.c:52:49: sparse: sparse: undefined identifier 'pmull64_high'
vim +/return +29 lib/crc/arm64/crc64-neon-inner.c
63432fd625372a Demian Shulhan 2026-03-29 23
38163ec975bb4f Ard Biesheuvel 2026-03-30 24 static inline uint64x2_t pmull64_high(uint64x2_t a, uint64x2_t b)
38163ec975bb4f Ard Biesheuvel 2026-03-30 25 {
38163ec975bb4f Ard Biesheuvel 2026-03-30 26 poly64x2_t l = vreinterpretq_p64_u64(a);
38163ec975bb4f Ard Biesheuvel 2026-03-30 27 poly64x2_t m = vreinterpretq_p64_u64(b);
63432fd625372a Demian Shulhan 2026-03-29 28
38163ec975bb4f Ard Biesheuvel 2026-03-30 @29 return vreinterpretq_u64_p128(vmull_high_p64(l, m));
38163ec975bb4f Ard Biesheuvel 2026-03-30 30 }
63432fd625372a Demian Shulhan 2026-03-29 31
38163ec975bb4f Ard Biesheuvel 2026-03-30 32 static inline uint64x2_t pmull64_hi_lo(uint64x2_t a, uint64x2_t b)
38163ec975bb4f Ard Biesheuvel 2026-03-30 33 {
38163ec975bb4f Ard Biesheuvel 2026-03-30 34 return vreinterpretq_u64_p128(vmull_p64(vgetq_lane_u64(a, 1),
38163ec975bb4f Ard Biesheuvel 2026-03-30 35 vgetq_lane_u64(b, 0)));
38163ec975bb4f Ard Biesheuvel 2026-03-30 36 }
63432fd625372a Demian Shulhan 2026-03-29 37
38163ec975bb4f Ard Biesheuvel 2026-03-30 38 u64 crc64_nvme_arm64_c(u64 crc, const u8 *p, size_t len)
38163ec975bb4f Ard Biesheuvel 2026-03-30 39 {
38163ec975bb4f Ard Biesheuvel 2026-03-30 40 uint64x2_t fold_consts = vld1q_u64(fold_consts_val);
38163ec975bb4f Ard Biesheuvel 2026-03-30 41 uint64x2_t v0 = { crc, 0 };
38163ec975bb4f Ard Biesheuvel 2026-03-30 42 uint64x2_t zero = { };
63432fd625372a Demian Shulhan 2026-03-29 43
38163ec975bb4f Ard Biesheuvel 2026-03-30 @44 for (;;) {
38163ec975bb4f Ard Biesheuvel 2026-03-30 45 v0 ^= vreinterpretq_u64_u8(vld1q_u8(p));
63432fd625372a Demian Shulhan 2026-03-29 46
63432fd625372a Demian Shulhan 2026-03-29 47 p += 16;
63432fd625372a Demian Shulhan 2026-03-29 48 len -= 16;
38163ec975bb4f Ard Biesheuvel 2026-03-30 @49 if (len < 16)
--
0-DAY CI Kernel Test Service
https://github.com/intel/lkp-tests/wiki
reply other threads:[~2026-03-31 21:57 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=202604010522.5iUE599X-lkp@intel.com \
--to=lkp@intel.com \
--cc=oe-kbuild@lists.linux.dev \
/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