From patchwork Wed Dec 22 15:55:58 2021 Content-Type: text/plain; charset="utf-8" MIME-Version: 1.0 Content-Transfer-Encoding: 7bit X-Patchwork-Submitter: Murray Steele X-Patchwork-Id: 49195 Return-Path: X-Original-To: patchwork@sourceware.org Delivered-To: patchwork@sourceware.org Received: from server2.sourceware.org (localhost [IPv6:::1]) by sourceware.org (Postfix) with ESMTP id 73DBA385842E for ; Wed, 22 Dec 2021 15:56:43 +0000 (GMT) DKIM-Filter: OpenDKIM Filter v2.11.0 sourceware.org 73DBA385842E DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=gcc.gnu.org; s=default; t=1640188603; bh=VlgU04oud+Cc1/t9I5PoMba063aPhOdg5bkZMbAfiV4=; h=Date:Subject:To:List-Id:List-Unsubscribe:List-Archive:List-Post: List-Help:List-Subscribe:From:Reply-To:From; b=e14beHet+aT4Vj2KNblnGJp+dGeESB6qxedAlmyGdxtQQl3vO3GxaD7IIwch6Ti71 agdmrdyFqzjDNmmcB5s8KOcXLdC1YNDdqG5396ug8ZMFDOOV8PfMl2Lr36X+eGdIGF z5I+t58g5znysbln6hc87m0zLFuTVbWqXguxfX0Y= X-Original-To: gcc-patches@gcc.gnu.org Delivered-To: gcc-patches@gcc.gnu.org Received: from EUR04-DB3-obe.outbound.protection.outlook.com (mail-eopbgr60079.outbound.protection.outlook.com [40.107.6.79]) by sourceware.org (Postfix) with ESMTPS id 713E53858C2C for ; Wed, 22 Dec 2021 15:56:12 +0000 (GMT) DMARC-Filter: OpenDMARC Filter v1.4.1 sourceware.org 713E53858C2C Received: from DU2PR04CA0326.eurprd04.prod.outlook.com (2603:10a6:10:2b5::31) by VI1PR08MB4334.eurprd08.prod.outlook.com (2603:10a6:803:f1::20) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.4778.18; Wed, 22 Dec 2021 15:56:08 +0000 Received: from DB5EUR03FT024.eop-EUR03.prod.protection.outlook.com (2603:10a6:10:2b5:cafe::9f) by DU2PR04CA0326.outlook.office365.com (2603:10a6:10:2b5::31) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.4823.14 via Frontend Transport; Wed, 22 Dec 2021 15:56: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; Received: from 64aa7808-outbound-1.mta.getcheckrecipient.com (63.35.35.123) by DB5EUR03FT024.mail.protection.outlook.com (10.152.20.67) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.4823.18 via Frontend Transport; Wed, 22 Dec 2021 15:56:08 +0000 Received: ("Tessian outbound f493ab4f1fb8:v110"); Wed, 22 Dec 2021 15:56:08 +0000 X-CheckRecipientChecked: true X-CR-MTA-CID: 0f515f040eed7b44 X-CR-MTA-TID: 64aa7808 Received: from f30c1ef4d7f7.1 by 64aa7808-outbound-1.mta.getcheckrecipient.com id 5378ECBB-40BB-41E1-88DE-826E01959E4D.1; Wed, 22 Dec 2021 15:56:02 +0000 Received: from EUR05-DB8-obe.outbound.protection.outlook.com by 64aa7808-outbound-1.mta.getcheckrecipient.com with ESMTPS id f30c1ef4d7f7.1 (version=TLSv1.2 cipher=ECDHE-RSA-AES256-GCM-SHA384); Wed, 22 Dec 2021 15:56:02 +0000 ARC-Seal: i=1; a=rsa-sha256; s=arcselector9901; d=microsoft.com; cv=none; b=KuclOXrkx3rwIEqrB1VmWQmmgJmtA+x55Er9baVlwsXYXxAAlAmP4LKeE60uxEW2nXbPyg4RkaZTq0ymJODdjDtM92acXFkWAqRqRU04MjYpUqbTRLRohqzWmZ3xInWgdBH0ASWQC1BEknv4ls0Oii8y+5sFx/MQ+H+yL/9ZlIgtrzsqi/Md9+Xxoa4NpCiAGql73aynEhSjV5MmcPestwuvWkx+IofiqqV2ZyvuojXtEQxLm5ZIiGgTaiI0HTLpRiay/CmAVfGzreNhymamOmHjCHTQecUsumkZZfZA/wUIKVOVQdrD8fgYCBzTJVCTwMbFoyoXUeul6vcJlv0jWg== 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=VlgU04oud+Cc1/t9I5PoMba063aPhOdg5bkZMbAfiV4=; b=mtvJLpqaWg185cK6N+O6aji0zSEPXYtNTdA1L6pXMsGOl9sFbsdmIBDhcaRwSmOZ/P2f+Iyny062p/wIVgNOpVvgtaq35HNnzXIuOP2C9pJ6wozT9ztR0jHjeobl+PlSj9ntjqGBI6+b0EgxR/zDLN61HMsVICO3AR1m0r89ALXpnbJq2T1VTVIHOVCaehYJkTuxXDwud2XMf4PK2RY/wxY3vqLQGNYvQBZwcr1RS0wk1pMWF/pX5l5hF2mlGxl/jXPWax+ryuMPjzYSlwkcoemuiMcEs7VBX5qhx/y+tjS1D6FVfaVBfSU835F2QPOXyyw9puTbvaUyl82lOVAY+g== 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 Authentication-Results-Original: dkim=none (message not signed) header.d=none;dmarc=none action=none header.from=arm.com; Received: from AM6PR08MB5175.eurprd08.prod.outlook.com (2603:10a6:20b:ef::11) by AM6PR08MB4739.eurprd08.prod.outlook.com (2603:10a6:20b:c6::14) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.4823.18; Wed, 22 Dec 2021 15:56:00 +0000 Received: from AM6PR08MB5175.eurprd08.prod.outlook.com ([fe80::39b0:fa4:8358:9292]) by AM6PR08MB5175.eurprd08.prod.outlook.com ([fe80::39b0:fa4:8358:9292%4]) with mapi id 15.20.4801.020; Wed, 22 Dec 2021 15:56:00 +0000 Message-ID: <0ff57aa7-038e-0ef4-abb7-51c4abb3bdb9@arm.com> Date: Wed, 22 Dec 2021 15:55:58 +0000 User-Agent: Mozilla/5.0 (Windows NT 10.0; Win64; x64; rv:91.0) Gecko/20100101 Thunderbird/91.4.1 Subject: [PATCH][GCC] arm: fix __arm_vld1q_z* and __arm_vst1q_p* intrinsics. To: gcc-patches@gcc.gnu.org X-ClientProxiedBy: LO4P123CA0075.GBRP123.PROD.OUTLOOK.COM (2603:10a6:600:190::8) To AM6PR08MB5175.eurprd08.prod.outlook.com (2603:10a6:20b:ef::11) MIME-Version: 1.0 X-MS-Office365-Filtering-Correlation-Id: 343badac-096f-4cc3-910a-08d9c5639185 X-MS-TrafficTypeDiagnostic: AM6PR08MB4739:EE_|DB5EUR03FT024:EE_|VI1PR08MB4334:EE_ X-Microsoft-Antispam-PRVS: x-checkrecipientrouted: true NoDisclaimer: true X-MS-Oob-TLC-OOBClassifiers: OLM:8273;OLM:8273; X-MS-Exchange-SenderADCheck: 1 X-MS-Exchange-AntiSpam-Relay: 0 X-Microsoft-Antispam-Untrusted: BCL:0; X-Microsoft-Antispam-Message-Info-Original: k+LFSRZ70uqXOHMs8M8S1IbTpn32+DnXMhzZ6YVAcYDei1/pYri/RnRneLehH5dRRd6DMllTB/FxPp09QW8EUptSzu7efIoyyrTqmBZyOnN5jyql7MWZ/ab51LYyBz5w6V+UFnTxEvd4rxzk9BqpxIaEVvGFv9dASEHba+YrqFu3PtNK6YodzQ8VWe2eSj4sx4mcMfi8bfVsyPEYdHbZl4evhAWWMdvFsAIK9wmPCvapvrp7OUqMG2e7g4yfAN+A0gUZW0TQtvOITPiWbwi6pImbStXyrtYUTKlXnIc9zpk/J+aRODUYIYXSWhB1Uj+aM/9JQ7SIBT/GjB6O9B+HW0GOTNbxRopa8skAlOLoaqKqjlRY7QqAWwBYENB/0uSYgzbDVO6D7DRSlmDVkdMiHSm13rnkvJc5snCnLlbzfyg7V4dp6V7mKhQ8rVhMbT34puJ1/g82JnoncWDR+6tR7w+uN4bvG6L5w/j2xhguWPyBAckwmkHVv68RxnqrpRwa3IcuZsHeC4ydlNGSxM2AKd0juTQV9Klaudo03UPjccyYMUjW8+ccRs+YQtj/+7ZPs/Tuz4I/Hl67FZan61QJLlT6m/kBFNvnBXhf2q5eRKMNdtiQzCioxRm1S1E8IeqeGybioTONk03rAgTc8IE9b7ogDE2K7YsnmxMdvlHerP3Dh3v2NkAPxHAe3o9k1PpX0OCT+8MVi1Mo9mq60bHRDml5B2UxoVus9tF2Xi1ADL/VyVuHXN9+8Rwt5D6L74fP/Z8BHVLpiQlgz2HnRtPcmvfzzYidvq7vCDTZApzr7WfCL5iMe878ZuBvotWzassT X-Forefront-Antispam-Report-Untrusted: CIP:255.255.255.255; CTRY:; LANG:en; SCL:1; SRV:; IPV:NLI; SFV:NSPM; H:AM6PR08MB5175.eurprd08.prod.outlook.com; PTR:; CAT:NONE; SFS:(4636009)(366004)(38100700002)(33964004)(84970400001)(86362001)(6916009)(21480400003)(6486002)(8676002)(31696002)(2906002)(8936002)(316002)(31686004)(508600001)(186003)(36756003)(6512007)(44832011)(5660300002)(66946007)(26005)(6506007)(235185007)(66556008)(66476007)(2616005)(45980500001)(43740500002); DIR:OUT; SFP:1101; X-MS-Exchange-Transport-CrossTenantHeadersStamped: AM6PR08MB4739 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: DB5EUR03FT024.eop-EUR03.prod.protection.outlook.com X-MS-PublicTrafficType: Email X-MS-Office365-Filtering-Correlation-Id-Prvs: 0feb88cf-b00d-4ecb-b63a-08d9c5638c7a X-Microsoft-Antispam: BCL:0; X-Microsoft-Antispam-Message-Info: HHALelJx+WMiwTKiwqD5WE1gn4IUoMSFlsgWXQKzlyYnqF29zEmNpHVrWepLlJXBFHMNr/CUGinmc88iA1vNqPzWg/jyg3DphFwPRNlo0nIGiyccv6MF87fFqbcAaVeSLGzJzl5bUp9/T2uyNpxHAPHh8Z0OKsTychGANDiuyOpRAPGrQmsaryUvbsQZoEnY/u26xauAX/odVTMehc+AFyQUFEATzL2Yy64phzc+9lPGYo/7PYe5IzLu3H4Ci5czyxl54pIz0U2TZdOBwLll2569welD6XMMftMx9mIoBRGW411DWdgRUFewXy7BRNUwxLSmxxNzMosoylBsbV1JerwAR/WgZFo3P3zVO10GILDmefa6rZsCa2+AA2VzJvffyIWCP4fYD+M9FyLXbnfNwX7vCFUjU2rmP9TwpyUHnhvIDL1mKbCfePSDNpWSwMNIzprelNEv2hJEEVOBm+GAFX+aHAuOnXV1ms9LX3rq8aZo+wXCCykzARWZqqGGKZ1cp7C3+kUENNoDPIlVBQNpvikFU7rKqaMR13UJ2hQkgAZ6X8cIYoiqh7MIMtGYEe5ReWCnOEBuEBNm66+KTiKhu8FIC/28EqFtOdxeQxRY4bsMA7Nk5gWdizW8LlWGF1BDzyk9tI6JYk5d2gIC5iZibMV3nvBfx8cVE7p+AWois4/ZitpzypLidQZqvCfzKpaFyvDstQL5EzUPQSyO2LvKKpel3K18mI8FWV3fjJ3PqdT+crgVjy/ZrW1iTQPci4Yf3HHvwEyqmxQCLvabjkocGc2a1N49gMOXfK6zkUXoBOzSN3HY1zB92lwK1ulG1OEmxHpmPegAM2BD4QNbSVkcDXJVw5dlWDrWXmJCVJkd4bTfSuuaFm5ClU/lBv2+cNH+ 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:(4636009)(40470700002)(36840700001)(46966006)(8676002)(84970400001)(40460700001)(47076005)(82310400004)(26005)(336012)(316002)(6916009)(186003)(508600001)(235185007)(44832011)(8936002)(6486002)(36860700001)(6512007)(36756003)(81166007)(356005)(2616005)(70586007)(5660300002)(70206006)(31696002)(2906002)(31686004)(21480400003)(86362001)(6506007)(33964004)(43740500002); DIR:OUT; SFP:1101; X-OriginatorOrg: arm.com X-MS-Exchange-CrossTenant-OriginalArrivalTime: 22 Dec 2021 15:56:08.3363 (UTC) X-MS-Exchange-CrossTenant-Network-Message-Id: 343badac-096f-4cc3-910a-08d9c5639185 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: DB5EUR03FT024.eop-EUR03.prod.protection.outlook.com X-MS-Exchange-CrossTenant-AuthAs: Anonymous X-MS-Exchange-CrossTenant-FromEntityHeader: HybridOnPrem X-MS-Exchange-Transport-CrossTenantHeadersStamped: VI1PR08MB4334 X-Spam-Status: No, score=-13.3 required=5.0 tests=BAYES_00, DKIM_SIGNED, DKIM_VALID, GIT_PATCH_0, KAM_SHORT, RCVD_IN_DNSWL_NONE, RCVD_IN_MSPIKE_H2, SPF_HELO_PASS, SPF_PASS, TXREP, UNPARSEABLE_RELAY autolearn=ham autolearn_force=no version=3.4.4 X-Spam-Checker-Version: SpamAssassin 3.4.4 (2020-01-24) on server2.sourceware.org X-BeenThere: gcc-patches@gcc.gnu.org X-Mailman-Version: 2.1.29 Precedence: list List-Id: Gcc-patches mailing list List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-Patchwork-Original-From: Murray Steele via Gcc-patches From: Murray Steele Reply-To: Murray Steele Errors-To: gcc-patches-bounces+patchwork=sourceware.org@gcc.gnu.org Sender: "Gcc-patches" Hi All, This patch fixes the implementation of the existing __arm_vld1q_z* and __arm_vst1q_p* MVE intrinsic functions. The MVE ACLE allows for __ARM_MVE_PRESERVE_USER_NAMESPACE to be defined, which removes definitions for intrinsic functions without the __arm_ prefix. __arm_vld1q_z* and __arm_vst1q_p* are currently implemented via calls to vldr* and vstr*, which results in several compile-time errors when __ARM_MVE_PRESERVE_USER_NAMESPACE is defined. This patch replaces these with calls to their prefixed counterparts, __arm_vldr* and __arm_str*, and adds a test covering the definition of __ARM_MVE_PRESERVE_USER_NAMESPACE. Regression tested on arm-eabi -- no issues. Thanks, Murray gcc/ChangeLog: * config/arm/arm_mve.h (__arm_vst1q_p_u8): Use prefixed intrinsic function. (__arm_vst1q_p_s8): Likewise. (__arm_vld1q_z_u8): Likewise. (__arm_vld1q_z_s8): Likewise. (__arm_vst1q_p_u16): Likewise. (__arm_vst1q_p_s16): Likewise. (__arm_vld1q_z_u16): Likewise. (__arm_vld1q_z_s16): Likewise. (__arm_vst1q_p_u32): Likewise. (__arm_vst1q_p_s32): Likewise. (__arm_vld1q_z_u32): Likewise. (__arm_vld1q_z_s32): Likewise. (__arm_vld1q_z_f16): Likewise. (__arm_vst1q_p_f16): Likewise. (__arm_vld1q_z_f32): Likewise. (__arm_vst1q_p_f32): Likewise. gcc/testsuite/ChangeLog: * gcc.target/arm/mve/general/preserve_user_namespace_1.c: New test. diff --git a/gcc/config/arm/arm_mve.h b/gcc/config/arm/arm_mve.h index e04d46218d03effdf0cb79471108cd2f24e92dec..708f5c71fddfc2cab0b0456e0b8724c803544ddc 100644 --- a/gcc/config/arm/arm_mve.h +++ b/gcc/config/arm/arm_mve.h @@ -16171,14 +16171,14 @@ __extension__ extern __inline void __attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) __arm_vst1q_p_u8 (uint8_t * __addr, uint8x16_t __value, mve_pred16_t __p) { - return vstrbq_p_u8 (__addr, __value, __p); + return __arm_vstrbq_p_u8 (__addr, __value, __p); } __extension__ extern __inline void __attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) __arm_vst1q_p_s8 (int8_t * __addr, int8x16_t __value, mve_pred16_t __p) { - return vstrbq_p_s8 (__addr, __value, __p); + return __arm_vstrbq_p_s8 (__addr, __value, __p); } __extension__ extern __inline void @@ -16203,14 +16203,14 @@ __extension__ extern __inline uint8x16_t __attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) __arm_vld1q_z_u8 (uint8_t const *__base, mve_pred16_t __p) { - return vldrbq_z_u8 ( __base, __p); + return __arm_vldrbq_z_u8 ( __base, __p); } __extension__ extern __inline int8x16_t __attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) __arm_vld1q_z_s8 (int8_t const *__base, mve_pred16_t __p) { - return vldrbq_z_s8 ( __base, __p); + return __arm_vldrbq_z_s8 ( __base, __p); } __extension__ extern __inline int8x16x2_t @@ -16253,14 +16253,14 @@ __extension__ extern __inline void __attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) __arm_vst1q_p_u16 (uint16_t * __addr, uint16x8_t __value, mve_pred16_t __p) { - return vstrhq_p_u16 (__addr, __value, __p); + return __arm_vstrhq_p_u16 (__addr, __value, __p); } __extension__ extern __inline void __attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) __arm_vst1q_p_s16 (int16_t * __addr, int16x8_t __value, mve_pred16_t __p) { - return vstrhq_p_s16 (__addr, __value, __p); + return __arm_vstrhq_p_s16 (__addr, __value, __p); } __extension__ extern __inline void @@ -16285,14 +16285,14 @@ __extension__ extern __inline uint16x8_t __attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) __arm_vld1q_z_u16 (uint16_t const *__base, mve_pred16_t __p) { - return vldrhq_z_u16 ( __base, __p); + return __arm_vldrhq_z_u16 ( __base, __p); } __extension__ extern __inline int16x8_t __attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) __arm_vld1q_z_s16 (int16_t const *__base, mve_pred16_t __p) { - return vldrhq_z_s16 ( __base, __p); + return __arm_vldrhq_z_s16 ( __base, __p); } __extension__ extern __inline int16x8x2_t @@ -16335,14 +16335,14 @@ __extension__ extern __inline void __attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) __arm_vst1q_p_u32 (uint32_t * __addr, uint32x4_t __value, mve_pred16_t __p) { - return vstrwq_p_u32 (__addr, __value, __p); + return __arm_vstrwq_p_u32 (__addr, __value, __p); } __extension__ extern __inline void __attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) __arm_vst1q_p_s32 (int32_t * __addr, int32x4_t __value, mve_pred16_t __p) { - return vstrwq_p_s32 (__addr, __value, __p); + return __arm_vstrwq_p_s32 (__addr, __value, __p); } __extension__ extern __inline void @@ -16367,14 +16367,14 @@ __extension__ extern __inline uint32x4_t __attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) __arm_vld1q_z_u32 (uint32_t const *__base, mve_pred16_t __p) { - return vldrwq_z_u32 ( __base, __p); + return __arm_vldrwq_z_u32 ( __base, __p); } __extension__ extern __inline int32x4_t __attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) __arm_vld1q_z_s32 (int32_t const *__base, mve_pred16_t __p) { - return vldrwq_z_s32 ( __base, __p); + return __arm_vldrwq_z_s32 ( __base, __p); } __extension__ extern __inline int32x4x2_t @@ -19837,7 +19837,7 @@ __extension__ extern __inline float16x8_t __attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) __arm_vld1q_z_f16 (float16_t const *__base, mve_pred16_t __p) { - return vldrhq_z_f16 (__base, __p); + return __arm_vldrhq_z_f16 (__base, __p); } __extension__ extern __inline void @@ -19853,7 +19853,7 @@ __extension__ extern __inline void __attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) __arm_vst1q_p_f16 (float16_t * __addr, float16x8_t __value, mve_pred16_t __p) { - return vstrhq_p_f16 (__addr, __value, __p); + return __arm_vstrhq_p_f16 (__addr, __value, __p); } __extension__ extern __inline float32x4x4_t @@ -19878,7 +19878,7 @@ __extension__ extern __inline float32x4_t __attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) __arm_vld1q_z_f32 (float32_t const *__base, mve_pred16_t __p) { - return vldrwq_z_f32 (__base, __p); + return __arm_vldrwq_z_f32 (__base, __p); } __extension__ extern __inline void @@ -19894,7 +19894,7 @@ __extension__ extern __inline void __attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) __arm_vst1q_p_f32 (float32_t * __addr, float32x4_t __value, mve_pred16_t __p) { - return vstrwq_p_f32 (__addr, __value, __p); + return __arm_vstrwq_p_f32 (__addr, __value, __p); } __extension__ extern __inline float16x8_t diff --git a/gcc/testsuite/gcc.target/arm/mve/general/preserve_user_namespace_1.c b/gcc/testsuite/gcc.target/arm/mve/general/preserve_user_namespace_1.c new file mode 100644 index 0000000000000000000000000000000000000000..f107ac44ca9c6810a9429f332126f82f3f8656ee --- /dev/null +++ b/gcc/testsuite/gcc.target/arm/mve/general/preserve_user_namespace_1.c @@ -0,0 +1,6 @@ +/* { dg-do compile } */ +/* { dg-require-effective-target arm_v8_1m_mve_ok } */ +/* { dg-add-options arm_v8_1m_mve } */ + +#define __ARM_MVE_PRESERVE_USER_NAMESPACE +#include