From mboxrd@z Thu Jan 1 00:00:00 1970 Received: from mgamail.intel.com (mgamail.intel.com [192.198.163.10]) (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 ABCC23D092D for ; Tue, 2 Jun 2026 09:50:08 +0000 (UTC) Authentication-Results: smtp.subspace.kernel.org; arc=none smtp.client-ip=192.198.163.10 ARC-Seal:i=1; a=rsa-sha256; d=subspace.kernel.org; s=arc-20240116; t=1780393810; cv=none; b=qZVGmQPks73MD49lWX1vaPDay3+x1Gu5uxLpoDJYTD8S4Lw0QJaWS7mfFqmOj76VxdcffJ+rqYyUM75XssfBwhZRgpdR4dYisF/0OEffMhl0UEDUFg+2rlEEkYkiTPCrsNcyG2tZ1Rgyl8SLLFSphjdUaZKJR68vtiIkLlB16O8= ARC-Message-Signature:i=1; a=rsa-sha256; d=subspace.kernel.org; s=arc-20240116; t=1780393810; c=relaxed/simple; bh=cRmUmqGzOagV/DiSgSXb9SJ5xx8pxSl/60yD/1T0+hc=; h=Date:From:To:Cc:Subject:Message-ID; b=oGDUH6UVi5XV6UwwHDr6EqozC6lyP/z6eBH0zsDOUD0XN3o07u/kXbc7AmZ4WUI2/h0VQ8/5UvKjYwKsVYVWVqDB39OVXW4jwbeGvPPQ6BnKyLWypH3cxUQSbqpchzoeu0MhTuuiWOrKLAsxy3vU0XN08U2uirFoQBlJvUQ37Xc= 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=OINPt0LQ; arc=none smtp.client-ip=192.198.163.10 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="OINPt0LQ" DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/simple; d=intel.com; i=@intel.com; q=dns/txt; s=Intel; t=1780393809; x=1811929809; h=date:from:to:cc:subject:message-id; bh=cRmUmqGzOagV/DiSgSXb9SJ5xx8pxSl/60yD/1T0+hc=; b=OINPt0LQH3/5qAiN0iKnQ4CH9YCCEgohPX7v8yKhNNvFZu1Zn1kiQ6OU LP+ahiLJ7UCj7JMC+iPbNj4VPj1kPp3Y6NJdI7J2+6hiBCTrpzlrJn4Ld dFQCAhTPSo1UW4pISV1xfSVYGElDVnG8mfanOQaNuPW4uRZOhSA7/p2ke 4hysVkUDXr4SEoLl7Idpeqe2whCJyMdkfkm/jqELyttI2sp69LVOiaRWR tk7OMXDc6yGCqTc/q4MKJpXEYX+eO6c+W9lbetP0MJgXVMV8z1Ju2+Uvi 6u52Frho6QJHTO1sk0NX59E07dyZRCjfQMME6mFEaHkkwpx/a7UQneIv3 g==; X-CSE-ConnectionGUID: hq7tipDQQvmK9RAECt+ktQ== X-CSE-MsgGUID: b3AWTukVR/SvHP/Zt3Ks0g== X-IronPort-AV: E=McAfee;i="6800,10657,11804"; a="92556530" X-IronPort-AV: E=Sophos;i="6.24,183,1774335600"; d="scan'208";a="92556530" Received: from orviesa001.jf.intel.com ([10.64.159.141]) by fmvoesa104.fm.intel.com with ESMTP/TLS/ECDHE-RSA-AES256-GCM-SHA384; 02 Jun 2026 02:50:08 -0700 X-CSE-ConnectionGUID: rDFNfdGeQAOMqyI6mDhItQ== X-CSE-MsgGUID: zhGNb/GCRMqDkYiADe/v+w== X-ExtLoop1: 1 X-IronPort-AV: E=Sophos;i="6.24,183,1774335600"; d="scan'208";a="281968460" Received: from lkp-server01.sh.intel.com (HELO f0d55cb201f0) ([10.239.97.150]) by orviesa001.jf.intel.com with ESMTP; 02 Jun 2026 02:50:06 -0700 Received: from kbuild by f0d55cb201f0 with local (Exim 4.98.2) (envelope-from ) id 1wULl6-00000000BpO-02x6; Tue, 02 Jun 2026 09:50:04 +0000 Date: Tue, 02 Jun 2026 17:49:13 +0800 From: kernel test robot To: oe-kbuild@lists.linux.dev Cc: lkp@intel.com, Dan Carpenter Subject: [linux-next:master 8590/9733] lib/raid/raid6/arm/recov_neon_inner.c:51 (null)() warn: statement has no effect 'uint8x16_t' Message-ID: <202606021711.560Eh9WX-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: BCC: lkp@intel.com CC: oe-kbuild-all@lists.linux.dev TO: Christoph Hellwig CC: Andrew Morton CC: Linux Memory Management List tree: https://git.kernel.org/pub/scm/linux/kernel/git/next/linux-next.git master head: 7da7f07112610a520567421dd2ffcb51beaefbcc commit: 3626738bc7147d52cb49f3994a9846aa2d34810a [8590/9733] raid6: move to lib/raid/ :::::: branch date: 3 days ago :::::: commit date: 4 days ago config: arm64-randconfig-r073-20260602 (https://download.01.org/0day-ci/archive/20260602/202606021711.560Eh9WX-lkp@intel.com/config) compiler: clang version 16.0.6 (https://github.com/llvm/llvm-project 7cbf1a2591520c2491aa35339f227775f4d3adf6) smatch: v0.5.0-9185-gbcc58b9c 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 | Reported-by: Dan Carpenter | Closes: https://lore.kernel.org/r/202606021711.560Eh9WX-lkp@intel.com/ New smatch warnings: lib/raid/raid6/arm/recov_neon_inner.c:51 (null)() warn: statement has no effect 'uint8x16_t' Old smatch warnings: lib/raid/raid6/arm/recov_neon_inner.c:93 (null)() warn: statement has no effect 'uint8x16_t' vim +/uint8x16_t +51 lib/raid/raid6/arm/recov_neon_inner.c 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 27 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 28 void __raid6_2data_recov_neon(int bytes, uint8_t *p, uint8_t *q, uint8_t *dp, 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 29 uint8_t *dq, const uint8_t *pbmul, 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 30 const uint8_t *qmul) 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 31 { 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 32 uint8x16_t pm0 = vld1q_u8(pbmul); 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 33 uint8x16_t pm1 = vld1q_u8(pbmul + 16); 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 34 uint8x16_t qm0 = vld1q_u8(qmul); 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 35 uint8x16_t qm1 = vld1q_u8(qmul + 16); 1ad3935b39da78 lib/raid6/recov_neon_inner.c Nick Desaulniers 2019-02-25 36 uint8x16_t x0f = vdupq_n_u8(0x0f); 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 37 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 38 /* 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 39 * while ( bytes-- ) { 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 40 * uint8_t px, qx, db; 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 41 * 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 42 * px = *p ^ *dp; 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 43 * qx = qmul[*q ^ *dq]; 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 44 * *dq++ = db = pbmul[px] ^ qx; 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 45 * *dp++ = db ^ px; 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 46 * p++; q++; 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 47 * } 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 48 */ 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 49 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 50 while (bytes) { 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 @51 uint8x16_t vx, vy, px, qx, db; 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 52 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 53 px = veorq_u8(vld1q_u8(p), vld1q_u8(dp)); 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 54 vx = veorq_u8(vld1q_u8(q), vld1q_u8(dq)); 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 55 335ebe3035b6fc lib/raid6/recov_neon_inner.c Ard Biesheuvel 2019-02-26 56 vy = vshrq_n_u8(vx, 4); 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 57 vx = vqtbl1q_u8(qm0, vandq_u8(vx, x0f)); 335ebe3035b6fc lib/raid6/recov_neon_inner.c Ard Biesheuvel 2019-02-26 58 vy = vqtbl1q_u8(qm1, vy); 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 59 qx = veorq_u8(vx, vy); 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 60 335ebe3035b6fc lib/raid6/recov_neon_inner.c Ard Biesheuvel 2019-02-26 61 vy = vshrq_n_u8(px, 4); 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 62 vx = vqtbl1q_u8(pm0, vandq_u8(px, x0f)); 335ebe3035b6fc lib/raid6/recov_neon_inner.c Ard Biesheuvel 2019-02-26 63 vy = vqtbl1q_u8(pm1, vy); 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 64 vx = veorq_u8(vx, vy); 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 65 db = veorq_u8(vx, qx); 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 66 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 67 vst1q_u8(dq, db); 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 68 vst1q_u8(dp, veorq_u8(db, px)); 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 69 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 70 bytes -= 16; 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 71 p += 16; 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 72 q += 16; 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 73 dp += 16; 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 74 dq += 16; 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 75 } 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 76 } 6ec4e2514decd6 lib/raid6/recov_neon_inner.c Ard Biesheuvel 2017-07-13 77 :::::: The code at line 51 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