From mboxrd@z Thu Jan 1 00:00:00 1970 Return-Path: Received: from EUR03-AM7-obe.outbound.protection.outlook.com (mail-am7eur03on2087.outbound.protection.outlook.com [40.107.105.87]) by sourceware.org (Postfix) with ESMTPS id 108C63858D35 for ; Thu, 9 Nov 2023 14:13:22 +0000 (GMT) DMARC-Filter: OpenDMARC Filter v1.4.2 sourceware.org 108C63858D35 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 108C63858D35 Authentication-Results: server2.sourceware.org; arc=pass smtp.remote-ip=40.107.105.87 ARC-Seal: i=3; a=rsa-sha256; d=sourceware.org; s=key; t=1699539203; cv=pass; b=opQ/JFc9ay3xwkaThBFRklwydBTkCbherh/5kLNa6BoHT1tI8b6dyQ6LDI2UKAFBclDNtnY05tEoj+z/YsLAQCrDrls0uXld3AbE8Uzzs1OVcDaWx/ajjmDcjdjVSPIcgYDS4ALllebrNVK1ifTPH4+eXDr9dA61u6PsdwSSLdU= ARC-Message-Signature: i=3; a=rsa-sha256; d=sourceware.org; s=key; t=1699539203; c=relaxed/simple; bh=WfjqasjBXOP0kf9MUAw4QsNbQTVWXgOSAsixcgc2YpE=; h=DKIM-Signature:DKIM-Signature:From:To:Subject:Date:Message-ID: MIME-Version; b=hB9E3sbGntauodccFbMfeFCKp1Ds0pOt2zFm47dHoGMRxWsCD2w5kUp5yPP1acBwlUtqc73W6kit3yfyDcAs0+emPmHkkR5VmeY7iYw7+WqlPP1Vn6ev0fb4YD3Hw9Jsmk4wC0MSLL3N3WIqLr4oaCddnUpvRodLtGAcoEKdOio= ARC-Authentication-Results: i=3; server2.sourceware.org ARC-Seal: i=2; a=rsa-sha256; s=arcselector9901; d=microsoft.com; cv=pass; b=OyQC+r1JmRk5WklPcGY65LZuNjWjFX0y0w4Sfy0Y7ggFrgPgFsjswYyjykkJDuhywme7FLqSu0puSfXa87Se1YjXxxHS/n2+txQay+PK0CKv/QO4rYQ2aTX9OpRNqvD8IfRZr6PP2zEoXHzlSfuzAdfXAyXTSqGw1ZHHcJaBqnka72o1CLNPEw8/jPpjeA2raPmIfPC92kA5N5vHVP9OqhT2PyJSZRHOA7GQ4qv/AJ5nHkfQgCiON8PtqlRZHPj5OMO0n3GqMSvv9lN3dQo1Ko1OpxoKw/aZ4fZfa5BrVtpKtrszGt+0uCUYyYctFMWY5uTMqabPu5IEBWH3GNwAPw== 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=HA0Gpy1fcRen3Ay0hz/40C7OWuH2yslAfdiAA2Blbvw=; b=MRTir7c1nCytl0T6qJMtjd06Mhuv1LMxF1SucHpqUVQgVQchtoHM6YY40/YNWD6z/TFsRvt6Z/V4zkA9E0n8P/i+kDj8hqCC5vdQKPSB5mHChziddDefkzkVIPz59Csk5UoUI+2fhMS9CqRi6s6g/FI8I57G27Ljqb6SqARqtDjBMeAMwR12pdKvfugsqjcOSx5fh9roxKOmz96E8qZHu4YOEAiL4hdpXIKMjwzPxrInlIblhTlR273Y+lO4FteLQ3bzq8T20OqzSXnn3FjTRSdWoNAGZBQ38R/ATV6O5e2Jzo/cYf+h5y+JHT7BAycUWQUMnzvWqUCzj0FBY27mQQ== 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] 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=HA0Gpy1fcRen3Ay0hz/40C7OWuH2yslAfdiAA2Blbvw=; b=OPjDDtVN2Orp7B5MJ7bH2jqk4QellhjstzJI/ev3Nwt9ZqV2jIXhIBhkALxP2WtQP1efF/lMmy96WTdyf4rKlLyKRV481KpRKLAspO+kH66IH8yqemYOe8mnKfIvgQ9OkOdad1jiZSPV57Vtrbyq1XIGpU5FBLZFLXRXuqNjX/w= Received: from DB8P191CA0030.EURP191.PROD.OUTLOOK.COM (2603:10a6:10:130::40) by DU2PR08MB7342.eurprd08.prod.outlook.com (2603:10a6:10:2f1::6) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.6954.28; Thu, 9 Nov 2023 14:13:18 +0000 Received: from DU2PEPF0001E9C3.eurprd03.prod.outlook.com (2603:10a6:10:130:cafe::cd) by DB8P191CA0030.outlook.office365.com (2603:10a6:10:130::40) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.6977.19 via Frontend Transport; Thu, 9 Nov 2023 14:13:18 +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 DU2PEPF0001E9C3.mail.protection.outlook.com (10.167.8.72) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.6977.16 via Frontend Transport; Thu, 9 Nov 2023 14:13:18 +0000 Received: ("Tessian outbound e243565b0037:v228"); Thu, 09 Nov 2023 14:13:18 +0000 X-CheckRecipientChecked: true X-CR-MTA-CID: 90767dd8960bffb2 X-CR-MTA-TID: 64aa7808 Received: from 114849afe090.1 by 64aa7808-outbound-1.mta.getcheckrecipient.com id 5571F61F-8963-4705-A68F-AF26063C19C2.1; Thu, 09 Nov 2023 14:13:11 +0000 Received: from EUR05-DB8-obe.outbound.protection.outlook.com by 64aa7808-outbound-1.mta.getcheckrecipient.com with ESMTPS id 114849afe090.1 (version=TLSv1.2 cipher=ECDHE-RSA-AES256-GCM-SHA384); Thu, 09 Nov 2023 14:13:11 +0000 ARC-Seal: i=1; a=rsa-sha256; s=arcselector9901; d=microsoft.com; cv=none; b=HjVS5X3cfvGI0oFnFWr6JmFPkajEbFFVryFepSTp1IU5DhFMvPsR1y/EDAuH+HLKwJk9uw92rJ7D2EmlzjDi8CaNUFh0R1Wdp0dYJa+6XK2hj3zD2rHWzZul4JvWYlgtwwgwSIgW/9J7qi5QU8b0v4+xYevTjmBoNEBNipcoPr6tdem4m6hnTEUoAOUzBq/ESUqEvqEEodwV2wLOJDhWBqQbw3xhHO3qGT0H942ptmzDog4Ssb3pDO/4+JvbF5STRpHwsJHOO+dKC7SZFEfttzCbHOlnUa5RWksHVGtoYTnC/kMkDP+GZQQGaOEuaSwYYpKqB5WmRFHacRpw+fQAhw== 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=HA0Gpy1fcRen3Ay0hz/40C7OWuH2yslAfdiAA2Blbvw=; b=KSKf/cfg2goGZLH1BTfVs1FGK9195yfKNBcn61sw305xqjkBQNUY/h19gIiSFtQ/YAj+GrOHzmqieYT69BpifOEFKeisbHFYu/inZYbCMT74v/Dx/8lIDSjVJSpECOIpPefhDI85KvS6kW96Rw5+/cwIU0pRChRKfv8pnRoYce3fQqCznbym8bKWcWLwCeR/+3ciE+2p2FVahmo8An2Xr1Dd9UbGc7vt7+JGAyl9ACZ3wTW+JhdeU8+eFkx8GU9GAbfj71OkKTqopGLsn7JxvlDT+N/6+ungKLd77QwOlvGu/blYavPyzRUgr3FzIV7l6By9RMYYFujK7ljkJn/Xmw== ARC-Authentication-Results: i=1; mx.microsoft.com 1; spf=pass (sender ip is 40.67.248.234) smtp.rcpttodomain=gcc.gnu.org smtp.mailfrom=arm.com; dmarc=pass (p=none sp=none pct=100) action=none header.from=arm.com; dkim=none (message not signed); arc=none (0) 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=HA0Gpy1fcRen3Ay0hz/40C7OWuH2yslAfdiAA2Blbvw=; b=OPjDDtVN2Orp7B5MJ7bH2jqk4QellhjstzJI/ev3Nwt9ZqV2jIXhIBhkALxP2WtQP1efF/lMmy96WTdyf4rKlLyKRV481KpRKLAspO+kH66IH8yqemYOe8mnKfIvgQ9OkOdad1jiZSPV57Vtrbyq1XIGpU5FBLZFLXRXuqNjX/w= Received: from DB7PR02CA0026.eurprd02.prod.outlook.com (2603:10a6:10:52::39) by AS8PR08MB8635.eurprd08.prod.outlook.com (2603:10a6:20b:563::12) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.6954.29; Thu, 9 Nov 2023 14:13:10 +0000 Received: from DB5PEPF00014B9D.eurprd02.prod.outlook.com (2603:10a6:10:52:cafe::f) by DB7PR02CA0026.outlook.office365.com (2603:10a6:10:52::39) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.6977.18 via Frontend Transport; Thu, 9 Nov 2023 14:13:10 +0000 X-MS-Exchange-Authentication-Results: spf=pass (sender IP is 40.67.248.234) smtp.mailfrom=arm.com; dkim=none (message not signed) header.d=none;dmarc=pass action=none header.from=arm.com; Received-SPF: Pass (protection.outlook.com: domain of arm.com designates 40.67.248.234 as permitted sender) receiver=protection.outlook.com; client-ip=40.67.248.234; helo=nebula.arm.com; pr=C Received: from nebula.arm.com (40.67.248.234) by DB5PEPF00014B9D.mail.protection.outlook.com (10.167.8.164) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_128_GCM_SHA256) id 15.20.6977.16 via Frontend Transport; Thu, 9 Nov 2023 14:13:10 +0000 Received: from AZ-NEU-EX04.Arm.com (10.251.24.32) by AZ-NEU-EX04.Arm.com (10.251.24.32) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_128_GCM_SHA256) id 15.1.2507.32; Thu, 9 Nov 2023 14:13:09 +0000 Received: from e125768.cambridge.arm.com (10.2.78.50) by mail.arm.com (10.251.24.32) with Microsoft SMTP Server id 15.1.2507.32 via Frontend Transport; Thu, 9 Nov 2023 14:13:08 +0000 From: Victor Do Nascimento To: CC: , , , Victor Do Nascimento Subject: [PATCH 0/5] aarch64: Add ACLE intrinsics codegen support for lrcpc3 instructions Date: Thu, 9 Nov 2023 14:12:43 +0000 Message-ID: <20231109141300.3542453-1-victor.donascimento@arm.com> X-Mailer: git-send-email 2.41.0 MIME-Version: 1.0 Content-Transfer-Encoding: 8bit Content-Type: text/plain X-EOPAttributedMessage: 1 X-MS-TrafficTypeDiagnostic: DB5PEPF00014B9D:EE_|AS8PR08MB8635:EE_|DU2PEPF0001E9C3:EE_|DU2PR08MB7342:EE_ X-MS-Office365-Filtering-Correlation-Id: ffaaaf34-2136-4a35-4cb6-08dbe12e059e 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: YYD68w/Rw6quLSgFEJ15KYwH6gs+N/wMjGxw9cTJ1YW+ZC0kjtlDdkWdoyN33bbcW0Cpq5hQCmrr0WT5KF2v7hkf9s9BMqIJbP2yKS1bU/Azt8yl8tSXwOCavnZAOZ9447Hir4vcp+kw/OWrtn832Y0ESkI47mTj0S05ynywSOcVpYXGq7B9C5FPbk98P6Lf/SEZqCJay6yv3QP1gb4ZqxJzaee5rFdnrHRVNr72eBQWm/yGMqR56fTr80bjUpmY1M5b1Y4M5dTy+ak2vP7LEgyun7zi+csNcNuPho0BsoxFyVqCjXzYJCho1a6nvgTWBTJZK2XPaZJ1IzVZd+Fi/Q6p3q07npTPnTzUIGalIAfulifdDQFBcfesG+KD73NBb8oGLXdmD+fN405bKCGvVBDa/58xY9LKU7BgrEGwOsKhC8U4nywfyy0LgqFfLunHzY8W90Vn9vBkD3PXwy6MmeepiR7SnpAPg3WsYq6dg+R25/5vbSq9V6zDaIaRO4HmFtERK+Kkd4Vm436G+IQHMdCuywI6rP2v7qNJ/yzZFxQ3xATXPiZofbc0V43PIhnsUmHor8S9SuBp0vFgW/2cVcEFBiV/CXDG6cPnym1wqlog/boliU5pthtaYWVaKsK1yvJL7oeJr14QmyZDCuabru6Nyk/lHSPy39hNoyDfEH08vJeOq28zQdSQJCjaRFR/TnpD2NMzXEqVv4UzZyl/YlckYXRHz5uZ1Pm2wWVCA1Pt/227tgQ807oHsZWG7yt93OY9t3/zRapxIvdb5YeHow== X-Forefront-Antispam-Report-Untrusted: CIP:40.67.248.234;CTRY:IE;LANG:en;SCL:1;SRV:;IPV:NLI;SFV:NSPM;H:nebula.arm.com;PTR:InfoDomainNonexistent;CAT:NONE;SFS:(13230031)(4636009)(136003)(376002)(346002)(396003)(39860400002)(230922051799003)(64100799003)(451199024)(82310400011)(186009)(1800799009)(36840700001)(40470700004)(46966006)(40460700003)(40480700001)(478600001)(82740400003)(83380400001)(36756003)(7696005)(86362001)(356005)(47076005)(81166007)(36860700001)(41300700001)(70206006)(1076003)(70586007)(426003)(6666004)(336012)(2906002)(26005)(316002)(5660300002)(2616005)(4326008)(8676002)(6916009)(8936002)(54906003)(36900700001);DIR:OUT;SFP:1101; X-MS-Exchange-Transport-CrossTenantHeadersStamped: AS8PR08MB8635 X-MS-Exchange-Transport-CrossTenantHeadersStripped: DU2PEPF0001E9C3.eurprd03.prod.outlook.com X-MS-PublicTrafficType: Email X-MS-Office365-Filtering-Correlation-Id-Prvs: ef8a4241-b032-44da-4cbf-08dbe12e00c8 X-Microsoft-Antispam: BCL:0; X-Microsoft-Antispam-Message-Info: fcZh0+5FYfKI1QiS6HC+xtm6EzeqmYftjBNKzB6XUq/L8Kh1k1h/A720OAzVsyAmDQKO67Jf/kRHS5KSZd9UDMarbeWanko1UmV3GRdRZD5wBfeP5pbHgX/+tKFSRC+GcoM2+76NMMPxJWaHGmAwXyFGi0/jZ20/4yQlcsMTNa9HIEmY2yvxnj4DYURubdDniWrjWllhvWmeN3/9+lTk8seYy/IRokMDoLgkbdJQMhe70QnAvRhKrHq1la+FyqKNAKEzO/rJwFrnf72hEAJCKAVWsTDr7KpNmdbfpvPuDVEhJZb4jYfxoG1HkAeBd1Tkda6x8bGcNeY+TfDWtaACp/4giDbM6Wry3cB9/HCqjBk3rPkx/9844KtPsdaKsecikLI75cP4yZKS/zPEG74iYUt6tCFH312ePdwoao6BiG0lKgYoBkjPKF9htkgVx+rWe3WurgumbEbKA3sqg0c45xznd8vlu91YzlDoyhx33p4jFzBxgVgjD4n5eKN5KFhek2MmABpfhDnidtlZypZ+JVvbxVq3M09Q1lMpVR5CVf+7MPH7qU72pK6n6YSHfiVF0MvkHN97GyrKjPGPSCS+LaLOQH147qa7KFHvLm+BAECPtEN13RpD4mLHRWaEZZ5jRVoJgt5cajpZQLRKxeGiP21oOD0n6hFly2uBwYnUPkqeZESUv5jk0UqTpdMVrxqOymqjs9ikSVLIM9FAR1sSJOZjweQQnAV9XhocfTiVRwHYKZEq77vkCWmjN9x5edQl 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)(39850400004)(346002)(396003)(376002)(136003)(230922051799003)(64100799003)(186009)(451199024)(82310400011)(1800799009)(40470700004)(36840700001)(46966006)(36860700001)(2906002)(41300700001)(7696005)(6916009)(316002)(54906003)(478600001)(8936002)(5660300002)(4326008)(8676002)(70586007)(70206006)(36756003)(47076005)(40480700001)(86362001)(1076003)(81166007)(83380400001)(426003)(40460700003)(336012)(82740400003)(2616005)(6666004)(26005);DIR:OUT;SFP:1101; X-OriginatorOrg: arm.com X-MS-Exchange-CrossTenant-OriginalArrivalTime: 09 Nov 2023 14:13:18.1906 (UTC) X-MS-Exchange-CrossTenant-Network-Message-Id: ffaaaf34-2136-4a35-4cb6-08dbe12e059e 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: DU2PEPF0001E9C3.eurprd03.prod.outlook.com X-MS-Exchange-CrossTenant-AuthAs: Anonymous X-MS-Exchange-CrossTenant-FromEntityHeader: HybridOnPrem X-MS-Exchange-Transport-CrossTenantHeadersStamped: DU2PR08MB7342 X-Spam-Status: No, score=-6.5 required=5.0 tests=BAYES_00,DKIM_SIGNED,DKIM_VALID,FORGED_SPF_HELO,KAM_DMARC_NONE,KAM_SHORT,RCVD_IN_DNSWL_NONE,RCVD_IN_MSPIKE_H2,SPF_HELO_PASS,SPF_NONE,TXREP,T_SCC_BODY_TEXT_LINE,UNPARSEABLE_RELAY autolearn=no autolearn_force=no version=3.4.6 X-Spam-Checker-Version: SpamAssassin 3.4.6 (2021-04-09) on server2.sourceware.org List-Id: Given the introduction of the third set of Release Consistency processor consistent (RCpc) memory model-compliant instructions in the form of FEAT_LRCPC3 as an optional extension from Armv8.2-a onward, this patch series adds the RCPC3 ACLE Neon intrinsics, thus enabling the use of the architectural feature in C. These intrinsics enable the use of the new LDAP1 and STL1 instructions and are given single and twin-lane variants for unsigned, signed and poly 64-bit values, in the form of the following builtin-functions: * vldap1_lane_{u|s|p}64 * vldap1q_lane_{u|s|p}64 * ldp1_lane_{u|s|p}64 * ldp1q_lane_{u|s|p}64 Bootstrapped and regression tested on aarch64-none-linux-gnu. Victor Do Nascimento (5): aarch64: rcpc3: Add +rcpc3 extension aarch64: rcpc3: Add relevant iterators to handle Neon intrinsics aarch64: rcpc3: Add Neon ACLE intrinsics aarch64: rcpc3: add Neon ACLE wrapper functions to `arm_neon.h' aarch64: rcpc3: Add intrinsics tests .../aarch64/aarch64-option-extensions.def | 1 + gcc/config/aarch64/aarch64-simd-builtins.def | 7 + gcc/config/aarch64/aarch64-simd.md | 65 +++++++++ gcc/config/aarch64/aarch64.h | 4 + gcc/config/aarch64/aarch64.md | 2 + gcc/config/aarch64/arm_neon.h | 129 ++++++++++++++++++ gcc/config/aarch64/iterators.md | 25 ++-- gcc/doc/invoke.texi | 4 + gcc/testsuite/gcc.target/aarch64/acle/rcpc3.c | 47 +++++++ 9 files changed, 276 insertions(+), 8 deletions(-) create mode 100644 gcc/testsuite/gcc.target/aarch64/acle/rcpc3.c -- 2.41.0