From mboxrd@z Thu Jan 1 00:00:00 1970 Return-Path: Received: from mgamail.intel.com (mgamail.intel.com [192.198.163.9]) by sourceware.org (Postfix) with ESMTPS id 5639A3858D38 for ; Mon, 22 Apr 2024 07:52:26 +0000 (GMT) DMARC-Filter: OpenDMARC Filter v1.4.2 sourceware.org 5639A3858D38 Authentication-Results: sourceware.org; dmarc=pass (p=none dis=none) header.from=intel.com Authentication-Results: sourceware.org; spf=pass smtp.mailfrom=intel.com ARC-Filter: OpenARC Filter v1.0.0 sourceware.org 5639A3858D38 Authentication-Results: server2.sourceware.org; arc=pass smtp.remote-ip=192.198.163.9 ARC-Seal: i=2; a=rsa-sha256; d=sourceware.org; s=key; t=1713772352; cv=pass; b=NyeWMp+advpTNNKSEDiqSGxxG4s30LnU0Oy5D0EyVl9ev75YgPDEbF33Cd91jNXJIFuee11XuYoXDRlDrwetdQSYeR9yRShZDQL6FUvQljiIv1nlOhP0F4sjR+z3UUjqt4I/A3gLV0e9Cp3ZAZdfZvg1OAoOnimOVBFQcBUf96U= ARC-Message-Signature: i=2; a=rsa-sha256; d=sourceware.org; s=key; t=1713772352; c=relaxed/simple; bh=UdrGf/83C6EzXpTH8OgMKLTOA+hFvx+J6aZ6jTCu4ro=; h=DKIM-Signature:From:To:Subject:Date:Message-ID:MIME-Version; b=XTcnV31tDGdFITy7+jjf9dPlcu5YTjcL0s6NrrmxdWjU0Ofs9YD6w4++D//twvZvBvX4jdHt/PW7WCuh8bi3c5+iePTXnKvjkYP/90KBm/+LA/H+MqEOC00ZrV3X7GYEAHOJXyVY3jk+rtBVsLDX2BzBPTyWPTyXSI2nBsKx2XQ= ARC-Authentication-Results: i=2; server2.sourceware.org DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/simple; d=intel.com; i=@intel.com; q=dns/txt; s=Intel; t=1713772346; x=1745308346; h=from:to:cc:subject:date:message-id:references: in-reply-to:mime-version; bh=UdrGf/83C6EzXpTH8OgMKLTOA+hFvx+J6aZ6jTCu4ro=; b=M8d+vvEyhQ6UishHw+jeBVhFfowq9qOZmSgy7UlqT6czPsldaNgmK2ad nniMcXrDZWlwTxsWifUa1KJsJ9i9s+m3c4jM4hhj+0j6D+aU/v8+475zx d+pBnF7EyuRYGGur756R6269vtPDYZev9yEjfZ4rlG9U6A/XjOY5dO9zx vNaYBDrIiulwol5g7WTjRHX2YjfMrq8MA0UfEsqeGnbV3yw2np5FkRgJN czcufWhDZHoux3Na0fEFVkT4ynT8TCedqLRCuzst7Kql9099r13SbFpG6 tPb8XiKC7LPZ5esP2cPBWxoc+s09235XKvfPUokZLQ8t9xZd47ihTE/ka w==; X-CSE-ConnectionGUID: hT1hws76TtK4SWy0n1dI8g== X-CSE-MsgGUID: ADTU9OGXRTWIOvLisF1Q/g== X-IronPort-AV: E=McAfee;i="6600,9927,11051"; a="19990941" X-IronPort-AV: E=Sophos;i="6.07,220,1708416000"; d="scan'208,217";a="19990941" Received: from fmviesa010.fm.intel.com ([10.60.135.150]) by fmvoesa103.fm.intel.com with ESMTP/TLS/ECDHE-RSA-AES256-GCM-SHA384; 22 Apr 2024 00:52:25 -0700 X-CSE-ConnectionGUID: M7PW41mzQBORipdDTE5eaQ== X-CSE-MsgGUID: QUaqjxOvT9W6Ns0l8wTkOA== X-ExtLoop1: 1 X-IronPort-AV: E=Sophos;i="6.07,220,1708416000"; d="scan'208,217";a="23981035" Received: from fmsmsx601.amr.corp.intel.com ([10.18.126.81]) by fmviesa010.fm.intel.com with ESMTP/TLS/AES256-GCM-SHA384; 22 Apr 2024 00:52:25 -0700 Received: from fmsmsx611.amr.corp.intel.com (10.18.126.91) by fmsmsx601.amr.corp.intel.com (10.18.126.81) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_128_GCM_SHA256) id 15.1.2507.35; Mon, 22 Apr 2024 00:52:24 -0700 Received: from fmsmsx601.amr.corp.intel.com (10.18.126.81) by fmsmsx611.amr.corp.intel.com (10.18.126.91) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_128_GCM_SHA256) id 15.1.2507.35; Mon, 22 Apr 2024 00:52:23 -0700 Received: from fmsedg602.ED.cps.intel.com (10.1.192.136) by fmsmsx601.amr.corp.intel.com (10.18.126.81) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_128_GCM_SHA256) id 15.1.2507.35 via Frontend Transport; Mon, 22 Apr 2024 00:52:23 -0700 Received: from NAM10-MW2-obe.outbound.protection.outlook.com (104.47.55.100) by edgegateway.intel.com (192.55.55.71) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.1.2507.35; Mon, 22 Apr 2024 00:52:23 -0700 ARC-Seal: i=1; a=rsa-sha256; s=arcselector9901; d=microsoft.com; cv=none; b=aTzJkloredud/iIa6zqIfMnYYykRzMesPUu6xUJcPGks2cTcroh9IADAyjhf43ewuQtgMi4SJK1pmfp4WwplMqfxlWWe2lplDbbGKzlHlVMnofDvIxB9xy4GVsu5F984Ut/URwfF5oVQd9IZ9sjol1nICjcMk3MUGfx7Y7naPi9q1eXEFwhk9YnajKiepOVDGzSseYUglOcVdiBSFAKZVzEqpqzgSUlCoixod1F3TRwoQ8IZhgUWAC6OksQCDOwkV86+0ammLmvpwC8zb8Bv/rUZtdMdWsufKkLibdFPB3ee0gNv7Z5VcTiDlyObZ6EfqMUYE2OE2weq9NJJC59j6g== ARC-Message-Signature: i=1; a=rsa-sha256; c=relaxed/relaxed; d=microsoft.com; s=arcselector9901; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-AntiSpam-MessageData-ChunkCount:X-MS-Exchange-AntiSpam-MessageData-0:X-MS-Exchange-AntiSpam-MessageData-1; bh=POBEft+6+BTgECKxLfg+vaAN8qMathkT105VRqONbBs=; b=LbVWcPY0Abq/g7r5NtT1dTMyID8pXupKrTSQqkkF+w1Wav/FHbIOunpLm2YOOCW+zfHgM1tYcPF2T1MIx/1e3BVcEhXxJIdx7U8GDOwPYj1+usKdWJ8XcNMVeuvXRYsm7CGFUWUyDLVKBHlhcEjQVHlnmE1p0TUoVn6DO1KmlOU7ntIgdeoEuD87yLHTHifRAK4UpULMN77k8CzrGsOW1akhzlxSAMqRKVBbmUI7Xr3yMnCFQN26ZJ5hiEWguLoCRrX1/jANloKfHq+56zjfZwqiqrumhnxOjcRfv+en7Zuzscj9OBPCQbuX6etFat+SYhffxoSkF31FF0FxPy1HYA== ARC-Authentication-Results: i=1; mx.microsoft.com 1; spf=pass smtp.mailfrom=intel.com; dmarc=pass action=none header.from=intel.com; dkim=pass header.d=intel.com; arc=none Received: from MW5PR11MB5908.namprd11.prod.outlook.com (2603:10b6:303:194::10) by PH7PR11MB6606.namprd11.prod.outlook.com (2603:10b6:510:1b1::12) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.7519.20; Mon, 22 Apr 2024 07:52:20 +0000 Received: from MW5PR11MB5908.namprd11.prod.outlook.com ([fe80::aaa8:bc22:5fb0:5ed0]) by MW5PR11MB5908.namprd11.prod.outlook.com ([fe80::aaa8:bc22:5fb0:5ed0%5]) with mapi id 15.20.7519.018; Mon, 22 Apr 2024 07:52:20 +0000 From: "Li, Pan2" To: "juzhe.zhong@rivai.ai" , gcc-patches CC: kito.cheng , Robin Dapp Subject: RE: [PATCH v2] RISC-V: Add xfail test case for indexed load overlap with SRC EEW < DEST EEW Thread-Topic: [PATCH v2] RISC-V: Add xfail test case for indexed load overlap with SRC EEW < DEST EEW Thread-Index: AQHalIjO2BbxKAT7ek6dwDK+jOiLVrFz6P2KgAAB5HA= Date: Mon, 22 Apr 2024 07:52:20 +0000 Message-ID: References: <20240422074330.1403339-1-pan2.li@intel.com> <295E2E736D1397D6+202404221544184842703@rivai.ai> In-Reply-To: <295E2E736D1397D6+202404221544184842703@rivai.ai> Accept-Language: en-US Content-Language: en-US X-MS-Has-Attach: X-MS-TNEF-Correlator: authentication-results: dkim=none (message not signed) header.d=none;dmarc=none action=none header.from=intel.com; x-ms-publictraffictype: Email x-ms-traffictypediagnostic: MW5PR11MB5908:EE_|PH7PR11MB6606:EE_ x-ms-office365-filtering-correlation-id: 25ddc254-7d3e-4c43-b8c4-08dc62a12373 x-ms-exchange-senderadcheck: 1 x-ms-exchange-antispam-relay: 0 x-microsoft-antispam: BCL:0;ARA:13230031|376005|1800799015|366007|38070700009; x-microsoft-antispam-message-info: =?us-ascii?Q?qZlNoXafh7+ZhEP+wYsd6OBoKd5hsSZnpNhKYDhiByCqtLGy/lXRz0XdNNMv?= =?us-ascii?Q?0XlU0YMN3hkHvF5NA/dAVQKNY0mLEeLO75MrK/5BMci9RvG1YDeHrILBTdZy?= =?us-ascii?Q?XiyxlClRyVpIWcGPYSCejJLihczp2CWGtCJLRmaLi78PzY1/QadjOYJ52yTi?= =?us-ascii?Q?4iDEWqe7Ly10Yu1E+0hcY3kyO5+O9SC4d5zJqTnx430PdhqVUiIzQ3EdCmPo?= =?us-ascii?Q?t8xwtZUUSTJg8bkfFWkP2k2vIzbrgTvv/SKDazfQsv+JsaSG82VpD0X+Xm5v?= =?us-ascii?Q?0I5kokg0uu5eeyoTnMZD616o/rphqTFFhgNgdL6l1h3Xk2S55rqihMgslpZP?= =?us-ascii?Q?BST9TYVd8EPjpPNlrHWeaDR+4iqUTKNzc2xSW4883yReFOLWJE+ocdgxjzPa?= =?us-ascii?Q?bVy5Rim730NyAPzWWpGMLC3VqwUnXUvHLSf4L34t9IA/xNNz3N2xFkS8Bw5I?= =?us-ascii?Q?QKhnH2FHFN1VGL8f3PZxJA4XzZOi6VZoG/2+MWWVR/Y0AQKUrMnmVHU8YEG0?= =?us-ascii?Q?rvujA2AdzsKAfpx5tfws9UBtT/nnhUBeRMhboUxh1xU//UOehtAiV+guwttD?= =?us-ascii?Q?AuqT5iFpPpHVYRdXT0Q9uXWnQ4ZHX7HMsNUWxzVBlVOWw+TCpq2L88uMonQF?= =?us-ascii?Q?5t3ZpDPPGlRMFkM4cLoouKroClSUxB1myEykza9xLqzMUQfFkq+LmbBmP2kL?= =?us-ascii?Q?4ti4mns+qC9mPtoUK3LGdm2A85x/n7GXEFnKOzv6mlwl7L4wNgO1TkpPp2d0?= =?us-ascii?Q?5PkndquKgnlbTbZUlEfqPedKxdRtnvWqUlxgOZera197fTLHwjHnWEYe86t2?= =?us-ascii?Q?sXYJKv/4B728b02VKA/bNswXj0PfkxHoeyNXZLpTU7FFTNTUSxdRTLG0BTDc?= =?us-ascii?Q?TKfZ0MwhwkyCUmAb0LIV+QI35iG+iTVNid4zm43DNR5pFWKteU1z7B/B+2jR?= =?us-ascii?Q?5zyDlSU9yStGK7Dl1jCsc9D58u8W8DdkSh6R/rYyMXWxKyOkjRre3lclJynP?= =?us-ascii?Q?ynkyYgKxPqAXgyNdl7dNu5XluIzVE+CTGeoQh8B5abVzQUG6BtiYTm85PBXs?= =?us-ascii?Q?uxnBBjKF9rQSp2HgtjKZU+Gqs1Fe56HTZekzl+wD2Jy1fiaS0uCu4h+Ti7xv?= =?us-ascii?Q?gUnVSo8REz7ZlO5fKXeweZhCGDs84hGsS315iy2a4Xmrj3RISexgkcd0eIOa?= =?us-ascii?Q?2DgaowXdVuJBbXjIDLLCuyJuzzanuONS4A7SDh6spq09wiyCu7EYI9KCvfb+?= =?us-ascii?Q?qUJjOK6lreE7QiUcPAJ/wsIayRF8V3UFzdf4O8nhFR9+66EtOpCwO95Sq0Rz?= =?us-ascii?Q?4D4=3D?= x-forefront-antispam-report: CIP:255.255.255.255;CTRY:;LANG:en;SCL:1;SRV:;IPV:NLI;SFV:NSPM;H:MW5PR11MB5908.namprd11.prod.outlook.com;PTR:;CAT:NONE;SFS:(13230031)(376005)(1800799015)(366007)(38070700009);DIR:OUT;SFP:1101; x-ms-exchange-antispam-messagedata-chunkcount: 1 x-ms-exchange-antispam-messagedata-0: =?us-ascii?Q?PnuGxrtnSqc3cm1c31XKbEWlkCyLC2St0rw+tKTu43fmHTTA1pGGLdkgoYWm?= =?us-ascii?Q?PC6EXYqgKiSebkFdF8xlIz4Z9cTINqp/AgmZo/SNM+nNkB+5fwKXrwAvfG0V?= =?us-ascii?Q?zFURkAah6ZlJbnTjqh0MVf7Omn0o1wzYdgj3knrNN0bxvFOJgTEM+Q5rMIPo?= =?us-ascii?Q?1rNt9gniD52fHFefXo52dFx1D3nJrlMQ8fkDkB6P8cuXlMW0eqSiFOGj78bg?= =?us-ascii?Q?mXsGjbhwP3e0dUUg7Cn60mUGRejkMkHvOtEQWuG9sMTNKBUJpTVrbiscYJm9?= =?us-ascii?Q?T+oSJgRS6vR/YRrrZWzy7Xl+aPhRp6BiLrrO7rSqQOaz9a+cksPOEV32NO36?= =?us-ascii?Q?n452uouiSMTvLN6xhwx9vz/FbgsrOYKO+g5Zlo5OvRcHWrNY6rldQ4Z6vhLP?= =?us-ascii?Q?ntq3LZftKAS14ZeeqmoxFO1Qu4ZWNYinhL9w4m6GWfou0F17tHpJGqgkhdxM?= =?us-ascii?Q?E1i21kbyS2QuwH5tzGe36X6M+3Ugn4fKI/4zJoG/S9Qk6qE05f6sosjFYRHZ?= =?us-ascii?Q?J8B/Te7JYSwItV0b8s8x9tZpfDmuw7ZBjIVDEV4vn8MDO29xG8XEIPjYrEoD?= =?us-ascii?Q?xyDrYp25kvVTIM6NseZ98rOBR9elgAS2YhDBifYOx9U6JRR3itU3VvpDwqU8?= =?us-ascii?Q?UbI5xAoy4nafhmO8uXK+e/Vl6Ped4OL3rYxO4I8T8gndXzqAMDvZQ6XGnmrQ?= =?us-ascii?Q?n+U361AQ1pJ93UOAa6tSQVofpDRJYKbuvtJFCd1e49FVlF6YvJECuc8/ZEIz?= =?us-ascii?Q?5EW3XeGk555YUmU+/rjTgEvybp70ES9J5hj00VnV+hBUxbQP7RlKNGLgcbuM?= =?us-ascii?Q?GCoA4qB2v2ufnBP3aWMrevyJ22RN4pDtamblbDr7aZUDivR/qYcEgrPYjxYv?= =?us-ascii?Q?Q89SPkUNoE58bI/jep5Cxf8+Ru+/NwW4DsqDKPR+au2u/3SM0OUE2rFPpyNU?= =?us-ascii?Q?RrSPmFW89r2Gf8bRS4VXRN70aK+qwf8GMF9kFkmDIIU9rrXSk8BtVWFl8e8Z?= =?us-ascii?Q?tqOzhRIja0I5jNRnhsvkdRkh256XabZ7CTIQGnd/eAymUD6Xtez29DbN17mr?= =?us-ascii?Q?vBqlSQRoeJzK+b/95Vbj8zAxUxmUiOxUiIhhpBG+3sIwPZumePRAVKxD0Tl8?= =?us-ascii?Q?zbOrw68nVkJNjoEwUI9OZmE7hakMdvL/q1XJGtcJv4mTJh1OMlLjZC4hsGIG?= =?us-ascii?Q?YFuI773oetAFHWK14FcguoEMZw3eE/JEmcNKNqCs+yVLWg4do6tFZt3DdXKM?= =?us-ascii?Q?tAkwtA6vHFmgDjURxB7eq5IAPTAwrdsWOVJNj0kBuenzvANZ956oXwiNFiP1?= =?us-ascii?Q?xJ7ysmtYALJDMK5XSHgse+f1/eUIy0yHBTkAp3k8c+KrMpfXSjtfBTdWtV7a?= =?us-ascii?Q?M8T387wqrSFUxL8oZuPA+TQgocFuf0k6N/379y7loziCRFu8Obo4QRzur6fM?= =?us-ascii?Q?koF6yRe37UrSjg6ATOGJ65HMovphx2h/PlnJAXoxEVNxcwnUC7uVO/MKwhah?= =?us-ascii?Q?k7oIADQJdsOSF934q0kiB1YZB1BfvBCknHz3ft4c+HJf5jCjOVLWANzORdeT?= =?us-ascii?Q?HKaloNayMEoLy1DevUg=3D?= Content-Type: multipart/alternative; boundary="_000_MW5PR11MB590881B666DE8883A818AF43A9122MW5PR11MB5908namp_" MIME-Version: 1.0 X-MS-Exchange-CrossTenant-AuthAs: Internal X-MS-Exchange-CrossTenant-AuthSource: MW5PR11MB5908.namprd11.prod.outlook.com X-MS-Exchange-CrossTenant-Network-Message-Id: 25ddc254-7d3e-4c43-b8c4-08dc62a12373 X-MS-Exchange-CrossTenant-originalarrivaltime: 22 Apr 2024 07:52:20.3317 (UTC) X-MS-Exchange-CrossTenant-fromentityheader: Hosted X-MS-Exchange-CrossTenant-id: 46c98d88-e344-4ed4-8496-4ed7712e255d X-MS-Exchange-CrossTenant-mailboxtype: HOSTED X-MS-Exchange-CrossTenant-userprincipalname: GuQbH3paJJ9zi/ruUi9rOffD6HQ1xA0zzgxxaOU/kjHOrvJmDWh5ZO43G84vbz1AOVq30pQonH+EZ9P84hzeAw== X-MS-Exchange-Transport-CrossTenantHeadersStamped: PH7PR11MB6606 X-OriginatorOrg: intel.com X-Spam-Status: No, score=-12.5 required=5.0 tests=BAYES_00,DKIMWL_WL_HIGH,DKIM_SIGNED,DKIM_VALID,DKIM_VALID_AU,DKIM_VALID_EF,GIT_PATCH_0,HTML_MESSAGE,KAM_SHORT,SPF_HELO_NONE,SPF_NONE,TXREP autolearn=ham autolearn_force=no version=3.4.6 X-Spam-Checker-Version: SpamAssassin 3.4.6 (2021-04-09) on server2.sourceware.org List-Id: --_000_MW5PR11MB590881B666DE8883A818AF43A9122MW5PR11MB5908namp_ Content-Type: text/plain; charset="us-ascii" Content-Transfer-Encoding: quoted-printable Committed, thanks Juzhe. Pan From: juzhe.zhong@rivai.ai Sent: Monday, April 22, 2024 3:44 PM To: Li, Pan2 ; gcc-patches Cc: kito.cheng ; Robin Dapp ; Li= , Pan2 Subject: Re: [PATCH v2] RISC-V: Add xfail test case for indexed load overla= p with SRC EEW < DEST EEW LGTM ________________________________ juzhe.zhong@rivai.ai From: pan2.li Date: 2024-04-22 15:43 To: gcc-patches CC: juzhe.zhong; kito.cheng; rdapp.gcc; Pan Li Subject: [PATCH v2] RISC-V: Add xfail test case for indexed load overlap wi= th SRC EEW < DEST EEW From: Pan Li > Update in v2: * Add change log to pr112431-34.c. Original log: We reverted below patch for register group overlap, add the related insn test and mark it as xfail. And we will remove the xfail after we support the register overlap in GCC-15. 4418d55bcd1 RISC-V: Support highpart overlap for indexed load with SRC EEW = < DEST EEW The below test suites are passed. * The rv64gcv fully regression test. gcc/testsuite/ChangeLog: * gcc.target/riscv/rvv/base/pr112431-34.c: Remove xfail for vluxei8 check. * gcc.target/riscv/rvv/base/pr112431-28.c: New test. * gcc.target/riscv/rvv/base/pr112431-29.c: New test. * gcc.target/riscv/rvv/base/pr112431-30.c: New test. * gcc.target/riscv/rvv/base/pr112431-31.c: New test. * gcc.target/riscv/rvv/base/pr112431-32.c: New test. * gcc.target/riscv/rvv/base/pr112431-33.c: New test. Signed-off-by: Pan Li > --- .../gcc.target/riscv/rvv/base/pr112431-28.c | 104 ++++++++++++++++++ .../gcc.target/riscv/rvv/base/pr112431-29.c | 68 ++++++++++++ .../gcc.target/riscv/rvv/base/pr112431-30.c | 51 +++++++++ .../gcc.target/riscv/rvv/base/pr112431-31.c | 68 ++++++++++++ .../gcc.target/riscv/rvv/base/pr112431-32.c | 51 +++++++++ .../gcc.target/riscv/rvv/base/pr112431-33.c | 51 +++++++++ .../gcc.target/riscv/rvv/base/pr112431-34.c | 2 +- 7 files changed, 394 insertions(+), 1 deletion(-) create mode 100644 gcc/testsuite/gcc.target/riscv/rvv/base/pr112431-28.c create mode 100644 gcc/testsuite/gcc.target/riscv/rvv/base/pr112431-29.c create mode 100644 gcc/testsuite/gcc.target/riscv/rvv/base/pr112431-30.c create mode 100644 gcc/testsuite/gcc.target/riscv/rvv/base/pr112431-31.c create mode 100644 gcc/testsuite/gcc.target/riscv/rvv/base/pr112431-32.c create mode 100644 gcc/testsuite/gcc.target/riscv/rvv/base/pr112431-33.c diff --git a/gcc/testsuite/gcc.target/riscv/rvv/base/pr112431-28.c b/gcc/te= stsuite/gcc.target/riscv/rvv/base/pr112431-28.c new file mode 100644 index 00000000000..c16cbdfe9f9 --- /dev/null +++ b/gcc/testsuite/gcc.target/riscv/rvv/base/pr112431-28.c @@ -0,0 +1,104 @@ +/* { dg-do compile } */ +/* { dg-options "-march=3Drv64gcv -mabi=3Dlp64d -O3" } */ + +#include "riscv_vector.h" + +size_t __attribute__ ((noinline)) +sumation (size_t sum0, size_t sum1, size_t sum2, size_t sum3, size_t sum4, + size_t sum5, size_t sum6, size_t sum7, size_t sum8, size_t sum9, + size_t sum10, size_t sum11, size_t sum12, size_t sum13, size_t sum14, + size_t sum15) +{ + return sum0 + sum1 + sum2 + sum3 + sum4 + sum5 + sum6 + sum7 + sum8 + su= m9 + + sum10 + sum11 + sum12 + sum13 + sum14 + sum15; +} + +size_t +foo (char const *buf, size_t len) +{ + size_t sum =3D 0; + size_t vl =3D __riscv_vsetvlmax_e8m8 (); + size_t step =3D vl * 4; + const char *it =3D buf, *end =3D buf + len; + for (; it + step <=3D end;) + { + vuint8m1_t v0 =3D __riscv_vle8_v_u8m1 ((void *) it, vl); + it +=3D vl; + vuint8m1_t v1 =3D __riscv_vle8_v_u8m1 ((void *) it, vl); + it +=3D vl; + vuint8m1_t v2 =3D __riscv_vle8_v_u8m1 ((void *) it, vl); + it +=3D vl; + vuint8m1_t v3 =3D __riscv_vle8_v_u8m1 ((void *) it, vl); + it +=3D vl; + vuint8m1_t v4 =3D __riscv_vle8_v_u8m1 ((void *) it, vl); + it +=3D vl; + vuint8m1_t v5 =3D __riscv_vle8_v_u8m1 ((void *) it, vl); + it +=3D vl; + vuint8m1_t v6 =3D __riscv_vle8_v_u8m1 ((void *) it, vl); + it +=3D vl; + vuint8m1_t v7 =3D __riscv_vle8_v_u8m1 ((void *) it, vl); + it +=3D vl; + vuint8m1_t v8 =3D __riscv_vle8_v_u8m1 ((void *) it, vl); + it +=3D vl; + vuint8m1_t v9 =3D __riscv_vle8_v_u8m1 ((void *) it, vl); + it +=3D vl; + vuint8m1_t v10 =3D __riscv_vle8_v_u8m1 ((void *) it, vl); + it +=3D vl; + vuint8m1_t v11 =3D __riscv_vle8_v_u8m1 ((void *) it, vl); + it +=3D vl; + vuint8m1_t v12 =3D __riscv_vle8_v_u8m1 ((void *) it, vl); + it +=3D vl; + vuint8m1_t v13 =3D __riscv_vle8_v_u8m1 ((void *) it, vl); + it +=3D vl; + vuint8m1_t v14 =3D __riscv_vle8_v_u8m1 ((void *) it, vl); + it +=3D vl; + vuint8m1_t v15 =3D __riscv_vle8_v_u8m1 ((void *) it, vl); + it +=3D vl; + + asm volatile("nop" ::: "memory"); + vint16m2_t vw0 =3D __riscv_vluxei8_v_i16m2 ((void *) it, v0, vl); + vint16m2_t vw1 =3D __riscv_vluxei8_v_i16m2 ((void *) it, v1, vl); + vint16m2_t vw2 =3D __riscv_vluxei8_v_i16m2 ((void *) it, v2, vl); + vint16m2_t vw3 =3D __riscv_vluxei8_v_i16m2 ((void *) it, v3, vl); + vint16m2_t vw4 =3D __riscv_vluxei8_v_i16m2 ((void *) it, v4, vl); + vint16m2_t vw5 =3D __riscv_vluxei8_v_i16m2 ((void *) it, v5, vl); + vint16m2_t vw6 =3D __riscv_vluxei8_v_i16m2 ((void *) it, v6, vl); + vint16m2_t vw7 =3D __riscv_vluxei8_v_i16m2 ((void *) it, v7, vl); + vint16m2_t vw8 =3D __riscv_vluxei8_v_i16m2 ((void *) it, v8, vl); + vint16m2_t vw9 =3D __riscv_vluxei8_v_i16m2 ((void *) it, v9, vl); + vint16m2_t vw10 =3D __riscv_vluxei8_v_i16m2 ((void *) it, v10, vl); + vint16m2_t vw11 =3D __riscv_vluxei8_v_i16m2 ((void *) it, v11, vl); + vint16m2_t vw12 =3D __riscv_vluxei8_v_i16m2 ((void *) it, v12, vl); + vint16m2_t vw13 =3D __riscv_vluxei8_v_i16m2 ((void *) it, v13, vl); + vint16m2_t vw14 =3D __riscv_vluxei8_v_i16m2 ((void *) it, v14, vl); + vint16m2_t vw15 =3D __riscv_vluxei8_v_i16m2 ((void *) it, v15, vl); + + asm volatile("nop" ::: "memory"); + size_t sum0 =3D __riscv_vmv_x_s_i16m2_i16 (vw0); + size_t sum1 =3D __riscv_vmv_x_s_i16m2_i16 (vw1); + size_t sum2 =3D __riscv_vmv_x_s_i16m2_i16 (vw2); + size_t sum3 =3D __riscv_vmv_x_s_i16m2_i16 (vw3); + size_t sum4 =3D __riscv_vmv_x_s_i16m2_i16 (vw4); + size_t sum5 =3D __riscv_vmv_x_s_i16m2_i16 (vw5); + size_t sum6 =3D __riscv_vmv_x_s_i16m2_i16 (vw6); + size_t sum7 =3D __riscv_vmv_x_s_i16m2_i16 (vw7); + size_t sum8 =3D __riscv_vmv_x_s_i16m2_i16 (vw8); + size_t sum9 =3D __riscv_vmv_x_s_i16m2_i16 (vw9); + size_t sum10 =3D __riscv_vmv_x_s_i16m2_i16 (vw10); + size_t sum11 =3D __riscv_vmv_x_s_i16m2_i16 (vw11); + size_t sum12 =3D __riscv_vmv_x_s_i16m2_i16 (vw12); + size_t sum13 =3D __riscv_vmv_x_s_i16m2_i16 (vw13); + size_t sum14 =3D __riscv_vmv_x_s_i16m2_i16 (vw14); + size_t sum15 =3D __riscv_vmv_x_s_i16m2_i16 (vw15); + + sum +=3D sumation (sum0, sum1, sum2, sum3, sum4, sum5, sum6, sum7, s= um8, + sum9, sum10, sum11, sum12, sum13, sum14, sum15); + } + return sum; +} + +/* { dg-final { scan-assembler-not {vmv1r} } } */ +/* { dg-final { scan-assembler-not {vmv2r} } } */ +/* { dg-final { scan-assembler-not {vmv4r} } } */ +/* { dg-final { scan-assembler-not {vmv8r} } } */ +/* { dg-final { scan-assembler-not {csrr} { xfail riscv*-*-* } } } */ diff --git a/gcc/testsuite/gcc.target/riscv/rvv/base/pr112431-29.c b/gcc/te= stsuite/gcc.target/riscv/rvv/base/pr112431-29.c new file mode 100644 index 00000000000..cee6afafe87 --- /dev/null +++ b/gcc/testsuite/gcc.target/riscv/rvv/base/pr112431-29.c @@ -0,0 +1,68 @@ +/* { dg-do compile } */ +/* { dg-options "-march=3Drv64gcv -mabi=3Dlp64d -O3" } */ + +#include "riscv_vector.h" + +size_t __attribute__ ((noinline)) +sumation (size_t sum0, size_t sum1, size_t sum2, size_t sum3, size_t sum4, + size_t sum5, size_t sum6, size_t sum7) +{ + return sum0 + sum1 + sum2 + sum3 + sum4 + sum5 + sum6 + sum7; +} + +size_t +foo (char const *buf, size_t len) +{ + size_t sum =3D 0; + size_t vl =3D __riscv_vsetvlmax_e8m8 (); + size_t step =3D vl * 4; + const char *it =3D buf, *end =3D buf + len; + for (; it + step <=3D end;) + { + vuint8m2_t v0 =3D __riscv_vle8_v_u8m2 ((void *) it, vl); + it +=3D vl; + vuint8m2_t v1 =3D __riscv_vle8_v_u8m2 ((void *) it, vl); + it +=3D vl; + vuint8m2_t v2 =3D __riscv_vle8_v_u8m2 ((void *) it, vl); + it +=3D vl; + vuint8m2_t v3 =3D __riscv_vle8_v_u8m2 ((void *) it, vl); + it +=3D vl; + vuint8m2_t v4 =3D __riscv_vle8_v_u8m2 ((void *) it, vl); + it +=3D vl; + vuint8m2_t v5 =3D __riscv_vle8_v_u8m2 ((void *) it, vl); + it +=3D vl; + vuint8m2_t v6 =3D __riscv_vle8_v_u8m2 ((void *) it, vl); + it +=3D vl; + vuint8m2_t v7 =3D __riscv_vle8_v_u8m2 ((void *) it, vl); + it +=3D vl; + + asm volatile("nop" ::: "memory"); + vint16m4_t vw0 =3D __riscv_vluxei8_v_i16m4 ((void *) it, v0, vl); + vint16m4_t vw1 =3D __riscv_vluxei8_v_i16m4 ((void *) it, v1, vl); + vint16m4_t vw2 =3D __riscv_vluxei8_v_i16m4 ((void *) it, v2, vl); + vint16m4_t vw3 =3D __riscv_vluxei8_v_i16m4 ((void *) it, v3, vl); + vint16m4_t vw4 =3D __riscv_vluxei8_v_i16m4 ((void *) it, v4, vl); + vint16m4_t vw5 =3D __riscv_vluxei8_v_i16m4 ((void *) it, v5, vl); + vint16m4_t vw6 =3D __riscv_vluxei8_v_i16m4 ((void *) it, v6, vl); + vint16m4_t vw7 =3D __riscv_vluxei8_v_i16m4 ((void *) it, v7, vl); + + asm volatile("nop" ::: "memory"); + size_t sum0 =3D __riscv_vmv_x_s_i16m4_i16 (vw0); + size_t sum1 =3D __riscv_vmv_x_s_i16m4_i16 (vw1); + size_t sum2 =3D __riscv_vmv_x_s_i16m4_i16 (vw2); + size_t sum3 =3D __riscv_vmv_x_s_i16m4_i16 (vw3); + size_t sum4 =3D __riscv_vmv_x_s_i16m4_i16 (vw4); + size_t sum5 =3D __riscv_vmv_x_s_i16m4_i16 (vw5); + size_t sum6 =3D __riscv_vmv_x_s_i16m4_i16 (vw6); + size_t sum7 =3D __riscv_vmv_x_s_i16m4_i16 (vw7); + + sum +=3D sumation (sum0, sum1, sum2, sum3, sum4, sum5, sum6, sum7); + } + return sum; +} + +/* { dg-final { scan-assembler-not {vmv1r} } } */ +/* { dg-final { scan-assembler-not {vmv2r} } } */ +/* { dg-final { scan-assembler-not {vmv4r} } } */ +/* { dg-final { scan-assembler-not {vmv8r} } } */ +/* { dg-final { scan-assembler-not {csrr} { xfail riscv*-*-* } } } */ diff --git a/gcc/testsuite/gcc.target/riscv/rvv/base/pr112431-30.c b/gcc/te= stsuite/gcc.target/riscv/rvv/base/pr112431-30.c new file mode 100644 index 00000000000..f2e23628022 --- /dev/null +++ b/gcc/testsuite/gcc.target/riscv/rvv/base/pr112431-30.c @@ -0,0 +1,51 @@ +/* { dg-do compile } */ +/* { dg-options "-march=3Drv64gcv -mabi=3Dlp64d -O3" } */ + +#include "riscv_vector.h" + +size_t __attribute__ ((noinline)) +sumation (size_t sum0, size_t sum1, size_t sum2, size_t sum3) +{ + return sum0 + sum1 + sum2 + sum3; +} + +size_t +foo (char const *buf, size_t len) +{ + size_t sum =3D 0; + size_t vl =3D __riscv_vsetvlmax_e8m8 (); + size_t step =3D vl * 4; + const char *it =3D buf, *end =3D buf + len; + for (; it + step <=3D end;) + { + vuint8m4_t v0 =3D __riscv_vle8_v_u8m4 ((void *) it, vl); + it +=3D vl; + vuint8m4_t v1 =3D __riscv_vle8_v_u8m4 ((void *) it, vl); + it +=3D vl; + vuint8m4_t v2 =3D __riscv_vle8_v_u8m4 ((void *) it, vl); + it +=3D vl; + vuint8m4_t v3 =3D __riscv_vle8_v_u8m4 ((void *) it, vl); + it +=3D vl; + + asm volatile("nop" ::: "memory"); + vint16m8_t vw0 =3D __riscv_vluxei8_v_i16m8 ((void *) it, v0, vl); + vint16m8_t vw1 =3D __riscv_vluxei8_v_i16m8 ((void *) it, v1, vl); + vint16m8_t vw2 =3D __riscv_vluxei8_v_i16m8 ((void *) it, v2, vl); + vint16m8_t vw3 =3D __riscv_vluxei8_v_i16m8 ((void *) it, v3, vl); + + asm volatile("nop" ::: "memory"); + size_t sum0 =3D __riscv_vmv_x_s_i16m8_i16 (vw0); + size_t sum1 =3D __riscv_vmv_x_s_i16m8_i16 (vw1); + size_t sum2 =3D __riscv_vmv_x_s_i16m8_i16 (vw2); + size_t sum3 =3D __riscv_vmv_x_s_i16m8_i16 (vw3); + + sum +=3D sumation (sum0, sum1, sum2, sum3); + } + return sum; +} + +/* { dg-final { scan-assembler-not {vmv1r} } } */ +/* { dg-final { scan-assembler-not {vmv2r} } } */ +/* { dg-final { scan-assembler-not {vmv4r} } } */ +/* { dg-final { scan-assembler-not {vmv8r} } } */ +/* { dg-final { scan-assembler-not {csrr} { xfail riscv*-*-* } } } */ diff --git a/gcc/testsuite/gcc.target/riscv/rvv/base/pr112431-31.c b/gcc/te= stsuite/gcc.target/riscv/rvv/base/pr112431-31.c new file mode 100644 index 00000000000..2cf006bd4c9 --- /dev/null +++ b/gcc/testsuite/gcc.target/riscv/rvv/base/pr112431-31.c @@ -0,0 +1,68 @@ +/* { dg-do compile } */ +/* { dg-options "-march=3Drv64gcv -mabi=3Dlp64d -O3" } */ + +#include "riscv_vector.h" + +size_t __attribute__ ((noinline)) +sumation (size_t sum0, size_t sum1, size_t sum2, size_t sum3, size_t sum4, + size_t sum5, size_t sum6, size_t sum7) +{ + return sum0 + sum1 + sum2 + sum3 + sum4 + sum5 + sum6 + sum7; +} + +size_t +foo (char const *buf, size_t len) +{ + size_t sum =3D 0; + size_t vl =3D __riscv_vsetvlmax_e8m8 (); + size_t step =3D vl * 4; + const char *it =3D buf, *end =3D buf + len; + for (; it + step <=3D end;) + { + vuint8m1_t v0 =3D __riscv_vle8_v_u8m1 ((void *) it, vl); + it +=3D vl; + vuint8m1_t v1 =3D __riscv_vle8_v_u8m1 ((void *) it, vl); + it +=3D vl; + vuint8m1_t v2 =3D __riscv_vle8_v_u8m1 ((void *) it, vl); + it +=3D vl; + vuint8m1_t v3 =3D __riscv_vle8_v_u8m1 ((void *) it, vl); + it +=3D vl; + vuint8m1_t v4 =3D __riscv_vle8_v_u8m1 ((void *) it, vl); + it +=3D vl; + vuint8m1_t v5 =3D __riscv_vle8_v_u8m1 ((void *) it, vl); + it +=3D vl; + vuint8m1_t v6 =3D __riscv_vle8_v_u8m1 ((void *) it, vl); + it +=3D vl; + vuint8m1_t v7 =3D __riscv_vle8_v_u8m1 ((void *) it, vl); + it +=3D vl; + + asm volatile("nop" ::: "memory"); + vint32m4_t vw0 =3D __riscv_vluxei8_v_i32m4 ((void *) it, v0, vl); + vint32m4_t vw1 =3D __riscv_vluxei8_v_i32m4 ((void *) it, v1, vl); + vint32m4_t vw2 =3D __riscv_vluxei8_v_i32m4 ((void *) it, v2, vl); + vint32m4_t vw3 =3D __riscv_vluxei8_v_i32m4 ((void *) it, v3, vl); + vint32m4_t vw4 =3D __riscv_vluxei8_v_i32m4 ((void *) it, v4, vl); + vint32m4_t vw5 =3D __riscv_vluxei8_v_i32m4 ((void *) it, v5, vl); + vint32m4_t vw6 =3D __riscv_vluxei8_v_i32m4 ((void *) it, v6, vl); + vint32m4_t vw7 =3D __riscv_vluxei8_v_i32m4 ((void *) it, v7, vl); + + asm volatile("nop" ::: "memory"); + size_t sum0 =3D __riscv_vmv_x_s_i32m4_i32 (vw0); + size_t sum1 =3D __riscv_vmv_x_s_i32m4_i32 (vw1); + size_t sum2 =3D __riscv_vmv_x_s_i32m4_i32 (vw2); + size_t sum3 =3D __riscv_vmv_x_s_i32m4_i32 (vw3); + size_t sum4 =3D __riscv_vmv_x_s_i32m4_i32 (vw4); + size_t sum5 =3D __riscv_vmv_x_s_i32m4_i32 (vw5); + size_t sum6 =3D __riscv_vmv_x_s_i32m4_i32 (vw6); + size_t sum7 =3D __riscv_vmv_x_s_i32m4_i32 (vw7); + + sum +=3D sumation (sum0, sum1, sum2, sum3, sum4, sum5, sum6, sum7); + } + return sum; +} + +/* { dg-final { scan-assembler-not {vmv1r} } } */ +/* { dg-final { scan-assembler-not {vmv2r} } } */ +/* { dg-final { scan-assembler-not {vmv4r} } } */ +/* { dg-final { scan-assembler-not {vmv8r} } } */ +/* { dg-final { scan-assembler-not {csrr} { xfail riscv*-*-* } } } */ diff --git a/gcc/testsuite/gcc.target/riscv/rvv/base/pr112431-32.c b/gcc/te= stsuite/gcc.target/riscv/rvv/base/pr112431-32.c new file mode 100644 index 00000000000..284b7a2891c --- /dev/null +++ b/gcc/testsuite/gcc.target/riscv/rvv/base/pr112431-32.c @@ -0,0 +1,51 @@ +/* { dg-do compile } */ +/* { dg-options "-march=3Drv64gcv -mabi=3Dlp64d -O3" } */ + +#include "riscv_vector.h" + +size_t __attribute__ ((noinline)) +sumation (size_t sum0, size_t sum1, size_t sum2, size_t sum3) +{ + return sum0 + sum1 + sum2 + sum3; +} + +size_t +foo (char const *buf, size_t len) +{ + size_t sum =3D 0; + size_t vl =3D __riscv_vsetvlmax_e8m8 (); + size_t step =3D vl * 4; + const char *it =3D buf, *end =3D buf + len; + for (; it + step <=3D end;) + { + vuint8m2_t v0 =3D __riscv_vle8_v_u8m2 ((void *) it, vl); + it +=3D vl; + vuint8m2_t v1 =3D __riscv_vle8_v_u8m2 ((void *) it, vl); + it +=3D vl; + vuint8m2_t v2 =3D __riscv_vle8_v_u8m2 ((void *) it, vl); + it +=3D vl; + vuint8m2_t v3 =3D __riscv_vle8_v_u8m2 ((void *) it, vl); + it +=3D vl; + + asm volatile("nop" ::: "memory"); + vint32m8_t vw0 =3D __riscv_vluxei8_v_i32m8 ((void *) it, v0, vl); + vint32m8_t vw1 =3D __riscv_vluxei8_v_i32m8 ((void *) it, v1, vl); + vint32m8_t vw2 =3D __riscv_vluxei8_v_i32m8 ((void *) it, v2, vl); + vint32m8_t vw3 =3D __riscv_vluxei8_v_i32m8 ((void *) it, v3, vl); + + asm volatile("nop" ::: "memory"); + size_t sum0 =3D __riscv_vmv_x_s_i32m8_i32 (vw0); + size_t sum1 =3D __riscv_vmv_x_s_i32m8_i32 (vw1); + size_t sum2 =3D __riscv_vmv_x_s_i32m8_i32 (vw2); + size_t sum3 =3D __riscv_vmv_x_s_i32m8_i32 (vw3); + + sum +=3D sumation (sum0, sum1, sum2, sum3); + } + return sum; +} + +/* { dg-final { scan-assembler-not {vmv1r} } } */ +/* { dg-final { scan-assembler-not {vmv2r} } } */ +/* { dg-final { scan-assembler-not {vmv4r} } } */ +/* { dg-final { scan-assembler-not {vmv8r} } } */ +/* { dg-final { scan-assembler-not {csrr} { xfail riscv*-*-* } } } */ diff --git a/gcc/testsuite/gcc.target/riscv/rvv/base/pr112431-33.c b/gcc/te= stsuite/gcc.target/riscv/rvv/base/pr112431-33.c new file mode 100644 index 00000000000..82baf0fadb3 --- /dev/null +++ b/gcc/testsuite/gcc.target/riscv/rvv/base/pr112431-33.c @@ -0,0 +1,51 @@ +/* { dg-do compile } */ +/* { dg-options "-march=3Drv64gcv -mabi=3Dlp64d -O3" } */ + +#include "riscv_vector.h" + +size_t __attribute__ ((noinline)) +sumation (size_t sum0, size_t sum1, size_t sum2, size_t sum3) +{ + return sum0 + sum1 + sum2 + sum3; +} + +size_t +foo (char const *buf, size_t len) +{ + size_t sum =3D 0; + size_t vl =3D __riscv_vsetvlmax_e8m8 (); + size_t step =3D vl * 4; + const char *it =3D buf, *end =3D buf + len; + for (; it + step <=3D end;) + { + vuint8m1_t v0 =3D __riscv_vle8_v_u8m1 ((void *) it, vl); + it +=3D vl; + vuint8m1_t v1 =3D __riscv_vle8_v_u8m1 ((void *) it, vl); + it +=3D vl; + vuint8m1_t v2 =3D __riscv_vle8_v_u8m1 ((void *) it, vl); + it +=3D vl; + vuint8m1_t v3 =3D __riscv_vle8_v_u8m1 ((void *) it, vl); + it +=3D vl; + + asm volatile("nop" ::: "memory"); + vint64m8_t vw0 =3D __riscv_vluxei8_v_i64m8 ((void *) it, v0, vl); + vint64m8_t vw1 =3D __riscv_vluxei8_v_i64m8 ((void *) it, v1, vl); + vint64m8_t vw2 =3D __riscv_vluxei8_v_i64m8 ((void *) it, v2, vl); + vint64m8_t vw3 =3D __riscv_vluxei8_v_i64m8 ((void *) it, v3, vl); + + asm volatile("nop" ::: "memory"); + size_t sum0 =3D __riscv_vmv_x_s_i64m8_i64 (vw0); + size_t sum1 =3D __riscv_vmv_x_s_i64m8_i64 (vw1); + size_t sum2 =3D __riscv_vmv_x_s_i64m8_i64 (vw2); + size_t sum3 =3D __riscv_vmv_x_s_i64m8_i64 (vw3); + + sum +=3D sumation (sum0, sum1, sum2, sum3); + } + return sum; +} + +/* { dg-final { scan-assembler-not {vmv1r} } } */ +/* { dg-final { scan-assembler-not {vmv2r} } } */ +/* { dg-final { scan-assembler-not {vmv4r} } } */ +/* { dg-final { scan-assembler-not {vmv8r} } } */ +/* { dg-final { scan-assembler-not {csrr} { xfail riscv*-*-* } } } */ diff --git a/gcc/testsuite/gcc.target/riscv/rvv/base/pr112431-34.c b/gcc/te= stsuite/gcc.target/riscv/rvv/base/pr112431-34.c index 286185aa01e..80ea65b85ff 100644 --- a/gcc/testsuite/gcc.target/riscv/rvv/base/pr112431-34.c +++ b/gcc/testsuite/gcc.target/riscv/rvv/base/pr112431-34.c @@ -98,4 +98,4 @@ foo (char const *buf, size_t len) return sum; } -/* { dg-final { scan-assembler-not {vluxei8\.v\tv0,\s*\([a-x0-9]+\),\s*v[0= -9]+,\s*v0.t} { xfail riscv*-*-* } } } */ +/* { dg-final { scan-assembler-not {vluxei8\.v\tv0,\s*\([a-x0-9]+\),\s*v[0= -9]+,\s*v0.t} } } */ -- 2.34.1 --_000_MW5PR11MB590881B666DE8883A818AF43A9122MW5PR11MB5908namp_--