* lib/crc/arm/crc64-neon.h:11:9: sparse: sparse: Trying to use reserved word 'return' as identifier
@ 2026-06-18 6:00 kernel test robot
0 siblings, 0 replies; 2+ messages in thread
From: kernel test robot @ 2026-06-18 6:00 UTC (permalink / raw)
To: oe-kbuild; +Cc: lkp
::::::
:::::: Manual check reason: "low confidence static check warning: lib/crc/arm/crc64-neon.h:11:9: sparse: sparse: Trying to use reserved word 'return' as identifier"
::::::
BCC: lkp@intel.com
CC: oe-kbuild-all@lists.linux.dev
CC: linux-kernel@vger.kernel.org
TO: Ard Biesheuvel <ardb@kernel.org>
CC: Eric Biggers <ebiggers@kernel.org>
tree: https://git.kernel.org/pub/scm/linux/kernel/git/torvalds/linux.git master
head: e771677c937da5808f7b6c1f0e4a97ec1a84f8a8
commit: e3babebfb83865ec2be90e64d3f73f9aca140b3a lib/crc: arm: Enable arm64's NEON intrinsics implementation of crc64
date: 3 weeks ago
:::::: branch date: 9 hours ago
:::::: commit date: 3 weeks ago
config: arm-randconfig-r112-20260618 (https://download.01.org/0day-ci/archive/20260618/202606181200.hWkw6EH4-lkp@intel.com/config)
compiler: clang version 20.1.8 (https://github.com/llvm/llvm-project 87f0227cb60147a26a1eeb4fb06e3b505e9c7261)
sparse: v0.6.5-rc1
reproduce (this is a W=1 build): (https://download.01.org/0day-ci/archive/20260618/202606181200.hWkw6EH4-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
| Fixes: e3babebfb838 ("lib/crc: arm: Enable arm64's NEON intrinsics implementation of crc64")
| Reported-by: kernel test robot <lkp@intel.com>
| Closes: https://lore.kernel.org/r/202606181200.hWkw6EH4-lkp@intel.com/
sparse warnings: (new ones prefixed by >>)
lib/crc/crc64-neon.c: note: in included file:
arch/arm/include/asm/neon-intrinsics.h:7:2: sparse: sparse: You should compile this file with '-march=armv7-a -mfloat-abi=softfp -mfpu=neon'
lib/crc/crc64-neon.c: note: in included file (through arch/arm/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/crc64-neon.c: note: in included file:
lib/crc/arm/crc64-neon.h:3:26: sparse: sparse: Expected ; at end of declaration
lib/crc/arm/crc64-neon.h:3:26: sparse: sparse: got pmull64
lib/crc/arm/crc64-neon.h:7:20: sparse: sparse: Expected ; at end of declaration
lib/crc/arm/crc64-neon.h:7:20: sparse: sparse: got result
>> lib/crc/arm/crc64-neon.h:11:9: sparse: sparse: Trying to use reserved word 'return' as identifier
lib/crc/arm/crc64-neon.h:11:16: sparse: sparse: Expected ; at end of declaration
lib/crc/arm/crc64-neon.h:11:16: sparse: sparse: got result
lib/crc/arm/crc64-neon.h:12:1: sparse: sparse: Expected ; at the end of type declaration
lib/crc/arm/crc64-neon.h:12:1: sparse: sparse: got }
lib/crc/arm/crc64-neon.h:18:20: sparse: sparse: Expected ; at end of declaration
lib/crc/arm/crc64-neon.h:18:20: sparse: sparse: got result
lib/crc/arm/crc64-neon.h:22:9: sparse: sparse: Trying to use reserved word 'return' as identifier
lib/crc/arm/crc64-neon.h:22:16: sparse: sparse: Expected ; at end of declaration
lib/crc/arm/crc64-neon.h:22:16: sparse: sparse: got result
lib/crc/arm/crc64-neon.h:23:1: sparse: sparse: Expected ; at the end of type declaration
lib/crc/arm/crc64-neon.h:23:1: sparse: sparse: got }
lib/crc/arm/crc64-neon.h:29:20: sparse: sparse: Expected ; at end of declaration
lib/crc/arm/crc64-neon.h:29:20: sparse: sparse: got result
lib/crc/arm/crc64-neon.h:33:9: sparse: sparse: Trying to use reserved word 'return' as identifier
lib/crc/arm/crc64-neon.h:33:16: sparse: sparse: Expected ; at end of declaration
lib/crc/arm/crc64-neon.h:33:16: sparse: sparse: got result
lib/crc/arm/crc64-neon.h:34:1: sparse: sparse: Expected ; at the end of type declaration
lib/crc/arm/crc64-neon.h:34:1: sparse: sparse: got }
lib/crc/crc64-neon.c:22:20: sparse: sparse: Expected ; at end of statement
lib/crc/crc64-neon.c:22:20: sparse: sparse: got fold_consts
lib/crc/crc64-neon.c:23:20: sparse: sparse: Expected ; at end of statement
lib/crc/crc64-neon.c:23:20: sparse: sparse: got v0
lib/crc/crc64-neon.c:24:20: sparse: sparse: Expected ; at end of statement
lib/crc/crc64-neon.c:24:20: sparse: sparse: got zero
lib/crc/crc64-neon.c:41:20: sparse: sparse: Expected ; at end of statement
lib/crc/crc64-neon.c:41:20: sparse: sparse: got bconsts
lib/crc/crc64-neon.c:42:20: sparse: sparse: Expected ; at end of statement
lib/crc/crc64-neon.c:42:20: sparse: sparse: got final
lib/crc/arm/crc64-neon.h:6:22: sparse: sparse: undefined identifier 'vgetq_lane_u64'
lib/crc/arm/crc64-neon.h:17:22: sparse: sparse: undefined identifier 'vgetq_lane_u64'
lib/crc/arm/crc64-neon.h:17:18: sparse: sparse: symbol 'm' has multiple initializers (originally initialized at lib/crc/arm/crc64-neon.h:6)
lib/crc/arm/crc64-neon.h:28:22: sparse: sparse: undefined identifier 'vgetq_lane_u64'
lib/crc/arm/crc64-neon.h:28:18: sparse: sparse: symbol 'm' has multiple initializers (originally initialized at lib/crc/arm/crc64-neon.h:17)
lib/crc/crc64-neon.c:27:17: sparse: sparse: undefined identifier 'v0'
lib/crc/crc64-neon.c:27:23: sparse: sparse: undefined identifier 'vreinterpretq_u64_u8'
lib/crc/crc64-neon.c:34:17: sparse: sparse: undefined identifier 'v0'
lib/crc/crc64-neon.c:34:22: sparse: sparse: undefined identifier 'pmull64'
lib/crc/crc64-neon.c:34:49: sparse: sparse: undefined identifier 'pmull64_high'
lib/crc/crc64-neon.c:38:9: sparse: sparse: undefined identifier 'v0'
lib/crc/crc64-neon.c:38:14: sparse: sparse: undefined identifier 'vextq_u64'
lib/crc/crc64-neon.c:38:39: sparse: sparse: undefined identifier 'pmull64_hi_lo'
lib/crc/crc64-neon.c:44:9: sparse: sparse: undefined identifier 'v0'
lib/crc/crc64-neon.c:44:15: sparse: sparse: undefined identifier 'vextq_u64'
lib/crc/crc64-neon.c:44:43: sparse: sparse: undefined identifier 'pmull64_hi_lo'
lib/crc/crc64-neon.c:46:16: sparse: sparse: undefined identifier 'vgetq_lane_u64'
vim +/return +11 lib/crc/arm/crc64-neon.h
e3babebfb83865 Ard Biesheuvel 2026-04-22 2
e3babebfb83865 Ard Biesheuvel 2026-04-22 3 static inline uint64x2_t pmull64(uint64x2_t a, uint64x2_t b)
e3babebfb83865 Ard Biesheuvel 2026-04-22 4 {
e3babebfb83865 Ard Biesheuvel 2026-04-22 5 uint64_t l = vgetq_lane_u64(a, 0);
e3babebfb83865 Ard Biesheuvel 2026-04-22 6 uint64_t m = vgetq_lane_u64(b, 0);
e3babebfb83865 Ard Biesheuvel 2026-04-22 7 uint64x2_t result;
e3babebfb83865 Ard Biesheuvel 2026-04-22 8
e3babebfb83865 Ard Biesheuvel 2026-04-22 9 asm("vmull.p64 %q0, %P1, %P2" : "=w"(result) : "w"(l), "w"(m));
e3babebfb83865 Ard Biesheuvel 2026-04-22 10
e3babebfb83865 Ard Biesheuvel 2026-04-22 @11 return result;
e3babebfb83865 Ard Biesheuvel 2026-04-22 12 }
e3babebfb83865 Ard Biesheuvel 2026-04-22 13
--
0-DAY CI Kernel Test Service
https://github.com/intel/lkp-tests/wiki
^ permalink raw reply [flat|nested] 2+ messages in thread
* lib/crc/arm/crc64-neon.h:11:9: sparse: sparse: Trying to use reserved word 'return' as identifier
@ 2026-07-24 13:14 kernel test robot
0 siblings, 0 replies; 2+ messages in thread
From: kernel test robot @ 2026-07-24 13:14 UTC (permalink / raw)
To: oe-kbuild; +Cc: lkp
::::::
:::::: Manual check reason: "low confidence static check warning: lib/crc/arm/crc64-neon.h:11:9: sparse: sparse: Trying to use reserved word 'return' as identifier"
::::::
BCC: lkp@intel.com
CC: oe-kbuild-all@lists.linux.dev
CC: linux-kernel@vger.kernel.org
TO: Ard Biesheuvel <ardb@kernel.org>
CC: Eric Biggers <ebiggers@kernel.org>
tree: https://git.kernel.org/pub/scm/linux/kernel/git/torvalds/linux.git master
head: 4539944e515183668109bdf4d0c3d7d228383d88
commit: e3babebfb83865ec2be90e64d3f73f9aca140b3a lib/crc: arm: Enable arm64's NEON intrinsics implementation of crc64
date: 8 weeks ago
:::::: branch date: 2 days ago
:::::: commit date: 8 weeks ago
config: arm-randconfig-r123-20260724 (https://download.01.org/0day-ci/archive/20260724/202607242030.gEsyDfTe-lkp@intel.com/config)
compiler: arm-linux-gnueabi-gcc (GCC) 8.5.0
sparse: v0.6.5-rc1
reproduce (this is a W=1 build): (https://download.01.org/0day-ci/archive/20260724/202607242030.gEsyDfTe-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
| Fixes: e3babebfb838 ("lib/crc: arm: Enable arm64's NEON intrinsics implementation of crc64")
| Reported-by: kernel test robot <lkp@intel.com>
| Closes: https://lore.kernel.org/r/202607242030.gEsyDfTe-lkp@intel.com/
sparse warnings: (new ones prefixed by >>)
lib/crc/crc64-neon.c: note: in included file:
arch/arm/include/asm/neon-intrinsics.h:7:2: sparse: sparse: You should compile this file with '-march=armv7-a -mfloat-abi=softfp -mfpu=neon'
lib/crc/crc64-neon.c: note: in included file (through arch/arm/include/asm/neon-intrinsics.h):
../lib/gcc/arm-linux-gnueabi/8.5.0/include/arm_neon.h:31:2: sparse: sparse: "NEON intrinsics not available with the soft-float ABI. Please use -mfloat-abi=softfp or -mfloat-abi=hard"
lib/crc/crc64-neon.c: note: in included file:
lib/crc/arm/crc64-neon.h:3:26: sparse: sparse: Expected ; at end of declaration
lib/crc/arm/crc64-neon.h:3:26: sparse: sparse: got pmull64
lib/crc/arm/crc64-neon.h:7:20: sparse: sparse: Expected ; at end of declaration
lib/crc/arm/crc64-neon.h:7:20: sparse: sparse: got result
>> lib/crc/arm/crc64-neon.h:11:9: sparse: sparse: Trying to use reserved word 'return' as identifier
lib/crc/arm/crc64-neon.h:11:16: sparse: sparse: Expected ; at end of declaration
lib/crc/arm/crc64-neon.h:11:16: sparse: sparse: got result
lib/crc/arm/crc64-neon.h:12:1: sparse: sparse: Expected ; at the end of type declaration
lib/crc/arm/crc64-neon.h:12:1: sparse: sparse: got }
lib/crc/arm/crc64-neon.h:18:20: sparse: sparse: Expected ; at end of declaration
lib/crc/arm/crc64-neon.h:18:20: sparse: sparse: got result
lib/crc/arm/crc64-neon.h:22:9: sparse: sparse: Trying to use reserved word 'return' as identifier
lib/crc/arm/crc64-neon.h:22:16: sparse: sparse: Expected ; at end of declaration
lib/crc/arm/crc64-neon.h:22:16: sparse: sparse: got result
lib/crc/arm/crc64-neon.h:23:1: sparse: sparse: Expected ; at the end of type declaration
lib/crc/arm/crc64-neon.h:23:1: sparse: sparse: got }
lib/crc/arm/crc64-neon.h:29:20: sparse: sparse: Expected ; at end of declaration
lib/crc/arm/crc64-neon.h:29:20: sparse: sparse: got result
lib/crc/arm/crc64-neon.h:33:9: sparse: sparse: Trying to use reserved word 'return' as identifier
lib/crc/arm/crc64-neon.h:33:16: sparse: sparse: Expected ; at end of declaration
lib/crc/arm/crc64-neon.h:33:16: sparse: sparse: got result
lib/crc/arm/crc64-neon.h:34:1: sparse: sparse: Expected ; at the end of type declaration
lib/crc/arm/crc64-neon.h:34:1: sparse: sparse: got }
lib/crc/crc64-neon.c:22:20: sparse: sparse: Expected ; at end of statement
lib/crc/crc64-neon.c:22:20: sparse: sparse: got fold_consts
lib/crc/crc64-neon.c:23:20: sparse: sparse: Expected ; at end of statement
lib/crc/crc64-neon.c:23:20: sparse: sparse: got v0
lib/crc/crc64-neon.c:24:20: sparse: sparse: Expected ; at end of statement
lib/crc/crc64-neon.c:24:20: sparse: sparse: got zero
lib/crc/crc64-neon.c:41:20: sparse: sparse: Expected ; at end of statement
lib/crc/crc64-neon.c:41:20: sparse: sparse: got bconsts
lib/crc/crc64-neon.c:42:20: sparse: sparse: Expected ; at end of statement
lib/crc/crc64-neon.c:42:20: sparse: sparse: got final
lib/crc/arm/crc64-neon.h:6:22: sparse: sparse: undefined identifier 'vgetq_lane_u64'
lib/crc/arm/crc64-neon.h:17:22: sparse: sparse: undefined identifier 'vgetq_lane_u64'
lib/crc/arm/crc64-neon.h:17:18: sparse: sparse: symbol 'm' has multiple initializers (originally initialized at lib/crc/arm/crc64-neon.h:6)
lib/crc/arm/crc64-neon.h:28:22: sparse: sparse: undefined identifier 'vgetq_lane_u64'
lib/crc/arm/crc64-neon.h:28:18: sparse: sparse: symbol 'm' has multiple initializers (originally initialized at lib/crc/arm/crc64-neon.h:17)
lib/crc/crc64-neon.c:27:17: sparse: sparse: undefined identifier 'v0'
lib/crc/crc64-neon.c:27:23: sparse: sparse: undefined identifier 'vreinterpretq_u64_u8'
lib/crc/crc64-neon.c:34:17: sparse: sparse: undefined identifier 'v0'
lib/crc/crc64-neon.c:34:22: sparse: sparse: undefined identifier 'pmull64'
lib/crc/crc64-neon.c:34:49: sparse: sparse: undefined identifier 'pmull64_high'
lib/crc/crc64-neon.c:38:9: sparse: sparse: undefined identifier 'v0'
lib/crc/crc64-neon.c:38:14: sparse: sparse: undefined identifier 'vextq_u64'
lib/crc/crc64-neon.c:38:39: sparse: sparse: undefined identifier 'pmull64_hi_lo'
lib/crc/crc64-neon.c:44:9: sparse: sparse: undefined identifier 'v0'
lib/crc/crc64-neon.c:44:15: sparse: sparse: undefined identifier 'vextq_u64'
lib/crc/crc64-neon.c:44:43: sparse: sparse: undefined identifier 'pmull64_hi_lo'
lib/crc/crc64-neon.c:46:16: sparse: sparse: undefined identifier 'vgetq_lane_u64'
vim +/return +11 lib/crc/arm/crc64-neon.h
e3babebfb83865 Ard Biesheuvel 2026-04-22 2
e3babebfb83865 Ard Biesheuvel 2026-04-22 @3 static inline uint64x2_t pmull64(uint64x2_t a, uint64x2_t b)
e3babebfb83865 Ard Biesheuvel 2026-04-22 4 {
e3babebfb83865 Ard Biesheuvel 2026-04-22 5 uint64_t l = vgetq_lane_u64(a, 0);
e3babebfb83865 Ard Biesheuvel 2026-04-22 6 uint64_t m = vgetq_lane_u64(b, 0);
e3babebfb83865 Ard Biesheuvel 2026-04-22 7 uint64x2_t result;
e3babebfb83865 Ard Biesheuvel 2026-04-22 8
e3babebfb83865 Ard Biesheuvel 2026-04-22 9 asm("vmull.p64 %q0, %P1, %P2" : "=w"(result) : "w"(l), "w"(m));
e3babebfb83865 Ard Biesheuvel 2026-04-22 10
e3babebfb83865 Ard Biesheuvel 2026-04-22 @11 return result;
e3babebfb83865 Ard Biesheuvel 2026-04-22 12 }
e3babebfb83865 Ard Biesheuvel 2026-04-22 13
--
0-DAY CI Kernel Test Service
https://github.com/intel/lkp-tests/wiki
^ permalink raw reply [flat|nested] 2+ messages in thread
end of thread, other threads:[~2026-07-24 13:14 UTC | newest]
Thread overview: 2+ messages (download: mbox.gz follow: Atom feed
-- links below jump to the message on this page --
2026-07-24 13:14 lib/crc/arm/crc64-neon.h:11:9: sparse: sparse: Trying to use reserved word 'return' as identifier kernel test robot
-- strict thread matches above, loose matches on Subject: below --
2026-06-18 6:00 kernel test robot
This is an external index of several public inboxes,
see mirroring instructions on how to clone and mirror
all data and code used by this external index.