From mboxrd@z Thu Jan 1 00:00:00 1970 Return-Path: Received: from EUR04-VI1-obe.outbound.protection.outlook.com (mail-vi1eur04on2078.outbound.protection.outlook.com [40.107.8.78]) by sourceware.org (Postfix) with ESMTPS id 9C0343857C66 for ; Thu, 16 Nov 2023 16:49:11 +0000 (GMT) DMARC-Filter: OpenDMARC Filter v1.4.2 sourceware.org 9C0343857C66 Authentication-Results: sourceware.org; dmarc=pass (p=none dis=none) header.from=arm.com Authentication-Results: sourceware.org; spf=pass smtp.mailfrom=arm.com ARC-Filter: OpenARC Filter v1.0.0 sourceware.org 9C0343857C66 Authentication-Results: server2.sourceware.org; arc=pass smtp.remote-ip=40.107.8.78 ARC-Seal: i=3; a=rsa-sha256; d=sourceware.org; s=key; t=1700153353; cv=pass; b=DAtp5ViRsZZUWC5ur6NGyVEZrONiXw9oTVZonyfJ+DhFkPfWeCFedDK+AKCbDa21XikmYaOSX6yX4EEIabalNLaXa15CWMdLNnJpCZee2OReETKoNvMaaNtUKkkFcSjiIdpMan+ppBoSDQ9zspE+tplKpwgDAuTh43tCcVjdKlk= ARC-Message-Signature: i=3; a=rsa-sha256; d=sourceware.org; s=key; t=1700153353; c=relaxed/simple; bh=h/S94RPYjrxzFLSCJWjSCNzgtE3CPcUPYJXMa3Qa5yw=; h=DKIM-Signature:DKIM-Signature:From:To:Subject:Date:Message-ID: MIME-Version; b=kJXmKvS87oFIGvS8DFaTYuJCRx0TEPiW2/4nq2fpRMyWOrMunc/8u87vMTulwd5JVMEpl0qp/svaW7iMQY7jin7Bj3HChX4Jnfi0arXnuFIr+1BW79mYXyP98OaU8903aGYijtIZKurqNa7BOAydCYjBsOs8oUsCTT++ghP56c0= ARC-Authentication-Results: i=3; server2.sourceware.org ARC-Seal: i=2; a=rsa-sha256; s=arcselector9901; d=microsoft.com; cv=pass; b=PF5q4/Fr5+QgFHi46EyeSc+1S/pyd8zDiv7zBbhhscN9+Ejj5vCvKcJwpTc5gNTF8j/LJuYy3jOLlGn6XimvHqUJYyaQhnyVeMJ+EIjcbl+TxjofjJq5OlOJinKVeHcagYy4CUYtqdwzkR0Jdqz9bmzfLzcLTtCDUxUzmVNK1MOG+ExhEwIBNw74hnmsR6Ha00MhNtzQ014urZ1TfkazjJ/CftO5/USstx3Y9DsM20DFYJYA+r6eFYXGbvAm+Fh71ECwMU46qyKxv44atWqduYcNlpLGUPKZXI3iq5d6lKHpGoZy/cXluAA4Ke5peS5C1gmOIB08HBQCa6SbN9LQXw== ARC-Message-Signature: i=2; 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=jGvwBMTYiUKLB7U/y0zj2wXaH4hYvLVUzsywt3kwHxQ=; b=neIB5buHCFOW9EYD0UhKIkSTLAVAOQba1HClKJZA8S9VcJ5OnbHu0kK+2Naat1zMQnh5Gow8VZ6Zw+8cumG+GIAh9Gk3Oq+vzPhqmcYYtTyEUr04dqNbNC4BoH2OtomXI57736VuP8AXZbpcFYhxNMGG30vbgWI63sPkQrIdMvkzc6PCiUPu4IVoZnUb+dwSHO7cnMpu5iQfyye9X4i7DsHt4cPGgnyOKMXRuqDUBAZbeShDVM6zrJo61qIUDeAL5Fo/wpztMPKL4s7JCGy0TcoLKWpWKrPfAYmnuXYmc4MJYmTsfZvDydwxhonxiX+SXSJObYFU2EpGRHJQXzJtkw== ARC-Authentication-Results: i=2; mx.microsoft.com 1; spf=pass (sender ip is 63.35.35.123) smtp.rcpttodomain=gcc.gnu.org smtp.mailfrom=arm.com; dmarc=pass (p=none sp=none pct=100) action=none header.from=arm.com; dkim=pass (signature was verified) header.d=armh.onmicrosoft.com; arc=pass (0 oda=1 ltdi=1 spf=[1,1,smtp.mailfrom=arm.com] dkim=[1,1,header.d=arm.com] dmarc=[1,1,header.from=arm.com]) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=armh.onmicrosoft.com; s=selector2-armh-onmicrosoft-com; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-SenderADCheck; bh=jGvwBMTYiUKLB7U/y0zj2wXaH4hYvLVUzsywt3kwHxQ=; b=kjRluA9VazQQHledEQ5fjSOjhNKJjEgPsqUgCLhN7PTHOcp5uU9T5RXSDxkS9/TgKtZT95ga4eUUUYKj4Kp90sIVJctDrHQ2CzlvCBud0bh3rPyW1F4F0WSlIczviOcJGFIJvBlxxp4ChVzpxSMfF6FUujCMpwCbHMiKc4sBSxw= Received: from DU2PR04CA0351.eurprd04.prod.outlook.com (2603:10a6:10:2b4::10) by DU0PR08MB7995.eurprd08.prod.outlook.com (2603:10a6:10:3e2::13) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.6977.33; Thu, 16 Nov 2023 16:49:08 +0000 Received: from DB1PEPF00039231.eurprd03.prod.outlook.com (2603:10a6:10:2b4:cafe::b6) by DU2PR04CA0351.outlook.office365.com (2603:10a6:10:2b4::10) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.7002.21 via Frontend Transport; Thu, 16 Nov 2023 16:49:08 +0000 X-MS-Exchange-Authentication-Results: spf=pass (sender IP is 63.35.35.123) smtp.mailfrom=arm.com; dkim=pass (signature was verified) header.d=armh.onmicrosoft.com;dmarc=pass action=none header.from=arm.com; Received-SPF: Pass (protection.outlook.com: domain of arm.com designates 63.35.35.123 as permitted sender) receiver=protection.outlook.com; client-ip=63.35.35.123; helo=64aa7808-outbound-1.mta.getcheckrecipient.com; pr=C Received: from 64aa7808-outbound-1.mta.getcheckrecipient.com (63.35.35.123) by DB1PEPF00039231.mail.protection.outlook.com (10.167.8.104) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.7002.20 via Frontend Transport; Thu, 16 Nov 2023 16:49:08 +0000 Received: ("Tessian outbound 20615a7e7970:v228"); Thu, 16 Nov 2023 16:49:08 +0000 X-CheckRecipientChecked: true X-CR-MTA-CID: 93c1a7f8cf759791 X-CR-MTA-TID: 64aa7808 Received: from ae101e57ed3b.1 by 64aa7808-outbound-1.mta.getcheckrecipient.com id 0A89A373-348B-4137-A625-5464301C931E.1; Thu, 16 Nov 2023 16:49:02 +0000 Received: from EUR04-DB3-obe.outbound.protection.outlook.com by 64aa7808-outbound-1.mta.getcheckrecipient.com with ESMTPS id ae101e57ed3b.1 (version=TLSv1.2 cipher=ECDHE-RSA-AES256-GCM-SHA384); Thu, 16 Nov 2023 16:49:02 +0000 ARC-Seal: i=1; a=rsa-sha256; s=arcselector9901; d=microsoft.com; cv=none; b=kTBfoAMe5jA0c+6l0gq73MmFTae0vrb5SdSbqgO4DEPEYUPR+4OsE4Hha8BToK5BvAoTZUl8lnLboW5RxcwdgaEK3D16/d77Otb4n17+CdF2Ez46p1jOHd9igINXAva45dT0eupqbo599F9GKznlRTMlliLaCWfXFBktAtL7vQQGLCvQC5L3FUsOjMJOqavhcEkbC5EcrwBzi8MyLLpsjXUF+z4cX9qqjTG05Dr9y//DpsZpjquGrRTRUrCmlF6EzzeV0T2KyQcPxIUZkon3giSzJgyR28v124cs5ro/Dfe47GnH3au+TW1ovvG8rxdL4yx7KKcxuBCG6vWeWpmezQ== 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=jGvwBMTYiUKLB7U/y0zj2wXaH4hYvLVUzsywt3kwHxQ=; b=dOAiOyD/8uCaILf2wOXPiYpgoR3QpWmPoNtQQfA/PbDtu7J/RirEJ13U+4B+TrLgIH+9+8c1aci8ev3WXpfN2yEpEZnCktp0qhmVnsLL+YPd8RXtIwKYyX34mNaGFIGy4C0Zf+FkJJ4HnHKLAIhTTKllSve1ekSi8IXs1uPKEugwUIj2A2yBGJsLIxe0pvhp9GzXOhTyrUCQSl9x2BQRFLlJg/4Wzx/tF9j2Y1Cw4VUMLMgmb97W44yEn6aVFOPlRYkAF3f6en1D4umpVumuLC1yuT3KsIyI6iDVh+FNSncu1Gi1pw5eTubf42mGelcgU9aLlW1931OGsMnckrj1MA== ARC-Authentication-Results: i=1; mx.microsoft.com 1; spf=pass smtp.mailfrom=arm.com; dmarc=pass action=none header.from=arm.com; dkim=pass header.d=arm.com; arc=none DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=armh.onmicrosoft.com; s=selector2-armh-onmicrosoft-com; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-SenderADCheck; bh=jGvwBMTYiUKLB7U/y0zj2wXaH4hYvLVUzsywt3kwHxQ=; b=kjRluA9VazQQHledEQ5fjSOjhNKJjEgPsqUgCLhN7PTHOcp5uU9T5RXSDxkS9/TgKtZT95ga4eUUUYKj4Kp90sIVJctDrHQ2CzlvCBud0bh3rPyW1F4F0WSlIczviOcJGFIJvBlxxp4ChVzpxSMfF6FUujCMpwCbHMiKc4sBSxw= Received: from PAXPR08MB6926.eurprd08.prod.outlook.com (2603:10a6:102:138::24) by DB9PR08MB8457.eurprd08.prod.outlook.com (2603:10a6:10:3d7::13) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.7002.21; Thu, 16 Nov 2023 16:49:00 +0000 Received: from PAXPR08MB6926.eurprd08.prod.outlook.com ([fe80::106e:538b:c12:4f38]) by PAXPR08MB6926.eurprd08.prod.outlook.com ([fe80::106e:538b:c12:4f38%4]) with mapi id 15.20.7002.021; Thu, 16 Nov 2023 16:49:00 +0000 From: Kyrylo Tkachov To: Christophe Lyon , "gcc-patches@gcc.gnu.org" , Richard Sandiford , Richard Earnshaw Subject: RE: [PATCH 4/6] arm: [MVE intrinsics] add load and store shapes Thread-Topic: [PATCH 4/6] arm: [MVE intrinsics] add load and store shapes Thread-Index: AQHaGKFXXBgik3v8okue/ykwdtawirB9KEjQ Date: Thu, 16 Nov 2023 16:49:00 +0000 Message-ID: References: <20231116152617.2193377-1-christophe.lyon@linaro.org> <20231116152617.2193377-4-christophe.lyon@linaro.org> In-Reply-To: <20231116152617.2193377-4-christophe.lyon@linaro.org> Accept-Language: en-GB, en-US Content-Language: en-US X-MS-Has-Attach: X-MS-TNEF-Correlator: Authentication-Results-Original: dkim=none (message not signed) header.d=none;dmarc=none action=none header.from=arm.com; x-ms-traffictypediagnostic: PAXPR08MB6926:EE_|DB9PR08MB8457:EE_|DB1PEPF00039231:EE_|DU0PR08MB7995:EE_ X-MS-Office365-Filtering-Correlation-Id: d51d0d9a-36d0-4d9c-3545-08dbe6c3f3cc x-checkrecipientrouted: true nodisclaimer: true X-MS-Exchange-SenderADCheck: 1 X-MS-Exchange-AntiSpam-Relay: 0 X-Microsoft-Antispam-Untrusted: BCL:0; X-Microsoft-Antispam-Message-Info-Original: Tmd4zVM6T0d6xk/16KI65AGnONL1efQ6jQVsk0CxijaZK2GHQ/vYs1wRKufPIO0/hbnm1gth2dq1EHaR2FUcctm8V8tPjKZ40+rDY9jfe6ipHgTZebRaSO6TD++qOsOo7mVqQULTUhmVwsnJms5GLgwpsrI0n6PfSoHNi53vs7vtPGxX0BswBhaVYGt+wSaVxq8zbr66UJhTdn0XQu22waHg5E7JBDLQYbWfoguBtOP/K1dhCWL15ZrDGXPiFn+ey09gaoD+oAvN2nTTSEFwsS85KdmfTgyvxhFtRe0ZzpMTbeEmY1kuOr6odb4lYIuE5rUTW88LvCsEoaPPQD3r2e/26WEa1+nW1H6XY2UpR8h4EDVgaN1Z2h8aQ0VeiAPHaPQamJZFXftJdRtQasMVi0zLZY3dz3C157NQMd8Zr3hjSMeRlQMa8+Ume6dbWjLAsrpQ389zxb094Y039xTy1eZebluL5GLQM/DH2xtt/Az0Tej1Wy2N/GJizWZ/8amnSxKcphQUuOVEJOBE4lO3mEOIfuQCTskaNTj3wjzc+tj0DzSFDxtQbrnZrQMppMxy9lXSF573GSPUpPI8a7jMRz8WsLEyvEt0FhrSlYVg4Gk5MPCHTqNL+yFKp982k8rU9JfQ9De1eVyjW/OPumFCnw== X-Forefront-Antispam-Report-Untrusted: CIP:255.255.255.255;CTRY:;LANG:en;SCL:1;SRV:;IPV:NLI;SFV:NSPM;H:PAXPR08MB6926.eurprd08.prod.outlook.com;PTR:;CAT:NONE;SFS:(13230031)(396003)(136003)(376002)(366004)(39860400002)(346002)(230922051799003)(451199024)(186009)(64100799003)(1800799009)(55016003)(66946007)(76116006)(110136005)(66476007)(66556008)(64756008)(122000001)(38100700002)(38070700009)(33656002)(86362001)(66446008)(83380400001)(26005)(6506007)(7696005)(53546011)(9686003)(71200400001)(2906002)(4001150100001)(6636002)(316002)(8936002)(5660300002)(8676002)(478600001)(52536014)(41300700001)(357404004);DIR:OUT;SFP:1101; Content-Type: text/plain; charset="us-ascii" Content-Transfer-Encoding: quoted-printable MIME-Version: 1.0 X-MS-Exchange-Transport-CrossTenantHeadersStamped: DB9PR08MB8457 Original-Authentication-Results: dkim=none (message not signed) header.d=none;dmarc=none action=none header.from=arm.com; X-EOPAttributedMessage: 0 X-MS-Exchange-Transport-CrossTenantHeadersStripped: DB1PEPF00039231.eurprd03.prod.outlook.com X-MS-PublicTrafficType: Email X-MS-Office365-Filtering-Correlation-Id-Prvs: 38d37a2c-8eb4-4112-da55-08dbe6c3eebd X-Microsoft-Antispam: BCL:0; X-Microsoft-Antispam-Message-Info: oua9zIA8Xur6qV0flggzk/0sdOv/pQrNR1Lz2w0entX/fyVNpWt/8SxhG1deQqF0mMelYOO9AzX3ZbSUbwln2OLcf+0WUETihLWNZayRHzjCa2IuWQRVLmRJD50rzj8y0swZ7RJpESK9T2LMY1KYp7G+okvHP4CuF4y4kEWXkwhTQc5g4hwta/yJcwlItets4TdSb2vb4hiKbGqP70UQjzZgoxOf5HE6e9JcOZzofFgShOfUm9jNx1cYCupOouO693vwI/P6Vj8usfTyk4dfXFAnmByyKF5qX63mD8o+pNKexntoyHOZiD4QSS1c25+848zS3GfGQd3JlWO7ir34fBarS7W3gGXfugDid/DDlRfUSfIShU0dyE8Kb0KbA3ADPcVLzSLumKdKPg1nFnckiMsk5/QGp8H0rG3dwMkKKQZEgjNSSidMXdjhY8zMuvOskStMyCDiAK8Lrx31KxBSb6tejppB2kGQcqlkTqcT336hSCeh4/qWVkhyUCgXnshbJN/nlWqlodg3SH5Qpjt+bENi9vRmjtN7iH2t8H9PC6gp1tBbHdxb2/vDwYXWF+KSDjvaEvXHnhIw5IvKYU8JZdjgDmQCjzSwSz5wygmkpwNRZ5iFBDQWgnuP5X8QuYBAEm/21MFOZ/pP2YanShAvS+skynrfExt24D/UNZpFuXW3Ehb9SUjLoG5LEenfsm/MgELne8quCSu0b3IDnPrSdXRWPk8v7eM5I8V4zReu4XadBlLyWN3oSSW3/EfxepchDWs8Z7QGIkl7DDfnjrFefA== X-Forefront-Antispam-Report: CIP:63.35.35.123;CTRY:IE;LANG:en;SCL:1;SRV:;IPV:CAL;SFV:NSPM;H:64aa7808-outbound-1.mta.getcheckrecipient.com;PTR:ec2-63-35-35-123.eu-west-1.compute.amazonaws.com;CAT:NONE;SFS:(13230031)(4636009)(376002)(39860400002)(346002)(136003)(396003)(230922051799003)(82310400011)(64100799003)(451199024)(1800799009)(186009)(46966006)(40470700004)(36840700001)(478600001)(2906002)(9686003)(6506007)(53546011)(7696005)(4001150100001)(40460700003)(86362001)(70586007)(52536014)(33656002)(5660300002)(70206006)(6636002)(316002)(110136005)(8676002)(8936002)(82740400003)(47076005)(41300700001)(81166007)(55016003)(356005)(36860700001)(40480700001)(26005)(336012)(83380400001)(357404004);DIR:OUT;SFP:1101; X-OriginatorOrg: arm.com X-MS-Exchange-CrossTenant-OriginalArrivalTime: 16 Nov 2023 16:49:08.6314 (UTC) X-MS-Exchange-CrossTenant-Network-Message-Id: d51d0d9a-36d0-4d9c-3545-08dbe6c3f3cc X-MS-Exchange-CrossTenant-Id: f34e5979-57d9-4aaa-ad4d-b122a662184d X-MS-Exchange-CrossTenant-OriginalAttributedTenantConnectingIp: TenantId=f34e5979-57d9-4aaa-ad4d-b122a662184d;Ip=[63.35.35.123];Helo=[64aa7808-outbound-1.mta.getcheckrecipient.com] X-MS-Exchange-CrossTenant-AuthSource: DB1PEPF00039231.eurprd03.prod.outlook.com X-MS-Exchange-CrossTenant-AuthAs: Anonymous X-MS-Exchange-CrossTenant-FromEntityHeader: HybridOnPrem X-MS-Exchange-Transport-CrossTenantHeadersStamped: DU0PR08MB7995 X-Spam-Status: No, score=-11.3 required=5.0 tests=BAYES_00,DKIM_SIGNED,DKIM_VALID,FORGED_SPF_HELO,GIT_PATCH_0,KAM_DMARC_NONE,RCVD_IN_DNSWL_NONE,RCVD_IN_MSPIKE_H2,SPF_HELO_PASS,SPF_NONE,TXREP,T_SCC_BODY_TEXT_LINE,UNPARSEABLE_RELAY 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: > -----Original Message----- > From: Christophe Lyon > Sent: Thursday, November 16, 2023 3:26 PM > To: gcc-patches@gcc.gnu.org; Richard Sandiford > ; Richard Earnshaw > ; Kyrylo Tkachov > Cc: Christophe Lyon > Subject: [PATCH 4/6] arm: [MVE intrinsics] add load and store shapes >=20 > This patch adds the load and store shapes descriptions. Ok. Thanks, Kyrill >=20 > 2023-11-16 Christophe Lyon >=20 > gcc/ > * config/arm/arm-mve-builtins-shapes.cc (load, store): New. > * config/arm/arm-mve-builtins-shapes.h (load, store): New. > --- > gcc/config/arm/arm-mve-builtins-shapes.cc | 67 +++++++++++++++++++++++ > gcc/config/arm/arm-mve-builtins-shapes.h | 2 + > 2 files changed, 69 insertions(+) >=20 > diff --git a/gcc/config/arm/arm-mve-builtins-shapes.cc b/gcc/config/arm/a= rm- > mve-builtins-shapes.cc > index ce87ebcef30..fe983e7c736 100644 > --- a/gcc/config/arm/arm-mve-builtins-shapes.cc > +++ b/gcc/config/arm/arm-mve-builtins-shapes.cc > @@ -1428,6 +1428,38 @@ struct inherent_def : public nonoverloaded_base > }; > SHAPE (inherent) >=20 > +/* sv_t svfoo[_t0](const _t *) > + > + Example: vld1q. > + int8x16_t [__arm_]vld1q[_s8](int8_t const *base) > + int8x16_t [__arm_]vld1q_z[_s8](int8_t const *base, mve_pred16_t p) *= / > +struct load_def : public overloaded_base<0> > +{ > + void > + build (function_builder &b, const function_group_info &group, > + bool preserve_user_namespace) const override > + { > + b.add_overloaded_functions (group, MODE_none, > preserve_user_namespace); > + build_all (b, "t0,al", group, MODE_none, preserve_user_namespace); > + } > + > + /* Resolve a call based purely on a pointer argument. */ > + tree > + resolve (function_resolver &r) const override > + { > + gcc_assert (r.mode_suffix_id =3D=3D MODE_none); > + > + unsigned int i, nargs; > + type_suffix_index type; > + if (!r.check_gp_argument (1, i, nargs) > + || (type =3D r.infer_pointer_type (i)) =3D=3D NUM_TYPE_SUFFIXES) > + return error_mark_node; > + > + return r.resolve_to (r.mode_suffix_id, type); > + } > +}; > +SHAPE (load) > + > /* _t vfoo[_t0](_t) > _t vfoo_n_t0(_t) >=20 > @@ -1477,6 +1509,41 @@ struct mvn_def : public overloaded_base<0> > }; > SHAPE (mvn) >=20 > +/* void vfoo[_t0](_t *, v[xN]_t) > + > + where might be tied to (for non-truncating stores) or might > + depend on the function base name (for truncating stores). > + > + Example: vst1q. > + void [__arm_]vst1q[_s8](int8_t *base, int8x16_t value) > + void [__arm_]vst1q_p[_s8](int8_t *base, int8x16_t value, mve_pred16_t= p) > */ > +struct store_def : public overloaded_base<0> > +{ > + void > + build (function_builder &b, const function_group_info &group, > + bool preserve_user_namespace) const override > + { > + b.add_overloaded_functions (group, MODE_none, > preserve_user_namespace); > + build_all (b, "_,as,v0", group, MODE_none, preserve_user_namespace); > + } > + > + tree > + resolve (function_resolver &r) const override > + { > + gcc_assert (r.mode_suffix_id =3D=3D MODE_none); > + > + unsigned int i, nargs; > + type_suffix_index type; > + if (!r.check_gp_argument (2, i, nargs) > + || !r.require_pointer_type (0) > + || (type =3D r.infer_vector_type (1)) =3D=3D NUM_TYPE_SUFFIXES) > + return error_mark_node; > + > + return r.resolve_to (r.mode_suffix_id, type); > + } > +}; > +SHAPE (store) > + > /* _t vfoo[_t0](_t, _t, _t) >=20 > i.e. the standard shape for ternary operations that operate on > diff --git a/gcc/config/arm/arm-mve-builtins-shapes.h b/gcc/config/arm/ar= m- > mve-builtins-shapes.h > index a93245321c9..aa9309dec7e 100644 > --- a/gcc/config/arm/arm-mve-builtins-shapes.h > +++ b/gcc/config/arm/arm-mve-builtins-shapes.h > @@ -61,7 +61,9 @@ namespace arm_mve > extern const function_shape *const cmp; > extern const function_shape *const create; > extern const function_shape *const inherent; > + extern const function_shape *const load; > extern const function_shape *const mvn; > + extern const function_shape *const store; > extern const function_shape *const ternary; > extern const function_shape *const ternary_lshift; > extern const function_shape *const ternary_n; > -- > 2.34.1