From mboxrd@z Thu Jan 1 00:00:00 1970 Return-Path: Received: from mga01.intel.com (mga01.intel.com [192.55.52.88]) by sourceware.org (Postfix) with ESMTPS id 244033858D20 for ; Fri, 14 Apr 2023 03:27:02 +0000 (GMT) DMARC-Filter: OpenDMARC Filter v1.4.2 sourceware.org 244033858D20 Authentication-Results: sourceware.org; dmarc=pass (p=none dis=none) header.from=intel.com Authentication-Results: sourceware.org; spf=pass smtp.mailfrom=intel.com DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/simple; d=intel.com; i=@intel.com; q=dns/txt; s=Intel; t=1681442822; x=1712978822; h=from:to:cc:subject:date:message-id:references: in-reply-to:mime-version; bh=iSYMtSZwvr4OGB4TK3j54gIFlPMDcPadi8+TRQLzo54=; b=iCyq7U4evIA7xAlCR1OUmzjZQccINO382wZNLcdyNSnSC9388AiXvr3Y AAkFYj40da+MMFtzFWqmhLe4mT8Y1vgebUubgi42YM9aevKW6v7BM0IbH /m55CJes09QLqSh0FL5p0SXllo+WFxUWDsRKZ9ThBRcqPXGLZIVbSx5b6 x+MqcBM5Q8SkvFznlqXqVMkjQVZFJ4hAfEDZouXe7byIXFEAp6IApp/sB frJU85zYo1vqnN0VoRevCNhdPmT9Huuad5JGjqDsTOV+lni3M0VZR8Ok/ Ncsd2+FNQRHxPIeUnS2DTi95KQGbuKETfeskBFrgwl4acvX93uPZsLT+2 g==; X-IronPort-AV: E=McAfee;i="6600,9927,10679"; a="372233488" X-IronPort-AV: E=Sophos;i="5.99,195,1677571200"; d="scan'208,217";a="372233488" Received: from orsmga002.jf.intel.com ([10.7.209.21]) by fmsmga101.fm.intel.com with ESMTP/TLS/ECDHE-RSA-AES256-GCM-SHA384; 13 Apr 2023 20:26:59 -0700 X-ExtLoop1: 1 X-IronPort-AV: E=McAfee;i="6600,9927,10679"; a="689636362" X-IronPort-AV: E=Sophos;i="5.99,195,1677571200"; d="scan'208,217";a="689636362" Received: from fmsmsx603.amr.corp.intel.com ([10.18.126.83]) by orsmga002.jf.intel.com with ESMTP; 13 Apr 2023 20:26:49 -0700 Received: from fmsmsx611.amr.corp.intel.com (10.18.126.91) by fmsmsx603.amr.corp.intel.com (10.18.126.83) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_128_GCM_SHA256) id 15.1.2507.23; Thu, 13 Apr 2023 20:26:48 -0700 Received: from fmsmsx610.amr.corp.intel.com (10.18.126.90) 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.23; Thu, 13 Apr 2023 20:26:47 -0700 Received: from FMSEDG603.ED.cps.intel.com (10.1.192.133) by fmsmsx610.amr.corp.intel.com (10.18.126.90) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_128_GCM_SHA256) id 15.1.2507.23 via Frontend Transport; Thu, 13 Apr 2023 20:26:47 -0700 Received: from NAM10-DM6-obe.outbound.protection.outlook.com (104.47.58.104) by edgegateway.intel.com (192.55.55.68) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.1.2507.23; Thu, 13 Apr 2023 20:26:47 -0700 ARC-Seal: i=1; a=rsa-sha256; s=arcselector9901; d=microsoft.com; cv=none; b=NoviySPxaPMU/F08uJ0CmFjpOS/98TaBnGTRvwiVv+5HhZPGqkH5bttDJjQjqm79PzH6dYHQhjmVJGLatlwwE2DEdpNgv86+/oXgMcCjeJMmr4hgroNZLS8VbuTZlaQrN6hDa3ksdC0T3nzpacXCcIW08DdolkD7IbaMwyByd2n+8fsynuiCXspAFGVKt1Z3dZASPSEg/MXDnafNHjaiOeWDin5VpoutO9UW9ct2Qm62XEofpngD9Z81IqKhEIevp6WdHtfy6p9/KssHtQSfCQeAjyiIND47H72WJ6q/RiBBcyC039+tH6syV7FMwm7CG7U65O7TRZ80Pmvjyf/Ipw== 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=HUyBirbiobZNy3/SpSK+ABjXRa+CJvTi4296EXYLuZ8=; b=IQAeihGOtnN6yh5H7UJCWgSlOIQPtVkYe/HXke++OKv8DJ6MQ60hErphODaPWevzKj9nFigb2QdV6HhYpiZ7Nf5ULBjyeB1CleoxIn3PaybTZaqPNr89uXdvVtHFw62GXnmIVO1wCdg1Cm6NTz8ndRCnztJwvpOQEsd0nqtBoRxEMFdNpmXkgY+LbpwsDndV8gYG3t34B36pJaZssWh4uxha61oNqAhn6RnFqkgLCnCRMfQmcZSdFX0doNFQunM4EABWYGr+zS/+Ep6KVAPPpMqujl8ssP6SuMqw6MBn7uINugLFfYT0QvG7O2ART0+WeBbIIloJSidQBFGh4ocI5g== 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 PH7PR11MB6498.namprd11.prod.outlook.com (2603:10b6:510:1f1::21) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.6277.35; Fri, 14 Apr 2023 03:26:44 +0000 Received: from MW5PR11MB5908.namprd11.prod.outlook.com ([fe80::d84:4cba:8307:78e8]) by MW5PR11MB5908.namprd11.prod.outlook.com ([fe80::d84:4cba:8307:78e8%4]) with mapi id 15.20.6277.043; Fri, 14 Apr 2023 03:26:44 +0000 From: "Li, Pan2" To: "juzhe.zhong@rivai.ai" , gcc-patches CC: Kito.cheng , "Wang, Yanzhang" Subject: RE: [PATCH v2] RISC-V: Add test cases for the RVV mask insn shortcut. Thread-Topic: [PATCH v2] RISC-V: Add test cases for the RVV mask insn shortcut. Thread-Index: AQHZbns1oP/hfv+aoEiqiDRtkEwOZq8qGeUsgAAKzuA= Date: Fri, 14 Apr 2023 03:26:43 +0000 Message-ID: References: <20230414023238.2921142-1-pan2.li@intel.com>, <20230414024529.2930664-1-pan2.li@intel.com> <7FCF953158846DE1+202304141046265870301@rivai.ai> In-Reply-To: <7FCF953158846DE1+202304141046265870301@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_|PH7PR11MB6498:EE_ x-ms-office365-filtering-correlation-id: 883c9cad-7c56-4131-b438-08db3c9811f4 x-ms-exchange-senderadcheck: 1 x-ms-exchange-antispam-relay: 0 x-microsoft-antispam: BCL:0; x-microsoft-antispam-message-info: TVQW3QTgdsxB2MBpsKvK/o3zmfaDxgKlWQn6g/tW+O+T8H/Ek3emQxwcMzBOFgqINM7FgPK/jYHON/eGU+xxga9uP/NRRvEwGwTnVmUcwEcjl7klfADTFKGv029V3elEiBs1p67DRTkS6HL9jdIsJSKNbHEEM9LXH4+hos5eKR4JtLd1WAiolU54n1J3HqxMDvtXPF+TUXZgIZEDsKVQ4Buxm32PTq362gxAVfMHXE9f4MuaxCgU2iNezH0KZAGfOZHpsCK0cCyAch6CjxZrluSSk4ERG50SS8kCEhWaXqCoTP/NkJWCf32fdXaHnysTCCcB9SFKtupXT2ZuePVyHOtO+bYhTdB7OUm/tA8wJK9G/3dZKiDUfJMepsKiLzWkUf02V+Nlrf+gAmP37GUqTGLO2giYmFO1R6jalQyXc4Zb0j4vuir6l/qyWA5B94ktV2xGwIePQDIejts8d6Nt0TQQqPTzmxalgHgAX1fWDfV6CENPnmTCJ5RSJjnXdm3YiYWja4di/bUJZoQxdfmgLcjZbsIl/rW2iMBCtW8Yhw3t2NRgH6GipDFup75CHgmgA6tFPm2SJInegSDTPSoGJDd4cYPlBPe17KlOvix22s8= 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:(13230028)(346002)(376002)(39860400002)(366004)(396003)(136003)(451199021)(33656002)(86362001)(7696005)(110136005)(76116006)(316002)(64756008)(66476007)(54906003)(66446008)(41300700001)(66556008)(71200400001)(478600001)(66946007)(8676002)(4326008)(82960400001)(38070700005)(8936002)(55016003)(122000001)(5660300002)(2906002)(38100700002)(52536014)(186003)(83380400001)(9686003)(26005)(53546011)(107886003)(6506007)(84970400001)(559001)(579004);DIR:OUT;SFP:1102; x-ms-exchange-antispam-messagedata-chunkcount: 1 x-ms-exchange-antispam-messagedata-0: =?us-ascii?Q?z/n05n4DNCI30536L6t6NTrvOxaAiRFFM2jpgKYpgm8d4aun8H0zkoAX42FJ?= =?us-ascii?Q?YfDDDYezMPWrcNsSmGOmMMYbXm9CoRKbzdMP0IAA4GPZX/VkgBE5TmXYO8v2?= =?us-ascii?Q?+UhKxBWyG87+TiYAH/DQpY0XMb1E82ILmg92XSv5t3SN4lxwk5N+8Ghv30Dw?= =?us-ascii?Q?ZvTL8eoXqKiF1Vmn3vPtvymS+SHeKxlrVzLlMNpJ0Yj5z+UjBJXiDmc4aL+B?= =?us-ascii?Q?I9I38iAOoGcE+K19acLPzb5fH36hVUnKNpJkyY51dFFFcBkSS8Tgt4RRZ/z2?= =?us-ascii?Q?WHhtka/1d8Z+KEJUx9Sh091bn21lT9nlGSGLeRYhu0USVsewDPtCf1ywLPAe?= =?us-ascii?Q?/oMioTdtqvHeRCfNEVbT63IE1DUYEBJVeGrSziAqKPZsydmW1eiSDYHQjh3w?= =?us-ascii?Q?K3s8az186tshimC3nNXLe617nO+/nhpp5u2XmhiViCHtnFalq1vlA12itd1I?= =?us-ascii?Q?hHZs5GncgJN4i+KYcq0lTIruxWwyka1y5p0LripDxQAP7VJES9YbNYynOqw1?= =?us-ascii?Q?CK4W3UvQtY2mUsmNefncwkyh94Ip6e4PgrXHSjxRAO7xTOu16QvzOAym0Bv3?= =?us-ascii?Q?NFRj6vY/JxvFeHj5s5L+pvYDE1ia9B0cImKqed0eAucma9IMecM1C8tYk4sj?= =?us-ascii?Q?OHiww9eaMQ9lx+7ZZq4lyTQpAuufSDvtUF48gWc8PHSwMNF3ZllCepkqbJFK?= =?us-ascii?Q?788qgg4JfzP5rT/l6olznpm+F1m103+EPp8FtFHsICHOoG85o3cpvEOf+BFY?= =?us-ascii?Q?+IkJGXIvI6NHNgsyf5ATxQDs5n8byQgbfU0vEuTiArET8s9bMLP3bmlKV4fN?= =?us-ascii?Q?t7O6TCa4jcPswUgw16Sk551OeGwTfQSbNgg6/m2Bp1+3ROzxj+c924Vye8TH?= =?us-ascii?Q?Ic5xsMUCnCGWBscgwUqZlSrmyBch2kQ72t0tDTJFHJU/+VAsFMOYDT+oF33X?= =?us-ascii?Q?L5eALoA/IXpVMiHfaleHP3POJlw/i5b/q5PKK1DufPVHRm/qVe/jjVMVDe89?= =?us-ascii?Q?0+N0iCihNkgSu5isB6TuzBsgWQhH3+wamKyLI6PUa/UN5HutlXEVVZf1uYQQ?= =?us-ascii?Q?LuhGlvM9vVR0sl3CfpaQrQuGM276oClxx7DwSxDY65ttC3YDjwVGfxx7ix9f?= =?us-ascii?Q?jUm/saUET0HSlgY/DUKGxs2p3iffP9jji7xLy7igKnduU8eHNfHYqjv7gb/Z?= =?us-ascii?Q?RkIHnLmG2EJLCQta4bgyqp8Vp/v85LeCBhfd5EQ3Gpi5lTaOIQcCr1QxmhqX?= =?us-ascii?Q?8Cmc6w+c8A876pzNIBtn6+OUcRrtjyXRCjOXjU62rSBABtPgnfj2F/Rr4ppk?= =?us-ascii?Q?c6D27CMYS30SC7wsBjcuSt7ZqYKwgQcCuW71N/biYKC2tTPxLOSFDRc2QiGT?= =?us-ascii?Q?V8yHulVvPJyNDl7kIrQVl3BPFLj9tx72CIQaQni7xGCctdkvay1XsXQyQZde?= =?us-ascii?Q?PtyRWtoRszPgwLsmTDkZ1iCgh8W94nESM8vIyHpTOrzH65KauOTAA+Gn1hij?= =?us-ascii?Q?WG34j4KAxC4G1xspd2LyYr3Qv03iGDylxKV2nskeJ/Mc+oeHC8oJhxF2siRX?= =?us-ascii?Q?A2lBxHp8MCBp5FziLt4=3D?= Content-Type: multipart/alternative; boundary="_000_MW5PR11MB59080A2E3D8EEF407DF7C1E4A9999MW5PR11MB5908namp_" 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: 883c9cad-7c56-4131-b438-08db3c9811f4 X-MS-Exchange-CrossTenant-originalarrivaltime: 14 Apr 2023 03:26:43.6612 (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: LQtESeOC7vxVPLNEqk6hzuRG8RIDrYO64/R19gbKRWI13k/j0YnEjDUBZ0Oha0y5SZ3dqzqzLdKV0lnFGLjfxQ== X-MS-Exchange-Transport-CrossTenantHeadersStamped: PH7PR11MB6498 X-OriginatorOrg: intel.com X-Spam-Status: No, score=-12.2 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,RCVD_IN_MSPIKE_H3,RCVD_IN_MSPIKE_WL,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_MW5PR11MB59080A2E3D8EEF407DF7C1E4A9999MW5PR11MB5908namp_ Content-Type: text/plain; charset="us-ascii" Content-Transfer-Encoding: quoted-printable Thanks juzhe, update new version [PATCH v3] for even more checks. Pan From: juzhe.zhong@rivai.ai Sent: Friday, April 14, 2023 10:46 AM To: Li, Pan2 ; gcc-patches Cc: Kito.cheng ; Wang, Yanzhang ; Li, Pan2 Subject: Re: [PATCH v2] RISC-V: Add test cases for the RVV mask insn shortc= ut. LGTM. Wait for Kito more comments. ________________________________ juzhe.zhong@rivai.ai From: pan2.li Date: 2023-04-14 10:45 To: gcc-patches CC: juzhe.zhong; kito.cheng; yanzhang.wang; pan2.li Subject: [PATCH v2] RISC-V: Add test cases for the RVV mask insn shortcut. From: Pan Li > There are sorts of shortcut codegen for the RVV mask insn. For example. vmxor vd, va, va =3D> vmclr vd. We would like to add more optimization like this but first of all we must add the tests for the existing shortcut optimization, to ensure we don't break existing optimization from underlying shortcut optimization. gcc/testsuite/ChangeLog: * gcc.target/riscv/rvv/base/mask_insn_shortcut.c: New test. Signed-off-by: Pan Li > --- .../riscv/rvv/base/mask_insn_shortcut.c | 239 ++++++++++++++++++ 1 file changed, 239 insertions(+) create mode 100644 gcc/testsuite/gcc.target/riscv/rvv/base/mask_insn_shortc= ut.c diff --git a/gcc/testsuite/gcc.target/riscv/rvv/base/mask_insn_shortcut.c b= /gcc/testsuite/gcc.target/riscv/rvv/base/mask_insn_shortcut.c new file mode 100644 index 00000000000..efc3af39fc3 --- /dev/null +++ b/gcc/testsuite/gcc.target/riscv/rvv/base/mask_insn_shortcut.c @@ -0,0 +1,239 @@ +/* { dg-do compile } */ +/* { dg-options "-march=3Drv64gcv -mabi=3Dlp64 -O3" } */ + +#include "riscv_vector.h" + +vbool1_t test_shortcut_for_riscv_vmand_case_0(vbool1_t v1, size_t vl) { + return __riscv_vmand_mm_b1(v1, v1, vl); +} + +vbool2_t test_shortcut_for_riscv_vmand_case_1(vbool2_t v1, size_t vl) { + return __riscv_vmand_mm_b2(v1, v1, vl); +} + +vbool4_t test_shortcut_for_riscv_vmand_case_2(vbool4_t v1, size_t vl) { + return __riscv_vmand_mm_b4(v1, v1, vl); +} + +vbool8_t test_shortcut_for_riscv_vmand_case_3(vbool8_t v1, size_t vl) { + return __riscv_vmand_mm_b8(v1, v1, vl); +} + +vbool16_t test_shortcut_for_riscv_vmand_case_4(vbool16_t v1, size_t vl) { + return __riscv_vmand_mm_b16(v1, v1, vl); +} + +vbool32_t test_shortcut_for_riscv_vmand_case_5(vbool32_t v1, size_t vl) { + return __riscv_vmand_mm_b32(v1, v1, vl); +} + +vbool64_t test_shortcut_for_riscv_vmand_case_6(vbool64_t v1, size_t vl) { + return __riscv_vmand_mm_b64(v1, v1, vl); +} + +vbool1_t test_shortcut_for_riscv_vmnand_case_0(vbool1_t v1, size_t vl) { + return __riscv_vmnand_mm_b1(v1, v1, vl); +} + +vbool2_t test_shortcut_for_riscv_vmnand_case_1(vbool2_t v1, size_t vl) { + return __riscv_vmnand_mm_b2(v1, v1, vl); +} + +vbool4_t test_shortcut_for_riscv_vmnand_case_2(vbool4_t v1, size_t vl) { + return __riscv_vmnand_mm_b4(v1, v1, vl); +} + +vbool8_t test_shortcut_for_riscv_vmnand_case_3(vbool8_t v1, size_t vl) { + return __riscv_vmnand_mm_b8(v1, v1, vl); +} + +vbool16_t test_shortcut_for_riscv_vmnand_case_4(vbool16_t v1, size_t vl) { + return __riscv_vmnand_mm_b16(v1, v1, vl); +} + +vbool32_t test_shortcut_for_riscv_vmnand_case_5(vbool32_t v1, size_t vl) { + return __riscv_vmnand_mm_b32(v1, v1, vl); +} + +vbool64_t test_shortcut_for_riscv_vmnand_case_6(vbool64_t v1, size_t vl) { + return __riscv_vmnand_mm_b64(v1, v1, vl); +} + +vbool1_t test_shortcut_for_riscv_vmandn_case_0(vbool1_t v1, size_t vl) { + return __riscv_vmandn_mm_b1(v1, v1, vl); +} + +vbool2_t test_shortcut_for_riscv_vmandn_case_1(vbool2_t v1, size_t vl) { + return __riscv_vmandn_mm_b2(v1, v1, vl); +} + +vbool4_t test_shortcut_for_riscv_vmandn_case_2(vbool4_t v1, size_t vl) { + return __riscv_vmandn_mm_b4(v1, v1, vl); +} + +vbool8_t test_shortcut_for_riscv_vmandn_case_3(vbool8_t v1, size_t vl) { + return __riscv_vmandn_mm_b8(v1, v1, vl); +} + +vbool16_t test_shortcut_for_riscv_vmandn_case_4(vbool16_t v1, size_t vl) { + return __riscv_vmandn_mm_b16(v1, v1, vl); +} + +vbool32_t test_shortcut_for_riscv_vmandn_case_5(vbool32_t v1, size_t vl) { + return __riscv_vmandn_mm_b32(v1, v1, vl); +} + +vbool64_t test_shortcut_for_riscv_vmandn_case_6(vbool64_t v1, size_t vl) { + return __riscv_vmandn_mm_b64(v1, v1, vl); +} + +vbool1_t test_shortcut_for_riscv_vmxor_case_0(vbool1_t v1, size_t vl) { + return __riscv_vmxor_mm_b1(v1, v1, vl); +} + +vbool2_t test_shortcut_for_riscv_vmxor_case_1(vbool2_t v1, size_t vl) { + return __riscv_vmxor_mm_b2(v1, v1, vl); +} + +vbool4_t test_shortcut_for_riscv_vmxor_case_2(vbool4_t v1, size_t vl) { + return __riscv_vmxor_mm_b4(v1, v1, vl); +} + +vbool8_t test_shortcut_for_riscv_vmxor_case_3(vbool8_t v1, size_t vl) { + return __riscv_vmxor_mm_b8(v1, v1, vl); +} + +vbool16_t test_shortcut_for_riscv_vmxor_case_4(vbool16_t v1, size_t vl) { + return __riscv_vmxor_mm_b16(v1, v1, vl); +} + +vbool32_t test_shortcut_for_riscv_vmxor_case_5(vbool32_t v1, size_t vl) { + return __riscv_vmxor_mm_b32(v1, v1, vl); +} + +vbool64_t test_shortcut_for_riscv_vmxor_case_6(vbool64_t v1, size_t vl) { + return __riscv_vmxor_mm_b64(v1, v1, vl); +} + +vbool1_t test_shortcut_for_riscv_vmor_case_0(vbool1_t v1, size_t vl) { + return __riscv_vmor_mm_b1(v1, v1, vl); +} + +vbool2_t test_shortcut_for_riscv_vmor_case_1(vbool2_t v1, size_t vl) { + return __riscv_vmor_mm_b2(v1, v1, vl); +} + +vbool4_t test_shortcut_for_riscv_vmor_case_2(vbool4_t v1, size_t vl) { + return __riscv_vmor_mm_b4(v1, v1, vl); +} + +vbool8_t test_shortcut_for_riscv_vmor_case_3(vbool8_t v1, size_t vl) { + return __riscv_vmor_mm_b8(v1, v1, vl); +} + +vbool16_t test_shortcut_for_riscv_vmor_case_4(vbool16_t v1, size_t vl) { + return __riscv_vmor_mm_b16(v1, v1, vl); +} + +vbool32_t test_shortcut_for_riscv_vmor_case_5(vbool32_t v1, size_t vl) { + return __riscv_vmor_mm_b32(v1, v1, vl); +} + +vbool64_t test_shortcut_for_riscv_vmor_case_6(vbool64_t v1, size_t vl) { + return __riscv_vmor_mm_b64(v1, v1, vl); +} + +vbool1_t test_shortcut_for_riscv_vmnor_case_0(vbool1_t v1, size_t vl) { + return __riscv_vmnor_mm_b1(v1, v1, vl); +} + +vbool2_t test_shortcut_for_riscv_vmnor_case_1(vbool2_t v1, size_t vl) { + return __riscv_vmnor_mm_b2(v1, v1, vl); +} + +vbool4_t test_shortcut_for_riscv_vmnor_case_2(vbool4_t v1, size_t vl) { + return __riscv_vmnor_mm_b4(v1, v1, vl); +} + +vbool8_t test_shortcut_for_riscv_vmnor_case_3(vbool8_t v1, size_t vl) { + return __riscv_vmnor_mm_b8(v1, v1, vl); +} + +vbool16_t test_shortcut_for_riscv_vmnor_case_4(vbool16_t v1, size_t vl) { + return __riscv_vmnor_mm_b16(v1, v1, vl); +} + +vbool32_t test_shortcut_for_riscv_vmnor_case_5(vbool32_t v1, size_t vl) { + return __riscv_vmnor_mm_b32(v1, v1, vl); +} + +vbool64_t test_shortcut_for_riscv_vmnor_case_6(vbool64_t v1, size_t vl) { + return __riscv_vmnor_mm_b64(v1, v1, vl); +} + +vbool1_t test_shortcut_for_riscv_vmorn_case_0(vbool1_t v1, size_t vl) { + return __riscv_vmorn_mm_b1(v1, v1, vl); +} + +vbool2_t test_shortcut_for_riscv_vmorn_case_1(vbool2_t v1, size_t vl) { + return __riscv_vmorn_mm_b2(v1, v1, vl); +} + +vbool4_t test_shortcut_for_riscv_vmorn_case_2(vbool4_t v1, size_t vl) { + return __riscv_vmorn_mm_b4(v1, v1, vl); +} + +vbool8_t test_shortcut_for_riscv_vmorn_case_3(vbool8_t v1, size_t vl) { + return __riscv_vmorn_mm_b8(v1, v1, vl); +} + +vbool16_t test_shortcut_for_riscv_vmorn_case_4(vbool16_t v1, size_t vl) { + return __riscv_vmorn_mm_b16(v1, v1, vl); +} + +vbool32_t test_shortcut_for_riscv_vmorn_case_5(vbool32_t v1, size_t vl) { + return __riscv_vmorn_mm_b32(v1, v1, vl); +} + +vbool64_t test_shortcut_for_riscv_vmorn_case_6(vbool64_t v1, size_t vl) { + return __riscv_vmorn_mm_b64(v1, v1, vl); +} + +vbool1_t test_shortcut_for_riscv_vmxnor_case_0(vbool1_t v1, size_t vl) { + return __riscv_vmxnor_mm_b1(v1, v1, vl); +} + +vbool2_t test_shortcut_for_riscv_vmxnor_case_1(vbool2_t v1, size_t vl) { + return __riscv_vmxnor_mm_b2(v1, v1, vl); +} + +vbool4_t test_shortcut_for_riscv_vmxnor_case_2(vbool4_t v1, size_t vl) { + return __riscv_vmxnor_mm_b4(v1, v1, vl); +} + +vbool8_t test_shortcut_for_riscv_vmxnor_case_3(vbool8_t v1, size_t vl) { + return __riscv_vmxnor_mm_b8(v1, v1, vl); +} + +vbool16_t test_shortcut_for_riscv_vmxnor_case_4(vbool16_t v1, size_t vl) { + return __riscv_vmxnor_mm_b16(v1, v1, vl); +} + +vbool32_t test_shortcut_for_riscv_vmxnor_case_5(vbool32_t v1, size_t vl) { + return __riscv_vmxnor_mm_b32(v1, v1, vl); +} + +vbool64_t test_shortcut_for_riscv_vmxnor_case_6(vbool64_t v1, size_t vl) { + return __riscv_vmxnor_mm_b64(v1, v1, vl); +} + +/* { dg-final { scan-assembler-not {vmand\.mm\s+v[0-9]+,\s*v[0-9]+} } } */ +/* { dg-final { scan-assembler-not {vmnand\.mm\s+v[0-9]+,\s*v[0-9]+} } } */ +/* { dg-final { scan-assembler-not {vmnandn\.mm\s+v[0-9]+,\s*v[0-9]+} } } = */ +/* { dg-final { scan-assembler-not {vmxor\.mm\s+v[0-9]+,\s*v[0-9]+} } } */ +/* { dg-final { scan-assembler-not {vmor\.mm\s+v[0-9]+,\s*v[0-9]+} } } */ +/* { dg-final { scan-assembler-not {vmnor\.mm\s+v[0-9]+,\s*v[0-9]+} } } */ +/* { dg-final { scan-assembler-times {vmorn\.mm\s+v[0-9]+,\s*v[0-9]+,\s*v[= 0-9]+} 7 } } */ +/* { dg-final { scan-assembler-not {vmxnor\.mm\s+v[0-9]+,\s*v[0-9]+} } } */ +/* { dg-final { scan-assembler-times {vmclr\.m\s+v[0-9]+} 14 } } */ +/* { dg-final { scan-assembler-times {vmset\.m\s+v[0-9]+} 7 } } */ -- 2.34.1 --_000_MW5PR11MB59080A2E3D8EEF407DF7C1E4A9999MW5PR11MB5908namp_--