From mboxrd@z Thu Jan 1 00:00:00 1970 Received: from mgamail.intel.com (mgamail.intel.com [198.175.65.16]) (using TLSv1.2 with cipher ECDHE-RSA-AES256-GCM-SHA384 (256/256 bits)) (No client certificate requested) by smtp.subspace.kernel.org (Postfix) with ESMTPS id B34FC36B05E for ; Tue, 29 Sep 2026 03:24:04 +0000 (UTC) Authentication-Results: smtp.subspace.kernel.org; arc=none smtp.client-ip=198.175.65.16 ARC-Seal:i=1; a=rsa-sha256; d=subspace.kernel.org; s=arc-20240116; t=1790652248; cv=none; b=GIqO1ZdkyFvntOriW2QV84BrfdktN9DpMRGciSKMbjcSdvTLqeHr24T/6i0ivsyRnOblJtUQ53wOHQfV87X8T7OCAKWlyOTKrxeYpEgQWAt6HWx9Ic9TsyASetG8HNxpaABcRFsn/+/6jD9b4wHjmZqav22iJM+Xi9mUqr1hh80= ARC-Message-Signature:i=1; a=rsa-sha256; d=subspace.kernel.org; s=arc-20240116; t=1790652248; c=relaxed/simple; bh=XY47yTaFaHZ3AG1bOac1aOf/BqCRKDwP6Tg1X69Ays0=; h=Date:From:To:Cc:Subject:Message-ID; b=gvBAEEX7wcIRKy8nn0FumEBMSeVF5HDgoYPo2JqRxQB7bPs9pa3bqzN+/g5cvDlW0ZmRGb6jDigS5RJMl8K3x3ZfwhYVBEiBaRrQEkDk9EllGsYfUNvjYKooYAlAijyHvS/1vcrBOxO7U/iuQibP9vzYWdm8GmTJ9g3YWJZFQGg= ARC-Authentication-Results:i=1; smtp.subspace.kernel.org; dmarc=pass (p=none dis=none) header.from=intel.com; spf=pass smtp.mailfrom=intel.com; dkim=pass (2048-bit key) header.d=intel.com header.i=@intel.com header.b=EWSr58Pc; arc=none smtp.client-ip=198.175.65.16 Authentication-Results: smtp.subspace.kernel.org; dmarc=pass (p=none dis=none) header.from=intel.com Authentication-Results: smtp.subspace.kernel.org; spf=pass smtp.mailfrom=intel.com Authentication-Results: smtp.subspace.kernel.org; dkim=pass (2048-bit key) header.d=intel.com header.i=@intel.com header.b="EWSr58Pc" DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/simple; d=intel.com; i=@intel.com; q=dns/txt; s=Intel; t=1790652245; x=1822188245; h=date:from:to:cc:subject:message-id; bh=XY47yTaFaHZ3AG1bOac1aOf/BqCRKDwP6Tg1X69Ays0=; b=EWSr58PcnQ0+VoJy4r7PpKIyfi9BglQSJpqkMDy8LmRYxo30e6ueW2nf sAJqDLl0lH4lHxtUce2+JC93qONh811Mx6NiaXdmI0EQ+DHG6Xvi2erMt a800nqb4RyYl92E1crzdvIUPjuoMUCZXWNEIlcovl45GyibB0TRRwb0LB D2vuWNdV/30ORC0CL2VkOha3j+FH5B8wtJqTT9wlcy5BQeFxm7upot5/c VJON3JrFUqo6ol5uPY0EXDWiX7d84O55AyJcDHemQ3wBc8oLeyOa6YnlL tTQewFsNtlS37zOSUlIjz7d5KqBzVQavJHbxawtjomOGuILlLsP2YsSpG Q==; X-CSE-ConnectionGUID: jy4UH5uWQWKCj7ePWGabjw== X-CSE-MsgGUID: uj9eOgT0TH68yjLFcrUe+A== X-IronPort-AV: E=McAfee;i="6800,10657,11919"; a="90581733" X-IronPort-AV: E=Sophos;i="6.27,129,1787036400"; d="scan'208";a="90581733" Received: from fmviesa003.fm.intel.com ([10.60.135.143]) by orvoesa108.jf.intel.com with ESMTP/TLS/ECDHE-RSA-AES256-GCM-SHA384; 28 Sep 2026 20:24:05 -0700 X-CSE-ConnectionGUID: rFSo+pC+SdG1Tjs6DSBg+A== X-CSE-MsgGUID: 5PkZeKQ1ROaMLW6kEsyKag== X-ExtLoop1: 1 Received: from igk-lkp-server01.igk.intel.com (HELO 04362d00df5a) ([10.211.93.152]) by fmviesa003.fm.intel.com with ESMTP; 28 Sep 2026 20:24:03 -0700 Received: from kbuild by 04362d00df5a with local (Exim 4.98.2) (envelope-from ) id 1xBORk-000000001HP-3Jrf; Tue, 29 Sep 2026 03:24:00 +0000 Date: Tue, 29 Sep 2026 05:23:28 +0200 From: kernel test robot To: oe-kbuild@lists.linux.dev Cc: lkp@intel.com Subject: lib/raid/raid6/arm/recov_neon_inner.c:23:9: sparse: sparse: Trying to use reserved word 'return' as identifier Message-ID: <202609290546.XKNiSECn-lkp@intel.com> User-Agent: s-nail v14.9.25 Precedence: bulk X-Mailing-List: oe-kbuild@lists.linux.dev List-Id: List-Subscribe: List-Unsubscribe: :::::: :::::: Manual check reason: "low confidence static check warning: lib/raid/raid6/arm/recov_neon_inner.c:23: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: Christoph Hellwig CC: Andrew Morton CC: Linux Memory Management List Hi Christoph, First bad commit (maybe != root cause): tree: https://git.kernel.org/pub/scm/linux/kernel/git/torvalds/linux.git master head: 72d3fcf802c45d00b300f25b848a93c3a2bd7c7e commit: 3626738bc7147d52cb49f3994a9846aa2d34810a raid6: move to lib/raid/ date: 4 months ago :::::: branch date: 30 hours ago :::::: commit date: 4 months ago config: arm-randconfig-r2305-20260929 (https://download.01.org/0day-ci/archive/20260929/202609290546.XKNiSECn-lkp@intel.com/config) compiler: clang version 24.0.0git (https://github.com/llvm/llvm-project 7615da10b75c57286a4032eac8bb43c1b8d2ba46) sparse: v0.6.5-rc1 reproduce (this is a W=1 build): (https://download.01.org/0day-ci/archive/20260929/202609290546.XKNiSECn-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: 3626738bc714 ("raid6: move to lib/raid/") | Reported-by: kernel test robot | Closes: https://lore.kernel.org/r/202609290546.XKNiSECn-lkp@intel.com/ sparse warnings: (new ones prefixed by >>) lib/raid/raid6/arm/recov_neon_inner.c: note: in included file: /opt/cross/clang-7615da10b7/lib/clang/24/include/arm_neon.h:30:2: sparse: sparse: "NEON intrinsics not available with the soft-float ABI. Please use -mfloat-abi=softfp or -mfloat-abi=hard" lib/raid/raid6/arm/recov_neon_inner.c: note: in included file: lib/raid/raid6/arm/neon.h:15:50: sparse: sparse: Expected ) in function declarator lib/raid/raid6/arm/neon.h:15:50: sparse: sparse: got * lib/raid/raid6/arm/neon.h:19:50: sparse: sparse: Expected ) in function declarator lib/raid/raid6/arm/neon.h:19:50: sparse: sparse: got * lib/raid/raid6/arm/recov_neon_inner.c:16:19: sparse: sparse: Expected ; at end of declaration lib/raid/raid6/arm/recov_neon_inner.c:16:19: sparse: sparse: got vqtbl1q_u8 lib/raid/raid6/arm/recov_neon_inner.c:20:33: sparse: sparse: Expected ; at end of declaration lib/raid/raid6/arm/recov_neon_inner.c:20:33: sparse: sparse: got pair lib/raid/raid6/arm/recov_neon_inner.c:21:9: sparse: sparse: Expected ; at the end of type declaration lib/raid/raid6/arm/recov_neon_inner.c:21:9: sparse: sparse: got } >> lib/raid/raid6/arm/recov_neon_inner.c:23:9: sparse: sparse: Trying to use reserved word 'return' as identifier lib/raid/raid6/arm/recov_neon_inner.c:23:16: sparse: sparse: Expected ; at end of declaration lib/raid/raid6/arm/recov_neon_inner.c:23:16: sparse: sparse: got vcombine_u8 lib/raid/raid6/arm/recov_neon_inner.c:25:1: sparse: sparse: Expected ; at the end of type declaration lib/raid/raid6/arm/recov_neon_inner.c:25:1: sparse: sparse: got } lib/raid/raid6/arm/recov_neon_inner.c:33:20: sparse: sparse: Expected ; at end of declaration lib/raid/raid6/arm/recov_neon_inner.c:33:20: sparse: sparse: got pm1 lib/raid/raid6/arm/recov_neon_inner.c:34:20: sparse: sparse: Expected ; at end of declaration lib/raid/raid6/arm/recov_neon_inner.c:34:20: sparse: sparse: got qm0 lib/raid/raid6/arm/recov_neon_inner.c:35:20: sparse: sparse: Expected ; at end of declaration lib/raid/raid6/arm/recov_neon_inner.c:35:20: sparse: sparse: got qm1 lib/raid/raid6/arm/recov_neon_inner.c:36:20: sparse: sparse: Expected ; at end of declaration lib/raid/raid6/arm/recov_neon_inner.c:36:20: sparse: sparse: got x0f lib/raid/raid6/arm/recov_neon_inner.c:50:9: sparse: sparse: Trying to use reserved word 'while' as identifier lib/raid/raid6/arm/recov_neon_inner.c:50:16: sparse: sparse: missing type declaration for parameter 'bytes' lib/raid/raid6/arm/recov_neon_inner.c:51:28: sparse: sparse: Expected ; at end of statement lib/raid/raid6/arm/recov_neon_inner.c:51:28: sparse: sparse: got vx lib/raid/raid6/arm/recov_neon_inner.c:76:1: sparse: sparse: Expected ; at the end of type declaration lib/raid/raid6/arm/recov_neon_inner.c:76:1: sparse: sparse: got } lib/raid/raid6/arm/recov_neon_inner.c:82:20: sparse: sparse: Expected ; at end of declaration lib/raid/raid6/arm/recov_neon_inner.c:82:20: sparse: sparse: got qm1 lib/raid/raid6/arm/recov_neon_inner.c:83:20: sparse: sparse: Expected ; at end of declaration lib/raid/raid6/arm/recov_neon_inner.c:83:20: sparse: sparse: got x0f lib/raid/raid6/arm/recov_neon_inner.c:92:9: sparse: sparse: Trying to use reserved word 'while' as identifier lib/raid/raid6/arm/recov_neon_inner.c:92:16: sparse: sparse: missing type declaration for parameter 'bytes' lib/raid/raid6/arm/recov_neon_inner.c:93:28: sparse: sparse: Expected ; at end of statement lib/raid/raid6/arm/recov_neon_inner.c:93:28: sparse: sparse: got vx lib/raid/raid6/arm/recov_neon_inner.c:111:1: sparse: sparse: Expected ; at the end of type declaration lib/raid/raid6/arm/recov_neon_inner.c:111:1: sparse: sparse: got } lib/raid/raid6/arm/recov_neon_inner.c:53:17: sparse: sparse: undefined identifier 'px' lib/raid/raid6/arm/recov_neon_inner.c:53:22: sparse: sparse: undefined identifier 'veorq_u8' lib/raid/raid6/arm/recov_neon_inner.c:54:17: sparse: sparse: undefined identifier 'vx' lib/raid/raid6/arm/recov_neon_inner.c:54:22: sparse: sparse: undefined identifier 'veorq_u8' lib/raid/raid6/arm/recov_neon_inner.c:56:17: sparse: sparse: undefined identifier 'vy' lib/raid/raid6/arm/recov_neon_inner.c:56:22: sparse: sparse: undefined identifier 'vshrq_n_u8' lib/raid/raid6/arm/recov_neon_inner.c:57:17: sparse: sparse: undefined identifier 'vx' lib/raid/raid6/arm/recov_neon_inner.c:57:22: sparse: sparse: undefined identifier 'vqtbl1q_u8' lib/raid/raid6/arm/recov_neon_inner.c:58:17: sparse: sparse: undefined identifier 'vy' lib/raid/raid6/arm/recov_neon_inner.c:58:22: sparse: sparse: undefined identifier 'vqtbl1q_u8' lib/raid/raid6/arm/recov_neon_inner.c:59:17: sparse: sparse: undefined identifier 'qx' lib/raid/raid6/arm/recov_neon_inner.c:59:22: sparse: sparse: undefined identifier 'veorq_u8' lib/raid/raid6/arm/recov_neon_inner.c:61:17: sparse: sparse: undefined identifier 'vy' lib/raid/raid6/arm/recov_neon_inner.c:61:22: sparse: sparse: undefined identifier 'vshrq_n_u8' lib/raid/raid6/arm/recov_neon_inner.c:62:17: sparse: sparse: undefined identifier 'vx' lib/raid/raid6/arm/recov_neon_inner.c:62:22: sparse: sparse: undefined identifier 'vqtbl1q_u8' lib/raid/raid6/arm/recov_neon_inner.c:63:17: sparse: sparse: undefined identifier 'vy' lib/raid/raid6/arm/recov_neon_inner.c:63:22: sparse: sparse: undefined identifier 'vqtbl1q_u8' lib/raid/raid6/arm/recov_neon_inner.c:64:17: sparse: sparse: undefined identifier 'vx' lib/raid/raid6/arm/recov_neon_inner.c:64:22: sparse: sparse: undefined identifier 'veorq_u8' lib/raid/raid6/arm/recov_neon_inner.c:65:17: sparse: sparse: undefined identifier 'db' lib/raid/raid6/arm/recov_neon_inner.c:65:22: sparse: sparse: undefined identifier 'veorq_u8' lib/raid/raid6/arm/recov_neon_inner.c:67:17: sparse: sparse: undefined identifier 'vst1q_u8' lib/raid/raid6/arm/recov_neon_inner.c:68:17: sparse: sparse: undefined identifier 'vst1q_u8' lib/raid/raid6/arm/recov_neon_inner.c:71:17: sparse: sparse: undefined identifier 'p' lib/raid/raid6/arm/recov_neon_inner.c:72:17: sparse: sparse: undefined identifier 'q' lib/raid/raid6/arm/recov_neon_inner.c:73:17: sparse: sparse: undefined identifier 'dp' lib/raid/raid6/arm/recov_neon_inner.c:74:17: sparse: sparse: undefined identifier 'dq' lib/raid/raid6/arm/recov_neon_inner.c:95:17: sparse: sparse: undefined identifier 'vx' lib/raid/raid6/arm/recov_neon_inner.c:95:22: sparse: sparse: undefined identifier 'veorq_u8' lib/raid/raid6/arm/recov_neon_inner.c:97:17: sparse: sparse: undefined identifier 'vy' lib/raid/raid6/arm/recov_neon_inner.c:97:22: sparse: sparse: undefined identifier 'vshrq_n_u8' lib/raid/raid6/arm/recov_neon_inner.c:98:17: sparse: sparse: undefined identifier 'vx' lib/raid/raid6/arm/recov_neon_inner.c:98:22: sparse: sparse: undefined identifier 'vqtbl1q_u8' lib/raid/raid6/arm/recov_neon_inner.c:99:17: sparse: sparse: undefined identifier 'vy' lib/raid/raid6/arm/recov_neon_inner.c:99:22: sparse: sparse: undefined identifier 'vqtbl1q_u8' lib/raid/raid6/arm/recov_neon_inner.c:100:17: sparse: sparse: undefined identifier 'vx' lib/raid/raid6/arm/recov_neon_inner.c:100:22: sparse: sparse: undefined identifier 'veorq_u8' lib/raid/raid6/arm/recov_neon_inner.c:101:17: sparse: sparse: undefined identifier 'vy' lib/raid/raid6/arm/recov_neon_inner.c:101:22: sparse: sparse: undefined identifier 'veorq_u8' lib/raid/raid6/arm/recov_neon_inner.c:103:17: sparse: sparse: undefined identifier 'vst1q_u8' lib/raid/raid6/arm/recov_neon_inner.c:104:17: sparse: sparse: undefined identifier 'vst1q_u8' lib/raid/raid6/arm/recov_neon_inner.c:107:17: sparse: sparse: undefined identifier 'p' lib/raid/raid6/arm/recov_neon_inner.c:108:17: sparse: sparse: undefined identifier 'q' lib/raid/raid6/arm/recov_neon_inner.c:109:17: sparse: sparse: undefined identifier 'dq' vim +/return +23 lib/raid/raid6/arm/recov_neon_inner.c 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 9 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 10 #ifdef CONFIG_ARM 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 11 /* 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 12 * AArch32 does not provide this intrinsic natively because it does not 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 13 * implement the underlying instruction. AArch32 only provides a 64-bit 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 14 * wide vtbl.8 instruction, so use that instead. 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 15 */ 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 16 static uint8x16_t vqtbl1q_u8(uint8x16_t a, uint8x16_t b) 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 17 { 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 18 union { 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 19 uint8x16_t val; 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 20 uint8x8x2_t pair; 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 21 } __a = { a }; 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 22 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 @23 return vcombine_u8(vtbl2_u8(__a.pair, vget_low_u8(b)), 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 24 vtbl2_u8(__a.pair, vget_high_u8(b))); 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 25 } 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 26 #endif 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 27 :::::: The code at line 23 was first introduced by commit :::::: 6ec4e2514decd6fb4782a9364fa71d6244d05af4 md/raid6: implement recovery using ARM NEON intrinsics :::::: TO: Ard Biesheuvel :::::: CC: Catalin Marinas -- 0-DAY CI Kernel Test Service https://github.com/intel/lkp-tests/wiki