From patchwork Thu Nov 9 14:12:44 2023 Content-Type: text/plain; charset="utf-8" MIME-Version: 1.0 Content-Transfer-Encoding: 7bit X-Patchwork-Submitter: Victor Do Nascimento X-Patchwork-Id: 1862106 Return-Path: X-Original-To: incoming@patchwork.ozlabs.org Delivered-To: patchwork-incoming@legolas.ozlabs.org Authentication-Results: legolas.ozlabs.org; dkim=pass (1024-bit key; unprotected) header.d=armh.onmicrosoft.com header.i=@armh.onmicrosoft.com header.a=rsa-sha256 header.s=selector2-armh-onmicrosoft-com header.b=fCv5eTDL; dkim=pass (1024-bit key) header.d=armh.onmicrosoft.com header.i=@armh.onmicrosoft.com header.a=rsa-sha256 header.s=selector2-armh-onmicrosoft-com header.b=fCv5eTDL; dkim-atps=neutral Authentication-Results: legolas.ozlabs.org; spf=pass (sender SPF authorized) smtp.mailfrom=gcc.gnu.org (client-ip=2620:52:3:1:0:246e:9693:128c; helo=server2.sourceware.org; envelope-from=gcc-patches-bounces+incoming=patchwork.ozlabs.org@gcc.gnu.org; receiver=patchwork.ozlabs.org) Received: from server2.sourceware.org (server2.sourceware.org [IPv6:2620:52:3:1:0:246e:9693:128c]) (using TLSv1.3 with cipher TLS_AES_256_GCM_SHA384 (256/256 bits) key-exchange X25519 server-signature ECDSA (secp384r1) server-digest SHA384) (No client certificate requested) by legolas.ozlabs.org (Postfix) with ESMTPS id 4SR3qp15WMz1yRF for ; Fri, 10 Nov 2023 01:14:46 +1100 (AEDT) Received: from server2.sourceware.org (localhost [IPv6:::1]) by sourceware.org (Postfix) with ESMTP id 1BAF138618BF for ; Thu, 9 Nov 2023 14:14:42 +0000 (GMT) X-Original-To: gcc-patches@gcc.gnu.org Delivered-To: gcc-patches@gcc.gnu.org Received: from EUR02-VI1-obe.outbound.protection.outlook.com (mail-vi1eur02on2049.outbound.protection.outlook.com [40.107.241.49]) by sourceware.org (Postfix) with ESMTPS id DF3C538582BC for ; Thu, 9 Nov 2023 14:13:27 +0000 (GMT) DMARC-Filter: OpenDMARC Filter v1.4.2 sourceware.org DF3C538582BC 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 DF3C538582BC Authentication-Results: server2.sourceware.org; arc=pass smtp.remote-ip=40.107.241.49 ARC-Seal: i=3; a=rsa-sha256; d=sourceware.org; s=key; t=1699539209; cv=pass; b=H0ihJUE+LniAxuP6anpQ6IF0n6lgTbYxgQTJAjH6zAaZFxm25/Epj1n+AIRV8NxU+eS2Kz+yQmYHOOnlvnnQPEJ2Q++BzZ1go1xZJps8thhrYH6M51kqOhPGAVpSKvZlOkLNTblyP49ulV+tnnw2YoLKKUElRB5NV1w57OQIqgM= ARC-Message-Signature: i=3; a=rsa-sha256; d=sourceware.org; s=key; t=1699539209; c=relaxed/simple; bh=qyXDXAsy3du1MMyur8cAlsHALbb8r7DSW/boJPpF9XE=; h=DKIM-Signature:DKIM-Signature:From:To:Subject:Date:Message-ID: MIME-Version; b=uoT+9duC2R1X2skCYwKGWNVN1stL+F/3UAj6t9lppY0p+/93zxytK/fxUjnSD5WLVKhzZGwd+PFgrladyOqdU+2yt1VW2z3j51fs6Gfu/vOJhaj3GzUhawkcYLTgPUS/l5DfkODvueMVxtwBESpuLd8vEm5+B487qfMwGw8SMVI= ARC-Authentication-Results: i=3; server2.sourceware.org ARC-Seal: i=2; a=rsa-sha256; s=arcselector9901; d=microsoft.com; cv=pass; b=ek3zhws7MRlkBpPyxmYdSN5BVJosYex0mWmDyx9PclYMC3fD2Clya0PM90FESQYutiQNbPTMShe+w5LtHYUJ1MjzKtsWA7YWmGH07tbJJ4BRcaSc9uy1OR6YKCpGboe3gjHW6fUBoiWS/FtU68UGpNosLr8v0JuvblgXYa6i7cMdCzGHTuNw7TpECzhMa4oFvawd/liULA1/LYDvq/muVw4DlLoSgIkjd4DRorG1M3+4zpzvVusCqbtd5kUUTwLVNzZCPHHghlnSh3oWLS9/8hh8cM7Onsy5fdQG8RjwRkaOXfvYCIKhgjThcVItgpEaxrB+I0eNNKs6pNMk7Ov/9g== 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=dD1853qYWjSO5Ub9BtRLNbFOc3P01PtCpWTQ4t51y2Y=; b=O7Q+QGVAUpRF6VoG6L//WVPjFm2nDghvkOzBRZbCPNI+bgTJg25dgK0JpzIqxUwjGpIK94WwL0aUUggeXsqQ7IOOAXC/UUDIchJZlGC2X7BNYmp6xkPM+VUsu1UjDM414GJ/vv649o6YbNILTAWEfytcmHr5BKTZziTQttus2GkcvkTO244Z9F5LKHeNpBe3cWsGJNE4w7hy8QbXVivnMmLwkQzaaRLeUIhDaf7UbensFWTWLD80LPAyVjhPaZrCDomfjpLGiEtW6rX1EDL6m2jzycC17zWMdbmdd/PPuhiIYjac79ymYy8h9NdAITMOjnHmGnHbnYircWC8mWi71A== 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=dD1853qYWjSO5Ub9BtRLNbFOc3P01PtCpWTQ4t51y2Y=; b=fCv5eTDLtZgGC+q+iYgOJnlUTqRLfcSPHUjQw92cIHHiu1YUYO44Z7AcerXUH45LRQqnk+JBj17ffm+QK4lU/7soyCyd34eBUJKDcMxtEffBLh17WitVWeUn5/s9otFFqf7R+X2EE7pGix/rkcB21xNMjICb1oQdoiI6dJQQsG0= Received: from DB8PR06CA0012.eurprd06.prod.outlook.com (2603:10a6:10:100::25) by AM9PR08MB6116.eurprd08.prod.outlook.com (2603:10a6:20b:2d4::17) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.6977.18; Thu, 9 Nov 2023 14:13:23 +0000 Received: from DU6PEPF0000B620.eurprd02.prod.outlook.com (2603:10a6:10:100:cafe::27) by DB8PR06CA0012.outlook.office365.com (2603:10a6:10:100::25) 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:23 +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 DU6PEPF0000B620.mail.protection.outlook.com (10.167.8.136) 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:23 +0000 Received: ("Tessian outbound 26ee1d40577c:v228"); Thu, 09 Nov 2023 14:13:23 +0000 X-CheckRecipientChecked: true X-CR-MTA-CID: b96b23bfe078c85e X-CR-MTA-TID: 64aa7808 Received: from 3f585a0d6f03.1 by 64aa7808-outbound-1.mta.getcheckrecipient.com id 36011975-557C-44B1-B36D-5D6250C96777.1; Thu, 09 Nov 2023 14:13:17 +0000 Received: from EUR05-VI1-obe.outbound.protection.outlook.com by 64aa7808-outbound-1.mta.getcheckrecipient.com with ESMTPS id 3f585a0d6f03.1 (version=TLSv1.2 cipher=ECDHE-RSA-AES256-GCM-SHA384); Thu, 09 Nov 2023 14:13:17 +0000 ARC-Seal: i=1; a=rsa-sha256; s=arcselector9901; d=microsoft.com; cv=none; b=kH/HlD+uCa7VFlynxJxJnISVKoCbcUhSk2NvphM8q8qFGb6v6jNVyw6qrpmYaholx8yCpOFVdxOGxC3I0xDdrw4m2VVjJX7OxMWSIc9Y35naToBtTk8RTuQpXL0bJLf5VMdXF4pBuLjdyfwnLgtdeCL2pLQrl3BUwRI9bH3A6uvbe4Q31KQ8D4PN3PUkn44TfAERHkmNZjay3wVWprREIh244RlU5Lafi0EPVQ+RoBZMKs36bvLITDJZZq0NBr9PL+T/ToFoMj7ybWYXyM91gAFj42DM5cxdz+PvEBB39aQ1Zuum5sTpy/OApdSHjKp/yoeJHe5UqjTy2D+Gn8vfTQ== 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=dD1853qYWjSO5Ub9BtRLNbFOc3P01PtCpWTQ4t51y2Y=; b=d6qekYgSKWen1z52wQe1D8JdhBhQ3V5eYyNUeyLqeHiS5V4g0nczax+IV8Glr9ymazlKp0l0CpyNoM78M6PTXCfloLn3kzkErdQdmxERB6nMDwXDAS9hsiAIdjKlU0dB0hB1vLBfoMymYeHek6AfVHn7qjsYjyMkX5JYXxJTQ1gg5ZaOiGuymNHhQ5ONywQZo8Djbi1pI0m+hhipGJQhYsOQcWy7PK4S2ho0zkz3YvArAlYLjR/1EljteH1TPaVhpleVSdBWTRgBc/g189wZe6NwGqOg7UgF1XoykndppvnmY7V7MtnG8uADNc3NyabyWWFscDdMuTM8szYzSKGXaA== 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=dD1853qYWjSO5Ub9BtRLNbFOc3P01PtCpWTQ4t51y2Y=; b=fCv5eTDLtZgGC+q+iYgOJnlUTqRLfcSPHUjQw92cIHHiu1YUYO44Z7AcerXUH45LRQqnk+JBj17ffm+QK4lU/7soyCyd34eBUJKDcMxtEffBLh17WitVWeUn5/s9otFFqf7R+X2EE7pGix/rkcB21xNMjICb1oQdoiI6dJQQsG0= Received: from DU6P191CA0012.EURP191.PROD.OUTLOOK.COM (2603:10a6:10:540::12) by AM9PR08MB6211.eurprd08.prod.outlook.com (2603:10a6:20b:2de::14) 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:12 +0000 Received: from DB5PEPF00014B9E.eurprd02.prod.outlook.com (2603:10a6:10:540:cafe::62) by DU6P191CA0012.outlook.office365.com (2603:10a6:10:540::12) 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:11 +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 DB5PEPF00014B9E.mail.protection.outlook.com (10.167.8.171) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_128_GCM_SHA256) id 15.20.6977.18 via Frontend Transport; Thu, 9 Nov 2023 14:13:11 +0000 Received: from AZ-NEU-EX02.Emea.Arm.com (10.251.26.5) 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 AZ-NEU-EX04.Arm.com (10.251.24.32) by AZ-NEU-EX02.Emea.Arm.com (10.251.26.5) 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:09 +0000 From: Victor Do Nascimento To: CC: , , , Victor Do Nascimento Subject: [PATCH 1/5] aarch64: rcpc3: Add +rcpc3 extension Date: Thu, 9 Nov 2023 14:12:44 +0000 Message-ID: <20231109141300.3542453-2-victor.donascimento@arm.com> X-Mailer: git-send-email 2.41.0 In-Reply-To: <20231109141300.3542453-1-victor.donascimento@arm.com> References: <20231109141300.3542453-1-victor.donascimento@arm.com> MIME-Version: 1.0 X-EOPAttributedMessage: 1 X-MS-TrafficTypeDiagnostic: DB5PEPF00014B9E:EE_|AM9PR08MB6211:EE_|DU6PEPF0000B620:EE_|AM9PR08MB6116:EE_ X-MS-Office365-Filtering-Correlation-Id: e42afa91-16b0-478f-da87-08dbe12e08e4 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: 6BWOIqtNxx79Un4P6sRlDRPyBRxPL987/EiZYCVoMVgKynaeAsOwCFtOUA+TflvHnz35xqQbXblaG8+lYxcUzJ0f0RorLz2KpUmg2hI8BgVoyvYVNIW2HrqwfpfZzId0wyymh/iVxgFG/oO/Ul5NzeAZ25qRHaFn0QCtgDDb4WTre6lvMklctX6LH/zAHWTf/fT7p4L9IYXDp7Thp6PKoyDyk6elvR26nSWMmQA44IsKVNSqU5Ab0lJukdUCchyto9aElbixByoWf0x6qBk2axmaP+PECQgxD8Gikae3gCIB+SBw9vfU66EDnLuFAj66KLBKfLdqxsjz4gWM24Wz0mM+EsPL8qUBrqkXnv4uHUrb0peF58eGwc1mfD6f7bd4aa7DPsgLl02ggUi+qHzUqug4PTAKcPhDQ+g2IQ3pBrL6I0pDhVndOYyfdcMgJ/09nItz23vQvRh4EMpy1koKRMwdPy/nvDUVljWYYdXMtUY3clcvdouAxLyEU+J2rG6xuO/fOvbkFOqdF8FaeDU5E/jq5kjNaoRxVadQ4JrMdSJVh4xBQmZqtsJHovrcZZ2cj2VQyhY8gBPVnUR3A/w88qbfZmL93upyG92zxMKHWNULkwhZyVB/s4RDg5VV61C1DGsObHOQI+5zTCMkf3Wxj/XB3zrS5ybgzW5/ayuO8otHDyFHjQ+D3LAQLUczfCTs9RrX6ZV1oBbaXILnaYd3LI93ySZDvOB6hVLlsy7tL89HpOxshe2vhTL30MTb2a8OBm3wVIyAHvc6MGoZl9r2zg== 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)(376002)(396003)(136003)(346002)(39860400002)(230922051799003)(1800799009)(82310400011)(186009)(64100799003)(451199024)(40470700004)(46966006)(36840700001)(47076005)(41300700001)(7696005)(2616005)(478600001)(6666004)(26005)(336012)(4326008)(8676002)(316002)(8936002)(5660300002)(70586007)(36860700001)(1076003)(54906003)(70206006)(6916009)(356005)(426003)(81166007)(2906002)(86362001)(82740400003)(40480700001)(36756003)(40460700003)(36900700001); DIR:OUT; SFP:1101; X-MS-Exchange-Transport-CrossTenantHeadersStamped: AM9PR08MB6211 X-MS-Exchange-Transport-CrossTenantHeadersStripped: DU6PEPF0000B620.eurprd02.prod.outlook.com X-MS-PublicTrafficType: Email X-MS-Office365-Filtering-Correlation-Id-Prvs: b1ae1d1f-a8d7-4856-2c5b-08dbe12e01e6 X-Microsoft-Antispam: BCL:0; X-Microsoft-Antispam-Message-Info: WCYXqV3RKLFaDKFHuBOePVlC2XvK3g3nM2iQtxKSQX07HAP2vCsurvNq5Uub4fwqSCL+ncmmKMjE36GlnswKse1eczBhyBuT+pEH/m7wgeUdHx5QUPv1q7Nu85cvxNAP4AsrStRJ/L1KbSV9J2mlEDxgNU5w07PWeXQ2n56+zuuWKqnvomaiHD39aU1RHmjWOjc9b499aTluB/7Dq1MTt1Y2/V7B0bLqR5U8nE1B45H6DPSd7M1/mI7g7/antfG7TZ6JZNRkryhCybguPnrgP2ZrlYst7Nbb+wivzgohMmEf+dcNtyYm9t1qP2qKo5SSN2WyLRjNmLoPR9taQuLBNdpziOcYdOldm3gvJTG0wH6Ah7RG6UEs7vv0uqvaMQ+ZeZUCUshnksMJ6TfksRg2kmKUYoMVuU6ZC1T8INLP9Np9C3F+T3xq0cq3e5RTxGS7JOxT7Ddw9MxOLAaB3n6ljKbxj0qLs25EA1vICNqZd0DW7wV/BJMKPLPWwutRLOc20keftnVoWkwRhhEWHSKlCfIUPd9B++Fh+Crm78KtJ0wBZAJIjdOLHHPOPOrrZWTPcETw5VCu1Z1+0DUxgYW3RzTpsZpmhykOoW/s3Sqx8egytCGrZMf5tNhHnf1C632wR5AKvLvDBdJKOph/OfXFHJN1WA8Muo8FKTrpXCOik/hPBYl9FbmRjdn8EF2quT9/IzmMGzACiVUQPCFwfcjvmnd5C1acjoxXQ/PxjnbTx4Tfa/RqIIBBKhtghh0rCo1f 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)(346002)(136003)(396003)(376002)(39860400002)(230922051799003)(64100799003)(451199024)(186009)(1800799009)(82310400011)(40470700004)(36840700001)(46966006)(40480700001)(40460700003)(2616005)(478600001)(7696005)(6666004)(36860700001)(36756003)(81166007)(82740400003)(86362001)(5660300002)(70206006)(41300700001)(47076005)(426003)(336012)(2906002)(26005)(1076003)(8676002)(70586007)(316002)(54906003)(8936002)(6916009)(4326008); DIR:OUT; SFP:1101; X-OriginatorOrg: arm.com X-MS-Exchange-CrossTenant-OriginalArrivalTime: 09 Nov 2023 14:13:23.7018 (UTC) X-MS-Exchange-CrossTenant-Network-Message-Id: e42afa91-16b0-478f-da87-08dbe12e08e4 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: DU6PEPF0000B620.eurprd02.prod.outlook.com X-MS-Exchange-CrossTenant-AuthAs: Anonymous X-MS-Exchange-CrossTenant-FromEntityHeader: HybridOnPrem X-MS-Exchange-Transport-CrossTenantHeadersStamped: AM9PR08MB6116 X-Spam-Status: No, score=-12.5 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 X-BeenThere: gcc-patches@gcc.gnu.org X-Mailman-Version: 2.1.30 Precedence: list List-Id: Gcc-patches mailing list List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , Errors-To: gcc-patches-bounces+incoming=patchwork.ozlabs.org@gcc.gnu.org Given the optional LRCPC3 target support for Armv8.2-a cores onwards, the +rcpc3 arch feature modifier is added to GCC's command-line options. gcc/ChangeLog: * config/aarch64/aarch64-option-extensions.def (rcpc3): New. * config/aarch64/aarch64.h (AARCH64_ISA_RCPC3): Likewise. (TARGET_RCPC3): Likewise. * doc/invoke.texi (rcpc3): Document feature in AArch64 Options. --- gcc/config/aarch64/aarch64-option-extensions.def | 1 + gcc/config/aarch64/aarch64.h | 4 ++++ gcc/doc/invoke.texi | 4 ++++ 3 files changed, 9 insertions(+) diff --git a/gcc/config/aarch64/aarch64-option-extensions.def b/gcc/config/aarch64/aarch64-option-extensions.def index 825f3bf7758..2ab94799d34 100644 --- a/gcc/config/aarch64/aarch64-option-extensions.def +++ b/gcc/config/aarch64/aarch64-option-extensions.def @@ -151,4 +151,5 @@ AARCH64_OPT_EXTENSION("mops", MOPS, (), (), (), "") AARCH64_OPT_EXTENSION("cssc", CSSC, (), (), (), "cssc") +AARCH64_OPT_EXTENSION("rcpc3", RCPC3, (), (), (), "rcpc3") #undef AARCH64_OPT_EXTENSION diff --git a/gcc/config/aarch64/aarch64.h b/gcc/config/aarch64/aarch64.h index 2f0777a37ac..68bbaccef1a 100644 --- a/gcc/config/aarch64/aarch64.h +++ b/gcc/config/aarch64/aarch64.h @@ -213,6 +213,7 @@ enum class aarch64_feature : unsigned char { #define AARCH64_ISA_F64MM (aarch64_isa_flags & AARCH64_FL_F64MM) #define AARCH64_ISA_BF16 (aarch64_isa_flags & AARCH64_FL_BF16) #define AARCH64_ISA_SB (aarch64_isa_flags & AARCH64_FL_SB) +#define AARCH64_ISA_RCPC3 (aarch64_isa_flags & AARCH64_FL_RCPC3) #define AARCH64_ISA_V8R (aarch64_isa_flags & AARCH64_FL_V8R) #define AARCH64_ISA_PAUTH (aarch64_isa_flags & AARCH64_FL_PAUTH) #define AARCH64_ISA_V9A (aarch64_isa_flags & AARCH64_FL_V9A) @@ -344,6 +345,9 @@ enum class aarch64_feature : unsigned char { and sign-extending versions.*/ #define TARGET_RCPC2 (AARCH64_ISA_RCPC8_4) +/* RCPC3 LDAP1/STL1 loads/stores from Armv8.2-a. */ +#define TARGET_RCPC3 (AARCH64_ISA_RCPC3) + /* Apply the workaround for Cortex-A53 erratum 835769. */ #define TARGET_FIX_ERR_A53_835769 \ ((aarch64_fix_a53_err835769 == 2) \ diff --git a/gcc/doc/invoke.texi b/gcc/doc/invoke.texi index 6e776a0faa1..ba28eb195ce 100644 --- a/gcc/doc/invoke.texi +++ b/gcc/doc/invoke.texi @@ -21028,6 +21028,10 @@ Enable the Flag Manipulation instructions Extension. Enable the Pointer Authentication Extension. @item cssc Enable the Common Short Sequence Compression instructions. +@item rcpc3 +Enable the RCpc3 extension. This enables the use of the LDAP1 and +STL1 instructions for loads/stores of 64-bit values to and from SIMD +register lanes, passing these on to the assembler. @end table From patchwork Thu Nov 9 14:12:45 2023 Content-Type: text/plain; charset="utf-8" MIME-Version: 1.0 Content-Transfer-Encoding: 7bit X-Patchwork-Submitter: Victor Do Nascimento X-Patchwork-Id: 1862101 Return-Path: X-Original-To: incoming@patchwork.ozlabs.org Delivered-To: patchwork-incoming@legolas.ozlabs.org Authentication-Results: legolas.ozlabs.org; dkim=pass (1024-bit key; unprotected) header.d=armh.onmicrosoft.com header.i=@armh.onmicrosoft.com header.a=rsa-sha256 header.s=selector2-armh-onmicrosoft-com header.b=bdxtHiiC; dkim=pass (1024-bit key) header.d=armh.onmicrosoft.com header.i=@armh.onmicrosoft.com header.a=rsa-sha256 header.s=selector2-armh-onmicrosoft-com header.b=bdxtHiiC; dkim-atps=neutral Authentication-Results: legolas.ozlabs.org; spf=pass (sender SPF authorized) smtp.mailfrom=gcc.gnu.org (client-ip=2620:52:3:1:0:246e:9693:128c; helo=server2.sourceware.org; envelope-from=gcc-patches-bounces+incoming=patchwork.ozlabs.org@gcc.gnu.org; receiver=patchwork.ozlabs.org) Received: from server2.sourceware.org (server2.sourceware.org [IPv6:2620:52:3:1:0:246e:9693:128c]) (using TLSv1.3 with cipher TLS_AES_256_GCM_SHA384 (256/256 bits) key-exchange X25519 server-signature ECDSA (secp384r1) server-digest SHA384) (No client certificate requested) by legolas.ozlabs.org (Postfix) with ESMTPS id 4SR3pg1G74z1yRF for ; Fri, 10 Nov 2023 01:13:47 +1100 (AEDT) Received: from server2.sourceware.org (localhost [IPv6:::1]) by sourceware.org (Postfix) with ESMTP id BD01A386189B for ; Thu, 9 Nov 2023 14:13:41 +0000 (GMT) X-Original-To: gcc-patches@gcc.gnu.org Delivered-To: gcc-patches@gcc.gnu.org Received: from EUR05-AM6-obe.outbound.protection.outlook.com (mail-am6eur05on2074.outbound.protection.outlook.com [40.107.22.74]) by sourceware.org (Postfix) with ESMTPS id 43DAA3857009 for ; Thu, 9 Nov 2023 14:13:26 +0000 (GMT) DMARC-Filter: OpenDMARC Filter v1.4.2 sourceware.org 43DAA3857009 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 43DAA3857009 Authentication-Results: server2.sourceware.org; arc=pass smtp.remote-ip=40.107.22.74 ARC-Seal: i=3; a=rsa-sha256; d=sourceware.org; s=key; t=1699539208; cv=pass; b=VjwAOtoOKk+pwTKbt7B4mNmjUKPp+e88zRrdD/X3Rzfe0msX+SGjpq3D1p8LC797bvsH96k6jTx3Usj8jw7mrUoL4uPTwjt5OWWyKOWGxyG38nlSnLQsivz0nOXaxiIBJElChGzBDM+lNL/J9HK8iIumZ97bxM1aO2CUM3rki6M= ARC-Message-Signature: i=3; a=rsa-sha256; d=sourceware.org; s=key; t=1699539208; c=relaxed/simple; bh=xji84LTFkWvDyPXCaqB4lXaL7UcLG2RJu4sWi+rfHfU=; h=DKIM-Signature:DKIM-Signature:From:To:Subject:Date:Message-ID: MIME-Version; b=UfX+Zp/wcWMmoclvU/8WQCGc+5f86+nGk+rC8xpHEH+1Lq+yYPneOyg6KOctz2Htq2OnzLICrXetzLTXgqjVHvchfEKfzqPKF15gtPdKZaxNf+R7bD6P+pghHdxSVZu1CBcvP06xtkHzlIbcSpPO/phKdEHuhVoSJFYtC5i0JAc= ARC-Authentication-Results: i=3; server2.sourceware.org ARC-Seal: i=2; a=rsa-sha256; s=arcselector9901; d=microsoft.com; cv=pass; b=M4kKUzgkj4AYyo2j5s1iypEkcsJ52tUEcT+JOcBN+kkPVzjOdAnte0ivxdcd5mPOtwEiyk3+8iaSdbqdw5fpUWfTf4K+zApiI9n/668HD9wB0yADU/cWkHsx1uata05dkxak1xshV/JEdA85Y1EO00xbiwxSkIpR49qXeYCxjfUwySj+oVs3JIjP3P6loLHOAkqN4KROO9gRcGZK6tDAO8FV0RixuVp5i3wwPQ0XhIM0bYACjxXxjoYc47Bmy1uIx2HPMV0XuzrfcZA0uge0/TH+iEWC9MHK6uAHOO3O4TamrnEeMToNVPRZ0k7fK9tuQ/7MbxkW9kepKE5SBTW8fQ== 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=IM0nM4nxg+MmMeBuNeOLT0ZhCTNeaP6GBTrOvA4MVz4=; b=GNiXSoUlGaMkoO+TY5VplgUUDJHNt6hwaJBCzQo3nV1enDpTmDIhk3c3WeplVTUDUUMlFBL6U+aWJ9A5UJboZd6ppMKHDYtEMryKhlM8hpOCu9FDsQEC1AtEyvrPs+/5c9gPee48PNF/vPom03LEBaLLfh05G/gKdcuhjDcO1VLusxXayPF8LaamJHl9X1shwL9m9JLN+BVM8a73RHwT7b4SS890nL/GW+KXo6EVPtY6wKrBxYkvESKFAhuOYMWCeD3sp4Kes3yysnQrhT0qmkI/FVXIWZI2xLhMYuxndtbyFtoY7tUrpt16uQNYRBhXIvr04eEmVMvRuteja9EYIw== 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=IM0nM4nxg+MmMeBuNeOLT0ZhCTNeaP6GBTrOvA4MVz4=; b=bdxtHiiCIRG0d2eDVHWNi7mY+C+KUy4Z9ykf4vhqZqJ7xjheBBWM40nQ4DycerOzcVp/X8FXMmY9ORzKOImvsqW9FZIMykUdgS5QTbyez/S2mkqH+Ejz/hXJmif8hJleEdIVbZURYmYpugBCoHJNOpHwZCvM0SFe9iJREOessME= Received: from DB7PR05CA0007.eurprd05.prod.outlook.com (2603:10a6:10:36::20) by DBAPR08MB5814.eurprd08.prod.outlook.com (2603:10a6:10:1b1::6) 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:23 +0000 Received: from DB5PEPF00014B90.eurprd02.prod.outlook.com (2603:10a6:10:36:cafe::1c) by DB7PR05CA0007.outlook.office365.com (2603:10a6:10:36::20) 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:23 +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 DB5PEPF00014B90.mail.protection.outlook.com (10.167.8.228) 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:23 +0000 Received: ("Tessian outbound 5d213238733f:v228"); Thu, 09 Nov 2023 14:13:23 +0000 X-CheckRecipientChecked: true X-CR-MTA-CID: c3b034109efbe9ca X-CR-MTA-TID: 64aa7808 Received: from 0cf3e2a9cbc5.1 by 64aa7808-outbound-1.mta.getcheckrecipient.com id C8DD486A-86AB-487A-847C-3B77BEE34FBB.1; Thu, 09 Nov 2023 14:13:17 +0000 Received: from EUR04-VI1-obe.outbound.protection.outlook.com by 64aa7808-outbound-1.mta.getcheckrecipient.com with ESMTPS id 0cf3e2a9cbc5.1 (version=TLSv1.2 cipher=ECDHE-RSA-AES256-GCM-SHA384); Thu, 09 Nov 2023 14:13:17 +0000 ARC-Seal: i=1; a=rsa-sha256; s=arcselector9901; d=microsoft.com; cv=none; b=BPpxWfqc+K3lup52hH/kqGK8rhW3fQ7oCILHJx5qZU5e5NYHKXJ3i+i0229rT5oVNhW5wktwJSPDoy195oNnd6PeW6l9mzCC4/FJk3zSo0Z1fZf9dNQikq1PSGHbj5tvimiEfNrKMmUpKu4NkUMOLZ0+6SGcqXUFVfI65+TuU7n07pZI94rNX0MmtxGHS0e2iMb4XkZhWLlrM5LPNnNdsoGWS6UMTD5d5oy78Kz293CtRL6tBMj01QPUndY4NYKPJWuc+N69CqAlOt2uUOucJsMApe4WG9ZmqDZseP2NQsTsTIE3kZGUmuvysHEX85dlE97ckS4hNHrMC4uRv3MTkw== 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=IM0nM4nxg+MmMeBuNeOLT0ZhCTNeaP6GBTrOvA4MVz4=; b=iY5ZONirt3z7SdyTpZAkn8XgOQ8hLz/Q7dzZ7/Ov+e665rbDG7LUAq6D2Gd8LeELFUbjMLsMqMXjVwd9NUx+CzEdTUHAbpG8FDgXwosMpX00Fm7prF2Sa4MLbGQmbtxOLnqmY5EZigybz+jgbrO3w93ioGN2mNMNvlQtB5jcmHMWAPPzLa11U+ycojKeDbAzWK1fALN69F74rhYJxj2UD7QQ5jWZsjMKmnN3uwJoctoOALWB6xe1auPJ/Fmg5ZfAMbHWhTEtjW8iB3dkgNa9fSt8weaUuFegngjUCrbhpjrwR5pLriipIN/ox2uYpElfCOtBkUK3oNnwe5nzI1hNbQ== 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=IM0nM4nxg+MmMeBuNeOLT0ZhCTNeaP6GBTrOvA4MVz4=; b=bdxtHiiCIRG0d2eDVHWNi7mY+C+KUy4Z9ykf4vhqZqJ7xjheBBWM40nQ4DycerOzcVp/X8FXMmY9ORzKOImvsqW9FZIMykUdgS5QTbyez/S2mkqH+Ejz/hXJmif8hJleEdIVbZURYmYpugBCoHJNOpHwZCvM0SFe9iJREOessME= Received: from DU6P191CA0021.EURP191.PROD.OUTLOOK.COM (2603:10a6:10:540::26) by VE1PR08MB5645.eurprd08.prod.outlook.com (2603:10a6:800:1a6::23) 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:11 +0000 Received: from DB5PEPF00014B9E.eurprd02.prod.outlook.com (2603:10a6:10:540:cafe::ad) by DU6P191CA0021.outlook.office365.com (2603:10a6:10:540::26) 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:11 +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 DB5PEPF00014B9E.mail.protection.outlook.com (10.167.8.171) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_128_GCM_SHA256) id 15.20.6977.18 via Frontend Transport; Thu, 9 Nov 2023 14:13:11 +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:09 +0000 From: Victor Do Nascimento To: CC: , , , Victor Do Nascimento Subject: [PATCH 2/5] aarch64: rcpc3: Add relevant iterators to handle Neon intrinsics Date: Thu, 9 Nov 2023 14:12:45 +0000 Message-ID: <20231109141300.3542453-3-victor.donascimento@arm.com> X-Mailer: git-send-email 2.41.0 In-Reply-To: <20231109141300.3542453-1-victor.donascimento@arm.com> References: <20231109141300.3542453-1-victor.donascimento@arm.com> MIME-Version: 1.0 X-EOPAttributedMessage: 1 X-MS-TrafficTypeDiagnostic: DB5PEPF00014B9E:EE_|VE1PR08MB5645:EE_|DB5PEPF00014B90:EE_|DBAPR08MB5814:EE_ X-MS-Office365-Filtering-Correlation-Id: ec8b7dcb-a4ac-4dc4-ee6a-08dbe12e08f2 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: NXrXYvMkEqIB5GD308ZkbzZhldOi57pmJwTFHqY1AXAbZox9K/Af1p78k9cit6d6iMmONOinLoges42YhPC42k+7jTgUPzHuY7CXA9kAQa5KiD47RKbQtjGRCfbTjH8BF762KtnM5eZ7sOp16txaeXSZ42UfaVHlOoWloc0UQiOLSlLh2f0sM/R9AaRYBEd28D3mrDgk2xCZ7Rsj7i2srd4ffUEx+wgY6jIrCLnI96DTmlaSOilZpL4IHZXvb1jy+kH5YnZUKBsmzhzbUCkYAPm8riAH9tFNha2KhtjmAwjbkF7cbrg6zO3ii9trBttzXr+GjfZ4INmyXzgGdTBAfgrALX00s9C6y0VwHp7MwH3+s9piY0rxWR8KTCA40JtLhfDA0/cIs9iDM9iedm3fyke8BqusbGVQuWVeV4LmZuTv16tX8gjaHQwZrBpfYq7T4bSUdUnw8ujOn1Ay0QzG47YAzYEPz6Yv/mZXEOGvu0FFN7hBUs4suSLxL9MMGlQauGS7xdz9inmvsaD8G9ipiAdG8PElQNnmpXJw+OAWoy9Vsd9FiTg+dDodprd5LZv2CILYOLUebugQReyH6FB/jgIq2Rlwurk698SfPyaUVfyJNlHA+R+D6TBU5xSQL5mmDPkZEQOYJcqkmUMNQUlmZ8U9u0+onEvevL4J3Yu6xiEK7LmIvYSWWKJMiIC9s32H/sGmd1dhODJ0DKa1Yg385cxAChhZci3D/CfxlAslHJkiGA1QcD9B/UFEgKDAbZXp 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)(376002)(39850400004)(346002)(136003)(396003)(230922051799003)(64100799003)(82310400011)(186009)(451199024)(1800799009)(36840700001)(46966006)(2616005)(426003)(1076003)(26005)(82740400003)(478600001)(41300700001)(8676002)(5660300002)(54906003)(36756003)(4326008)(86362001)(2906002)(6916009)(316002)(70586007)(70206006)(336012)(8936002)(6666004)(7696005)(36860700001)(356005)(40480700001)(47076005)(83380400001)(81166007)(36900700001); DIR:OUT; SFP:1101; X-MS-Exchange-Transport-CrossTenantHeadersStamped: VE1PR08MB5645 X-MS-Exchange-Transport-CrossTenantHeadersStripped: DB5PEPF00014B90.eurprd02.prod.outlook.com X-MS-PublicTrafficType: Email X-MS-Office365-Filtering-Correlation-Id-Prvs: 612a717a-a4c0-440a-6a9a-08dbe12e01a3 X-Microsoft-Antispam: BCL:0; X-Microsoft-Antispam-Message-Info: 35BawR3P9DDrQERfG0tSRHc5xyoVDPbw5WFhgY5tYHDMKABqOCEsB1pvHLVupbWgwbj8I3QFDoZwlZnOcKUVWheSj/cs/uq/qUZzDUI8p7hEX5Rr5efGyZ5BvVclPYX5g95gs9tdZ0UIQGmeTN9GEXqwViEGp5lwbOa63Ei7XWYT9E/hWnt4JQnVdWnL+5jb+mjtR6icptA7psLklFhgEBgfle/gyGMP+E3elJlkFk9c2emmX3I/kSCVTvxjNTHkM5SHzrU7CAoowx/vNR/1Uag63De2GHGTfao52fdWWPNh4WYTVN7k2OslmbUchFT+KCbP1XMSeg67ELqZszsbP+0vXZuVNd/GpaRocNuUnN1SJL41m7NoC+NfSRMxZiCtdtfOKx6VtC4lM1aXaCQoAzAC6F4/JsBdpQhBcOot63zV6RZHoVlTXGfZF0MNOUut029uT6onNOLrJPBs09xbrfN0zy8ROnTp3yBA+vdw68e7GHd+sboxu1hgy1fu7J05f7mjlmNhcy5ReU6LOH2m+OC15qdwhe5Wt6WaFxDJjlLmruCXGonqJKECAsUNHcMgnEl7DZ7ShV7/5s5akKO2ntfZFxST5g9RSq98OPvSu2cpNtG9CeXtIg2gpUmrAdsDED9pHD0dBG1LHTd0d3hdgxsIIlu+cfGeU0adAk9fMKQzxFa/RRFJvN9DylLHK9JqixcZxBHDbcmw9qhA6LRlPb5Q79DBaV5Zvwq/Dh/rX7M7NhD69C+IbWGubSAJyLFQ 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)(346002)(376002)(136003)(396003)(39850400004)(230922051799003)(82310400011)(64100799003)(186009)(451199024)(1800799009)(36840700001)(46966006)(40470700004)(36860700001)(7696005)(6666004)(81166007)(83380400001)(40480700001)(47076005)(26005)(82740400003)(41300700001)(40460700003)(8936002)(6916009)(2906002)(5660300002)(8676002)(36756003)(86362001)(316002)(70206006)(54906003)(70586007)(1076003)(4326008)(426003)(2616005)(478600001)(336012); DIR:OUT; SFP:1101; X-OriginatorOrg: arm.com X-MS-Exchange-CrossTenant-OriginalArrivalTime: 09 Nov 2023 14:13:23.7940 (UTC) X-MS-Exchange-CrossTenant-Network-Message-Id: ec8b7dcb-a4ac-4dc4-ee6a-08dbe12e08f2 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: DB5PEPF00014B90.eurprd02.prod.outlook.com X-MS-Exchange-CrossTenant-AuthAs: Anonymous X-MS-Exchange-CrossTenant-FromEntityHeader: HybridOnPrem X-MS-Exchange-Transport-CrossTenantHeadersStamped: DBAPR08MB5814 X-Spam-Status: No, score=-12.5 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 X-BeenThere: gcc-patches@gcc.gnu.org X-Mailman-Version: 2.1.30 Precedence: list List-Id: Gcc-patches mailing list List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , Errors-To: gcc-patches-bounces+incoming=patchwork.ozlabs.org@gcc.gnu.org The LDAP1 and STL1 Neon ACLE intrinsics, operating on 64-bit data values, operate on single-lane (Vt.1D) or twin-lane (Vt.2D) SIMD register configurations, either in the DI or DF modes. This leads to the need for a mode iterator accounting for the V1DI, V1DF, V2DI and V2DF modes. This patch therefore introduces the new V12DIF mode iterator with which to generate functions operating on signed 64-bit integer and float values and V12DIUP for generating the unsigned and polynomial-type counterparts. Along with this, we modify the associated mode attributes accordingly in order to allow for the implementation of the relevant backend patterns for the intrinsics. gcc/ChangeLog: * config/aarch64/iterators.md (V12DIF): New. (V12DUP): Likewise. (VEL): Add support for all V12DIF-associated modes. (Vetype): Add support for V1DI and V1DF. (Vel): Likewise. --- gcc/config/aarch64/iterators.md | 25 +++++++++++++++++-------- 1 file changed, 17 insertions(+), 8 deletions(-) diff --git a/gcc/config/aarch64/iterators.md b/gcc/config/aarch64/iterators.md index f9e2210095e..471438e27be 100644 --- a/gcc/config/aarch64/iterators.md +++ b/gcc/config/aarch64/iterators.md @@ -314,6 +314,12 @@ ;; All byte modes. (define_mode_iterator VB [V8QI V16QI]) +;; 1 and 2 lane DI and DF modes. +(define_mode_iterator V12DIF [V1DI V1DF V2DI V2DF]) + +;; 1 and 2 lane DI mode for unsigned and poly types. +(define_mode_iterator V12DIUP [V1DI V2DI]) + ;; 2 and 4 lane SI modes. (define_mode_iterator VS [V2SI V4SI]) @@ -1195,10 +1201,10 @@ (define_mode_attr Vetype [(V8QI "b") (V16QI "b") (V4HI "h") (V8HI "h") (V2SI "s") (V4SI "s") - (V2DI "d") + (V2DI "d") (V1DI "d") (V4HF "h") (V8HF "h") (V2SF "s") (V4SF "s") - (V2DF "d") + (V2DF "d") (V1DF "d") (V2x8QI "b") (V2x4HI "h") (V2x2SI "s") (V2x1DI "d") (V2x4HF "h") (V2x2SF "s") @@ -1358,10 +1364,12 @@ (define_mode_attr VEL [(V8QI "QI") (V16QI "QI") (V4HI "HI") (V8HI "HI") (V2SI "SI") (V4SI "SI") - (DI "DI") (V2DI "DI") + (DI "DI") (V1DI "DI") + (V2DI "DI") (V4HF "HF") (V8HF "HF") (V2SF "SF") (V4SF "SF") - (DF "DF") (V2DF "DF") + (DF "DF") (V1DF "DF") + (V2DF "DF") (SI "SI") (HI "HI") (QI "QI") (V4BF "BF") (V8BF "BF") @@ -1378,12 +1386,13 @@ (define_mode_attr Vel [(V8QI "qi") (V16QI "qi") (V4HI "hi") (V8HI "hi") (V2SI "si") (V4SI "si") - (DI "di") (V2DI "di") + (DI "di") (V1DI "si") + (V2DI "di") (V4HF "hf") (V8HF "hf") (V2SF "sf") (V4SF "sf") - (V2DF "df") (DF "df") - (SI "si") (HI "hi") - (QI "qi") + (V1DF "df") (V2DF "df") + (DF "df") (SI "si") + (HI "hi") (QI "qi") (V4BF "bf") (V8BF "bf") (VNx16QI "qi") (VNx8QI "qi") (VNx4QI "qi") (VNx2QI "qi") (VNx8HI "hi") (VNx4HI "hi") (VNx2HI "hi") From patchwork Thu Nov 9 14:12:46 2023 Content-Type: text/plain; charset="utf-8" MIME-Version: 1.0 Content-Transfer-Encoding: 7bit X-Patchwork-Submitter: Victor Do Nascimento X-Patchwork-Id: 1862103 Return-Path: X-Original-To: incoming@patchwork.ozlabs.org Delivered-To: patchwork-incoming@legolas.ozlabs.org Authentication-Results: legolas.ozlabs.org; dkim=pass (1024-bit key; unprotected) header.d=armh.onmicrosoft.com header.i=@armh.onmicrosoft.com header.a=rsa-sha256 header.s=selector2-armh-onmicrosoft-com header.b=9JKOhjnj; dkim=pass (1024-bit key) header.d=armh.onmicrosoft.com header.i=@armh.onmicrosoft.com header.a=rsa-sha256 header.s=selector2-armh-onmicrosoft-com header.b=9JKOhjnj; dkim-atps=neutral Authentication-Results: legolas.ozlabs.org; spf=pass (sender SPF authorized) smtp.mailfrom=gcc.gnu.org (client-ip=8.43.85.97; helo=server2.sourceware.org; envelope-from=gcc-patches-bounces+incoming=patchwork.ozlabs.org@gcc.gnu.org; receiver=patchwork.ozlabs.org) Received: from server2.sourceware.org (server2.sourceware.org [8.43.85.97]) (using TLSv1.3 with cipher TLS_AES_256_GCM_SHA384 (256/256 bits) key-exchange X25519 server-signature ECDSA (secp384r1) server-digest SHA384) (No client certificate requested) by legolas.ozlabs.org (Postfix) with ESMTPS id 4SR3q82TgXz1yRF for ; Fri, 10 Nov 2023 01:14:12 +1100 (AEDT) Received: from server2.sourceware.org (localhost [IPv6:::1]) by sourceware.org (Postfix) with ESMTP id 604443858408 for ; Thu, 9 Nov 2023 14:14:10 +0000 (GMT) X-Original-To: gcc-patches@gcc.gnu.org Delivered-To: gcc-patches@gcc.gnu.org Received: from EUR03-DBA-obe.outbound.protection.outlook.com (mail-dbaeur03on2075.outbound.protection.outlook.com [40.107.104.75]) by sourceware.org (Postfix) with ESMTPS id 7CD7B3858D35 for ; Thu, 9 Nov 2023 14:13:24 +0000 (GMT) DMARC-Filter: OpenDMARC Filter v1.4.2 sourceware.org 7CD7B3858D35 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 7CD7B3858D35 Authentication-Results: server2.sourceware.org; arc=pass smtp.remote-ip=40.107.104.75 ARC-Seal: i=3; a=rsa-sha256; d=sourceware.org; s=key; t=1699539206; cv=pass; b=iZ2pYGe1tRQOuGpKoExEoHuxs92hKqsjuXpFNXVGXP8gKGoqR3+xiK/H+s+k66WqF5hjHgIyzJVNlioA3m/ZHS7TESCZ0/CHLPoOx6NwP/i+rNlPmkD2M6BCSy0wGYan/mMX8NZoE0HkO/+ei+xufPMl89kNvB2RJNo935Z2+D4= ARC-Message-Signature: i=3; a=rsa-sha256; d=sourceware.org; s=key; t=1699539206; c=relaxed/simple; bh=ANuxQIN1DJvrxvO7fqMef4VfNmDfaI/iS+g6u6FvnJ4=; h=DKIM-Signature:DKIM-Signature:From:To:Subject:Date:Message-ID: MIME-Version; b=p/20I+jpohPVmW3nsmLOT9QCJ1lgb+l0ylERAh3phwdfdZnbOxezSpgCfjvPI2GYM4B4yhhfW9F4VtCnGEXysuKghjTDI9YPonUk3slo9HGLi21bHXk3XXn7H+GGkQeomCKcRfj+RfJxxLOsTWQ0LRGhbqIBs8fs5E+uTatyQA0= ARC-Authentication-Results: i=3; server2.sourceware.org ARC-Seal: i=2; a=rsa-sha256; s=arcselector9901; d=microsoft.com; cv=pass; b=dsCqL8ExHide+QhEweuwKkGhqrH0q6LXsZ0UB3Jj2z1JtO5OM+TEfkvfkPP3qdj5C/5bTwtEibxEyhQqGpsIt9kQ9Q4elLI6zOU/Glr2rvSFkOGI90agvILpmg+85IvCADl97CBvjsGSf3t2XlfjpTPa/jlp3j0D649Js2tZ1HV9q80egZ2esqrOAFwJSFvu+ZwP5AFb7u2PDcoBwwJ129n+lJSH7HdkLuc8uU6CsTbOOv9QEgbQ5++D4/jOJGeuVnsteApeUz3K2ElNCLD9HsyGW6PTGHh5oKSFpo+44Dh1Udxli5yu4Y/h3kWYGVUL5F6p2oi8d5VxV1poXADSiQ== 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=OTffXKUi2L8ZiE0tmieT/yMeMiuM5+yT/3fjH5iksRM=; b=kh233vp/MmfRcmRzHz6lxyr7/i1gWkzz5ffaEEvjgplcrBr1LCzJRIY5XJdTKmgXrp+puP6Xd6WJ+s4k13+Vkn/xxgjKkNpXeVETtQYIfxxGs+Hd+mGj2ImqR2loINMnkUu+UqY27tfyI742BndCrrlK4hizClphFm9eGoZcHmpCmk79yf6YR+AcALB5tdxMFe2JMji6grtfZ++9vmnNSboGGxV0IxQfER/jRH3/XaF2ZGE4xCBWDbboyISfiWw9ZPSLIJxRQqTCEkXMoqof4DgMVd/6GPo7v6hhI2i+tWx+Zf+ENgO5OOCN5GvtbXq0ZSi0bXmzMntLuETZICsTwA== 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=OTffXKUi2L8ZiE0tmieT/yMeMiuM5+yT/3fjH5iksRM=; b=9JKOhjnjrxkj2ES/a4ujFiEX2ITWG6+Qbg8Cg/tcVb5Su1UUBjdWHE53dq2ziBwT+ZYE8VCPP4MKtvv9mOv7VIn+tX2Zfq1EWPNhrLejDycqQVcauNS1dS0+uQx1RkboPXPEaEUJE9/Y8cdsOwI8kK78N5SM23J55MoTSK1rl0M= Received: from AS9PR0301CA0045.eurprd03.prod.outlook.com (2603:10a6:20b:469::13) by DU0PR08MB8397.eurprd08.prod.outlook.com (2603:10a6:10:407::17) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.6977.19; Thu, 9 Nov 2023 14:13:21 +0000 Received: from AM2PEPF0001C70B.eurprd05.prod.outlook.com (2603:10a6:20b:469:cafe::c6) by AS9PR0301CA0045.outlook.office365.com (2603:10a6:20b:469::13) 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:21 +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 AM2PEPF0001C70B.mail.protection.outlook.com (10.167.16.199) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.6977.17 via Frontend Transport; Thu, 9 Nov 2023 14:13:21 +0000 Received: ("Tessian outbound 7c4ecdadb9e7:v228"); Thu, 09 Nov 2023 14:13:21 +0000 X-CheckRecipientChecked: true X-CR-MTA-CID: ee3b24461d92b9ef X-CR-MTA-TID: 64aa7808 Received: from c6c9f193b09f.1 by 64aa7808-outbound-1.mta.getcheckrecipient.com id 61EDFB5E-A9C0-477F-9733-9F4DEF023F3B.1; Thu, 09 Nov 2023 14:13:14 +0000 Received: from EUR05-AM6-obe.outbound.protection.outlook.com by 64aa7808-outbound-1.mta.getcheckrecipient.com with ESMTPS id c6c9f193b09f.1 (version=TLSv1.2 cipher=ECDHE-RSA-AES256-GCM-SHA384); Thu, 09 Nov 2023 14:13:14 +0000 ARC-Seal: i=1; a=rsa-sha256; s=arcselector9901; d=microsoft.com; cv=none; b=nIZkOlcZ2YGawMdjZYvr6LPwmAzLrKor2aNpPN9r5Upc7TWKrFSDQzO8+tL9XthVCPQW83bZ1KWIGJz2BPPc6edhfA/pqFVZGtjXflJZLHwMS03+R+ta/LWAI08zwMoyJ/BbkMmza5Oyb4G2Fn47UOn04Aaq/rP7bloLkD24r75/aMIMs8oTrncOebopCMpR3wEfcS0c3m6dejrRNnM9N7gXFd2C9difuOQc1kBrTcdQFZTB9F9yGXuiEiqH8T5m4deTwbm7YMAU0vzur+Cwy+62JNMb1Bnyc+SCSLVFpwXwWKVduf7QRe1Pj76E4IKqU+ns1sWdmwsob93Z9akuVQ== 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=OTffXKUi2L8ZiE0tmieT/yMeMiuM5+yT/3fjH5iksRM=; b=gU4lVSCtqfq8+0upPVq++63iSh3/eL95UhE8t3UTbww+1xCYnZJXAod/Q/nlGndagEIBs5ac2kv8kes4KQtZZxW2wWJEp2/7fLNa7eZqpWNXevUsdTgzf05myaFGNLO7mWJcIRK54qQmaKVh7O0JvOqMRCAZkng3FhvgwV/spxpm5eZ13v1kwu1wT4sBhUFZ+ovuU/HM7FgTd3LoO/bpHDQypcd36xl/u6m4EXMyAyStUiW8V37+oqpNPBpWmtwbZyq5x19Xx9JcyNojhjuePNMtI/hHN9NTyyrxLnLlg5namyg5CU+FnipfFIPAveDIMAJshk+JAHjEickM+qH5DA== 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=OTffXKUi2L8ZiE0tmieT/yMeMiuM5+yT/3fjH5iksRM=; b=9JKOhjnjrxkj2ES/a4ujFiEX2ITWG6+Qbg8Cg/tcVb5Su1UUBjdWHE53dq2ziBwT+ZYE8VCPP4MKtvv9mOv7VIn+tX2Zfq1EWPNhrLejDycqQVcauNS1dS0+uQx1RkboPXPEaEUJE9/Y8cdsOwI8kK78N5SM23J55MoTSK1rl0M= Received: from DU2PR04CA0190.eurprd04.prod.outlook.com (2603:10a6:10:28d::15) by DB9PR08MB9468.eurprd08.prod.outlook.com (2603:10a6:10:45a::9) 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:10 +0000 Received: from DU6PEPF0000B61C.eurprd02.prod.outlook.com (2603:10a6:10:28d:cafe::75) by DU2PR04CA0190.outlook.office365.com (2603:10a6:10:28d::15) 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 DU6PEPF0000B61C.mail.protection.outlook.com (10.167.8.135) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_128_GCM_SHA256) id 15.20.6977.18 via Frontend Transport; Thu, 9 Nov 2023 14:13:10 +0000 Received: from AZ-NEU-EX02.Emea.Arm.com (10.251.26.5) by AZ-NEU-EX03.Arm.com (10.251.24.31) 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:10 +0000 Received: from AZ-NEU-EX04.Arm.com (10.251.24.32) by AZ-NEU-EX02.Emea.Arm.com (10.251.26.5) 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:09 +0000 From: Victor Do Nascimento To: CC: , , , Victor Do Nascimento Subject: [PATCH 3/5] aarch64: rcpc3: Add Neon ACLE intrinsics Date: Thu, 9 Nov 2023 14:12:46 +0000 Message-ID: <20231109141300.3542453-4-victor.donascimento@arm.com> X-Mailer: git-send-email 2.41.0 In-Reply-To: <20231109141300.3542453-1-victor.donascimento@arm.com> References: <20231109141300.3542453-1-victor.donascimento@arm.com> MIME-Version: 1.0 X-EOPAttributedMessage: 1 X-MS-TrafficTypeDiagnostic: DU6PEPF0000B61C:EE_|DB9PR08MB9468:EE_|AM2PEPF0001C70B:EE_|DU0PR08MB8397:EE_ X-MS-Office365-Filtering-Correlation-Id: 9226c2e4-74a9-41da-756b-08dbe12e0781 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: xT0zWn00ZFwDQv+GrgOrAx1IO++ngZycJ0YMBTjgFU99xLXP/A8uW5mXvpCOOCDbh7jdF0bKSiMfUZquRSoenbedndmcsm6FeWen6/WR68q6dD1wN6hOKGxu3latMPFHNlwxFlQT7/9gSTlSkkSlRxVvoySyaB+JJtUERmXIEDtGlGIrZl/T7GuK30GVSJgIys1W7MBkTUtb7B+iblttPDE65HsQvYt9wAduoupx4KMH3LY4lQQ0DAkcMzMNHgeKV4GX74I+PVhMh9SAKT9nok2RmVcNhrK2dkFRmkPmkDLRTpHGrGwbq74yHdtzfpKsVOnXYhoi1gQmwuzNnuw1qHwCmREO5FbpV0c1sS4GWyjQ2lvpx/P0tMTUpLP+EgU9O8FXJZRrJ64fUk94YeqxEvbRoD7O30B3rb/xtcja1rEMnPc0oGUraZotcTWvoTCQ9//vMNGMARL5bv7M8hFTRXg6yZsWaYyXysnEwSyz1XZE1LMerCsWn+FouEk69vrUGFJBZ0t0NJB70gv9YGZ174hI/UgxlaczezPOuxSPzuAREpsE2EHJcwSwR5CCwV222g5VeS9eYrSu2g9V+Ji1CGvfxWjksbAhX7jK2wIOX3uZJLAF7EWFdmmsZ806nMekyFxivpbFFmf0N/n+fhajz9MZN/aF6KtqKHUqWkf3FtZcrRloHUWA1KtfdkbZojcYzdaZthrMFcOEFOQzXTFG4tO82EPtIdMA8O50MAfvAZZHcn8W9F5M7lE8yL7d2wwGF9k86AZzjgcFQWnpYi8Xag== 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)(376002)(39860400002)(346002)(136003)(396003)(230922051799003)(186009)(451199024)(1800799009)(64100799003)(82310400011)(36840700001)(40470700004)(46966006)(356005)(36860700001)(7696005)(6666004)(81166007)(47076005)(40480700001)(336012)(426003)(1076003)(2616005)(41300700001)(86362001)(8936002)(5660300002)(4326008)(36756003)(8676002)(40460700003)(6916009)(70586007)(316002)(70206006)(54906003)(82740400003)(26005)(2906002)(478600001)(36900700001); DIR:OUT; SFP:1101; X-MS-Exchange-Transport-CrossTenantHeadersStamped: DB9PR08MB9468 X-MS-Exchange-Transport-CrossTenantHeadersStripped: AM2PEPF0001C70B.eurprd05.prod.outlook.com X-MS-PublicTrafficType: Email X-MS-Office365-Filtering-Correlation-Id-Prvs: 59b02434-c489-4a86-9792-08dbe12e0100 X-Microsoft-Antispam: BCL:0; X-Microsoft-Antispam-Message-Info: avnC1k0tQAVcPv8736nZV8UYTRZ2o67jeD1aYyn7WIq7E0ouCSi6BxdEHTlfl0h+KHkCjdMvccbwc41XI1XElXxkgLtIX/44/kY4pPLKomj52l4hxYDtoZAPh48zntrxhFPjmPstGrKxma4TWE8TH347C4HQpPj7vK3duSKfaRIstYh5d/iGlNhijZ6IqyE+1+3rZ46whAz+6ZGIASuZ3FAwVlLzqgIetp6Ix2yUJ3m8+247ItCehW4IFE6CQzhi9164ek2Yg5gXByJ2fTj38N713z1JWFH5VggunMaYlS7Q9YQiPwjYRceJVagwwcB4VtlJ7Dlqd/Ru4SaojEkGteVit1ZmHvswGs7uNj239qbg/MIgGMSLLGQvpetCAi4W4KmT70kP/LswvfmYrIkzLJ9nSrgrJhPAwbjknzkS8GK25uz7ISjhfSmYKkYyzxWaLOwNuV9FYq+XkLLh/vqEw42+6eMbi1Xc8IZQ4TV+qyEE70sUv5iZQL3x1LLPnWHwv8bTsuobkfXbaMNiwkuk8n8i6sV8T2O33wGxs7I+4OOjyGpdH1ZzmxZnrBl5NFh8CPP3qn0iHRU4Ar79NVXj+hSByJ4flAHwgQf6I4B3Zi7n/o6KFRYaQZUgMjsB2MdeYp2bcUZ7C/ohZRHrAHpxAm76Dc0Y++zyqkLw6gzEnGzfGyTFOcfbeudUEslA9/wMSW3/mlVvP4BZ8T+PCFYTHsFQ70E2eDZLk54QSWT+VY29oc7XtFY1cD7c3GQuCJZf 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)(136003)(39860400002)(376002)(396003)(346002)(230922051799003)(451199024)(82310400011)(64100799003)(1800799009)(186009)(36840700001)(46966006)(40470700004)(40460700003)(40480700001)(426003)(26005)(7696005)(6666004)(2616005)(47076005)(36860700001)(41300700001)(5660300002)(4326008)(8676002)(8936002)(2906002)(478600001)(336012)(6916009)(70586007)(54906003)(70206006)(1076003)(82740400003)(36756003)(86362001)(81166007)(316002); DIR:OUT; SFP:1101; X-OriginatorOrg: arm.com X-MS-Exchange-CrossTenant-OriginalArrivalTime: 09 Nov 2023 14:13:21.3258 (UTC) X-MS-Exchange-CrossTenant-Network-Message-Id: 9226c2e4-74a9-41da-756b-08dbe12e0781 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: AM2PEPF0001C70B.eurprd05.prod.outlook.com X-MS-Exchange-CrossTenant-AuthAs: Anonymous X-MS-Exchange-CrossTenant-FromEntityHeader: HybridOnPrem X-MS-Exchange-Transport-CrossTenantHeadersStamped: DU0PR08MB8397 X-Spam-Status: No, score=-13.0 required=5.0 tests=BAYES_00, DKIM_SIGNED, DKIM_VALID, GIT_PATCH_0, KAM_DMARC_NONE, RCVD_IN_DNSWL_NONE, RCVD_IN_MSPIKE_H2, SPF_HELO_NONE, 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 X-BeenThere: gcc-patches@gcc.gnu.org X-Mailman-Version: 2.1.30 Precedence: list List-Id: Gcc-patches mailing list List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , Errors-To: gcc-patches-bounces+incoming=patchwork.ozlabs.org@gcc.gnu.org Register the target specific builtins in `aarch64-simd-builtins.def' and implement their associated backend patterns in `aarch64-simd.md'. gcc/ChangeLog: * config/aarch64/aarch64-simd-builtins.def (vec_ldap1_lane): New. (vec_stl1_lane): Likewise. * config/aarch64/aarch64-simd.md (aarch64_vec_stl1_lanes_lane): New. (aarch64_vec_stl1_lane): Likewise. (aarch64_vec_ldap1_lanes_lane): Likewise. (aarch64_vec_ldap1_lane): Likewise. --- gcc/config/aarch64/aarch64-simd-builtins.def | 7 +++ gcc/config/aarch64/aarch64-simd.md | 65 ++++++++++++++++++++ gcc/config/aarch64/aarch64.md | 2 + 3 files changed, 74 insertions(+) diff --git a/gcc/config/aarch64/aarch64-simd-builtins.def b/gcc/config/aarch64/aarch64-simd-builtins.def index e2b94ad8247..0ae6c4ad41a 100644 --- a/gcc/config/aarch64/aarch64-simd-builtins.def +++ b/gcc/config/aarch64/aarch64-simd-builtins.def @@ -43,6 +43,13 @@ help describe the attributes (for example, pure) for the intrinsic function. */ + BUILTIN_V12DIF (LOADSTRUCT_LANE, vec_ldap1_lane, 0, ALL) + BUILTIN_V12DIUP (LOADSTRUCT_LANE_U, vec_ldap1_lane, 0, ALL) + BUILTIN_V12DIUP (LOADSTRUCT_LANE_P, vec_ldap1_lane, 0, ALL) + BUILTIN_V12DIF (STORESTRUCT_LANE, vec_stl1_lane, 0, ALL) + BUILTIN_V12DIUP (STORESTRUCT_LANE_U, vec_stl1_lane, 0, ALL) + BUILTIN_V12DIUP (STORESTRUCT_LANE_P, vec_stl1_lane, 0, ALL) + BUILTIN_VDC (BINOP, combine, 0, AUTO_FP) BUILTIN_VD_I (BINOPU, combine, 0, NONE) BUILTIN_VDC_P (BINOPP, combine, 0, NONE) diff --git a/gcc/config/aarch64/aarch64-simd.md b/gcc/config/aarch64/aarch64-simd.md index 81ff5bad03d..79697336f61 100644 --- a/gcc/config/aarch64/aarch64-simd.md +++ b/gcc/config/aarch64/aarch64-simd.md @@ -7697,6 +7697,71 @@ DONE; }) +;; Patterns for rcpc3 vector lane loads and stores. + +(define_insn "aarch64_vec_stl1_lanes_lane" + [(set (match_operand:BLK 0 "aarch64_simd_struct_operand" "=Q") + (unspec:BLK [(match_operand:V12DIF 1 "register_operand" "w") + (match_operand:SI 2 "immediate_operand" "i")] + UNSPEC_STL1_LANE))] + "TARGET_RCPC3" + { + operands[2] = aarch64_endian_lane_rtx (mode, + INTVAL (operands[2])); + return "stl1\\t{%S1.}[%2], %0"; + } + [(set_attr "type" "neon_store2_one_lane")] +) + +(define_expand "aarch64_vec_stl1_lane" + [(match_operand:DI 0 "register_operand") + (match_operand:V12DIF 1 "register_operand") + (match_operand:SI 2 "immediate_operand")] + "TARGET_RCPC3" +{ + rtx mem = gen_rtx_MEM (BLKmode, operands[0]); + set_mem_size (mem, GET_MODE_SIZE (GET_MODE_INNER (mode))); + + aarch64_simd_lane_bounds (operands[2], 0, + GET_MODE_NUNITS (mode).to_constant (), NULL); + emit_insn (gen_aarch64_vec_stl1_lanes_lane (mem, + operands[1], operands[2])); + DONE; +}) + +(define_insn "aarch64_vec_ldap1_lanes_lane" + [(set (match_operand:V12DIF 0 "register_operand" "=w") + (unspec:V12DIF [ + (match_operand:BLK 1 "aarch64_simd_struct_operand" "Q") + (match_operand:V12DIF 2 "register_operand" "0") + (match_operand:SI 3 "immediate_operand" "i")] + UNSPEC_LDAP1_LANE))] + "TARGET_RCPC3" + { + operands[3] = aarch64_endian_lane_rtx (mode, + INTVAL (operands[3])); + return "ldap1\\t{%S0.}[%3], %1"; + } + [(set_attr "type" "neon_load2_one_lane")] +) + +(define_expand "aarch64_vec_ldap1_lane" + [(match_operand:V12DIF 0 "register_operand") + (match_operand:DI 1 "register_operand") + (match_operand:V12DIF 2 "register_operand") + (match_operand:SI 3 "immediate_operand")] + "TARGET_RCPC3" +{ + rtx mem = gen_rtx_MEM (BLKmode, operands[1]); + set_mem_size (mem, GET_MODE_SIZE (GET_MODE_INNER (mode))); + + aarch64_simd_lane_bounds (operands[3], 0, + GET_MODE_NUNITS (mode).to_constant (), NULL); + emit_insn (gen_aarch64_vec_ldap1_lanes_lane (operands[0], + mem, operands[2], operands[3])); + DONE; +}) + (define_insn_and_split "aarch64_rev_reglist" [(set (match_operand:VSTRUCT_QD 0 "register_operand" "=&w") (unspec:VSTRUCT_QD diff --git a/gcc/config/aarch64/aarch64.md b/gcc/config/aarch64/aarch64.md index 5bb8c772be8..fb6de3b1fbf 100644 --- a/gcc/config/aarch64/aarch64.md +++ b/gcc/config/aarch64/aarch64.md @@ -295,6 +295,8 @@ UNSPEC_LD1RO UNSPEC_SALT_ADDR UNSPECV_PATCHABLE_AREA + UNSPEC_LDAP1_LANE + UNSPEC_STL1_LANE ]) (define_c_enum "unspecv" [ From patchwork Thu Nov 9 14:12:47 2023 Content-Type: text/plain; charset="utf-8" MIME-Version: 1.0 Content-Transfer-Encoding: 7bit X-Patchwork-Submitter: Victor Do Nascimento X-Patchwork-Id: 1862104 Return-Path: X-Original-To: incoming@patchwork.ozlabs.org Delivered-To: patchwork-incoming@legolas.ozlabs.org Authentication-Results: legolas.ozlabs.org; dkim=pass (1024-bit key; unprotected) header.d=armh.onmicrosoft.com header.i=@armh.onmicrosoft.com header.a=rsa-sha256 header.s=selector2-armh-onmicrosoft-com header.b=g8G81Wp1; dkim=pass (1024-bit key) header.d=armh.onmicrosoft.com header.i=@armh.onmicrosoft.com header.a=rsa-sha256 header.s=selector2-armh-onmicrosoft-com header.b=g8G81Wp1; dkim-atps=neutral Authentication-Results: legolas.ozlabs.org; spf=pass (sender SPF authorized) smtp.mailfrom=gcc.gnu.org (client-ip=2620:52:3:1:0:246e:9693:128c; helo=server2.sourceware.org; envelope-from=gcc-patches-bounces+incoming=patchwork.ozlabs.org@gcc.gnu.org; receiver=patchwork.ozlabs.org) Received: from server2.sourceware.org (server2.sourceware.org [IPv6:2620:52:3:1:0:246e:9693:128c]) (using TLSv1.3 with cipher TLS_AES_256_GCM_SHA384 (256/256 bits) key-exchange X25519 server-signature ECDSA (secp384r1) server-digest SHA384) (No client certificate requested) by legolas.ozlabs.org (Postfix) with ESMTPS id 4SR3qF4F5yz1yRF for ; Fri, 10 Nov 2023 01:14:17 +1100 (AEDT) Received: from server2.sourceware.org (localhost [IPv6:::1]) by sourceware.org (Postfix) with ESMTP id B8C533831E15 for ; Thu, 9 Nov 2023 14:14:14 +0000 (GMT) X-Original-To: gcc-patches@gcc.gnu.org Delivered-To: gcc-patches@gcc.gnu.org Received: from EUR05-DB8-obe.outbound.protection.outlook.com (mail-db8eur05on2078.outbound.protection.outlook.com [40.107.20.78]) by sourceware.org (Postfix) with ESMTPS id 59B373856DC8 for ; Thu, 9 Nov 2023 14:13:26 +0000 (GMT) DMARC-Filter: OpenDMARC Filter v1.4.2 sourceware.org 59B373856DC8 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 59B373856DC8 Authentication-Results: server2.sourceware.org; arc=pass smtp.remote-ip=40.107.20.78 ARC-Seal: i=3; a=rsa-sha256; d=sourceware.org; s=key; t=1699539208; cv=pass; b=uvO9CkMiwcW1aL6q8RnuC3U6HyvlFIqB7X3Me+Isegq+TJW89r1hwlL/BdKKstBiV4EiiBkeAT191piSPQM3B0qunhQ4wLWyoKWBjsQk2LNY54L0cG/mX9S5ccc7fyXTqPX4euyaMdOT2Sfx+EXP/1Ncq2slx/vcNPfbX8rWbP0= ARC-Message-Signature: i=3; a=rsa-sha256; d=sourceware.org; s=key; t=1699539208; c=relaxed/simple; bh=XblLLLPdF4qWosgDTIP3HsQgJ2mBbgXaG5Z0WjRz/Ro=; h=DKIM-Signature:DKIM-Signature:From:To:Subject:Date:Message-ID: MIME-Version; b=CJIFRI9UlvTEQt6ST6WKkcoKh+/nwbo/ZGHvDGy9IxG90fJ/DqPO2HHxRzaB4EtsZ0YY48d8+TRLMSKZgeVHRi0tYOcY6owI/PnOROEC701EjrpwFQ/qJ4L5h/cOxH94JXrhpI7hdOQmC4GU6NdK7pyXdiG0+oK8rtoTJ+OFSvY= ARC-Authentication-Results: i=3; server2.sourceware.org ARC-Seal: i=2; a=rsa-sha256; s=arcselector9901; d=microsoft.com; cv=pass; b=OjeFcGHOQqCJ3dQQTCoSajm8tbNyB47EDOEXXJgUVKydX3M39Vwe6zayQRSMk37rdO3IVX2xTc5kOqhlTiw+nLIDrd4WpZRQg86QrFOBMLESNfVUXtLWPTgGhkv7Mof7qPxe6B2BQFThj6Yc40pwHsbqwu5aU375Hh/Vg82iRQPOx1RBd08FCYRdFnxoX3T7DxZzc9EQT6AoPsMAztQCBCi58x0UJpZ1EiHmChgYyOzku9Abc7P+aDfemhPSz8gdBdxeFAnJZeDPlxbBvlmIifcrJOinFG2TYqbv6uy+pnhS7AiWjZ4KVupk3jrUa1v/oRopQlkrLtKFp6r0uVde8w== 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=CKJAdwEeqGg/2UGWN9FCnellR6/6m2tM9qUFMfkf0+g=; b=EAxEYMtVsTAQl2qm4LZmdWdhceiS/ql71Dfi4b/kNnOqoq80EwEO+xGSle5Hr3hWSlhfSr5462h6sXlwVa+fE81pUS6lc9hGpRsqxDnZ9972me8qeCwPw7MsTxSPtqryziow4sqKr3+W+ycR1G9XABO2jwHh9LavJUb+dgWEA0tMJoDie/gyWiSYy4EZE7rVRf9WJic32S+PtfGbdYzPADAxvYOaX1/h8LqlOy9FMcTdxqda3YoKFtKStintec2y6vCPgBcJWENQOGhcRUxB57l8a3xdcPAf7+8EBWMOnn9IfwT2BEfk+b+5uPn4bYAxgYhRVUqg/InRy8pWK9VKuQ== 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=CKJAdwEeqGg/2UGWN9FCnellR6/6m2tM9qUFMfkf0+g=; b=g8G81Wp1PVFhxowG9mfVy/8cAMmObZ/f6GrYp0zGeSXjz5MUe8YA2b70XkoR5cZC4VyslEnGGwL3mFla8RzJquv3Z1iFOtWPW9aigkvezuHewoud6/K+zhlqflFMrBCvhGt6Nx1/YnRkxtW3LG8DZccOSWGZoezOm+Si64mdz6M= Received: from DU2PR04CA0272.eurprd04.prod.outlook.com (2603:10a6:10:28c::7) by DBBPR08MB6236.eurprd08.prod.outlook.com (2603:10a6:10:20c::10) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.6977.19; Thu, 9 Nov 2023 14:13:24 +0000 Received: from DU6PEPF0000B621.eurprd02.prod.outlook.com (2603:10a6:10:28c:cafe::cc) by DU2PR04CA0272.outlook.office365.com (2603:10a6:10:28c::7) 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:23 +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 DU6PEPF0000B621.mail.protection.outlook.com (10.167.8.138) 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:23 +0000 Received: ("Tessian outbound 7671e7ddc218:v228"); Thu, 09 Nov 2023 14:13:23 +0000 X-CheckRecipientChecked: true X-CR-MTA-CID: c0c6b1903c35da6e X-CR-MTA-TID: 64aa7808 Received: from d5bf533edbeb.1 by 64aa7808-outbound-1.mta.getcheckrecipient.com id 72962C8C-306D-48A7-8623-79346879C36C.1; Thu, 09 Nov 2023 14:13:16 +0000 Received: from EUR04-HE1-obe.outbound.protection.outlook.com by 64aa7808-outbound-1.mta.getcheckrecipient.com with ESMTPS id d5bf533edbeb.1 (version=TLSv1.2 cipher=ECDHE-RSA-AES256-GCM-SHA384); Thu, 09 Nov 2023 14:13:16 +0000 ARC-Seal: i=1; a=rsa-sha256; s=arcselector9901; d=microsoft.com; cv=none; b=m0vWdMDhm2KegEc5ajDCEe6rtG4mY+Q7SFnMvnN96JB3wD0dSNKtK4/vtiYQBqZnRMH0eS8eoL6E/lxYGaCy1ehHUtKfM/BDbmi5S5fosGsdKcgTc34MA6+HFKZnDOTnv0ka6JtT6iArZo0woV2RWchKTiyn037hndAWpbYYmZiA+kf2tsEvntiL4ehBoy7XcT1a7gF9bWHwjUjguCOY0ItrXZpkZQCFI7kNvnvxLhUmLYA/pLI0B/RqT0V0SUNJZgZUqaEsEzbMpF3ZOqcX7+vIuoOAHVFCzxf7RX8VTADDDQpYOYXCv3pF8FLnFvMcXhKXSGKsvjiDfQ66BnuCsg== 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=CKJAdwEeqGg/2UGWN9FCnellR6/6m2tM9qUFMfkf0+g=; b=goVZYgbHlpFvfFdlOH4jMnR2x3zzG2PL8Dc+gdCcJcJF2dhXZr6zXHEIy4uNyN9xcCM4Qrzi3/fq65FXNh+SLv7M0MiU4a53KCeQvh/mVBz+vLpQnxYMnzBM1a83q71IWlVNHJCbdIlHT3HQ8sJpbvOM/S+5e1Y3H7eXfREmd281fpyZxO7kRm349icfZtwiL7rxlhCWvZITfMRRJpUBNVMCM8hnE/gsvsvOr+5/LVRDOXfxYoHRJXqYj6XB1HBzhpJmY+tZugM+raijcr+IY1ehRBFNjG7aGHZrpAFnqiXchrB3UamVoq6tJdf8ftR5y+95ZYIjUp6ouSFZE/vMAA== 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=CKJAdwEeqGg/2UGWN9FCnellR6/6m2tM9qUFMfkf0+g=; b=g8G81Wp1PVFhxowG9mfVy/8cAMmObZ/f6GrYp0zGeSXjz5MUe8YA2b70XkoR5cZC4VyslEnGGwL3mFla8RzJquv3Z1iFOtWPW9aigkvezuHewoud6/K+zhlqflFMrBCvhGt6Nx1/YnRkxtW3LG8DZccOSWGZoezOm+Si64mdz6M= Received: from DU6P191CA0024.EURP191.PROD.OUTLOOK.COM (2603:10a6:10:540::14) by AS8PR08MB6152.eurprd08.prod.outlook.com (2603:10a6:20b:298::8) 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:14 +0000 Received: from DB5PEPF00014B9E.eurprd02.prod.outlook.com (2603:10a6:10:540:cafe::f7) by DU6P191CA0024.outlook.office365.com (2603:10a6:10:540::14) 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:14 +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 DB5PEPF00014B9E.mail.protection.outlook.com (10.167.8.171) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_128_GCM_SHA256) id 15.20.6977.18 via Frontend Transport; Thu, 9 Nov 2023 14:13:14 +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:10 +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:10 +0000 From: Victor Do Nascimento To: CC: , , , Victor Do Nascimento Subject: [PATCH 4/5] aarch64: rcpc3: add Neon ACLE wrapper functions to `arm_neon.h' Date: Thu, 9 Nov 2023 14:12:47 +0000 Message-ID: <20231109141300.3542453-5-victor.donascimento@arm.com> X-Mailer: git-send-email 2.41.0 In-Reply-To: <20231109141300.3542453-1-victor.donascimento@arm.com> References: <20231109141300.3542453-1-victor.donascimento@arm.com> MIME-Version: 1.0 X-EOPAttributedMessage: 1 X-MS-TrafficTypeDiagnostic: DB5PEPF00014B9E:EE_|AS8PR08MB6152:EE_|DU6PEPF0000B621:EE_|DBBPR08MB6236:EE_ X-MS-Office365-Filtering-Correlation-Id: b1ed8f7c-2762-4377-7812-08dbe12e090f 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: LTNUDowExECLMB/5+oUNBAs34nFN3d+hRRhw/wRPaOECNE6ZfLjdKlHFemicx+ZRKoct49HHXLLWOsrmWEyYYIO2XcPLYtGDFUSTKMwCyCuJUVBe4s3e1d7dm6rnzqKr+tNN8DkuCOyU1HQj3VjuUFTuoBo3cxiXPZnu/LEit4L/XAjG+dU4aMi+oGe7fv0AU37x5Ik5TQXi/gCqLG/HPOhDF8IekjWz2aAGXV10U0C2D8qbPfhzTMgEqt6nWLR78xviiOR/LvWkPuEJZgYqh7TqBcNvFWpwiMZkVfkjbiO5zMeg6ivlp3S+woL+iKnvg/v2o8lQtxW4gmDRRa6lNps4wqRJt68bB8CXnN4a8tjfF7hxSf+fyvutiGlCptPPPW/jMsizP+RjxgZo/6cRIQ6i5cMxs8oyTZYwr2We/ufBGWQWX9gHZSjsSTK/rm7H6syCKLUkUsj1Far4oixzASR5HA9vNY5sP1oMgLvqKxBr0guXzTLlQgKZaI2RYzmJt6m43DfGI/znpAbrcdv72o/65gjAo/vBLkUxZF+8XGb1I8LktZezTOBzQWhl5xRbbP+1qnCIeKR+kMa++srMKOR7cZvSytXspKSl/HJ3lFVORMblcwwkC0qVrzco0Y6/HKf+ToD8K2yYTso9PpDotPdlXcVzFFySHb2ZhZTkZK2YTvLC+BxDEOpiz8f7IsCOlBzKTBtxKfG6BPv1xEgaTD4NBPXgqN2gbKJBNgIrQwJ+CmXB+xlpGoI6YCzglyHXzC0/yG4hrBbveqqFmBTExOM4Wp8rI1lo9uTNK9M692I= 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)(396003)(39860400002)(376002)(346002)(136003)(230922051799003)(186009)(64100799003)(1800799009)(82310400011)(451199024)(40470700004)(46966006)(36840700001)(2906002)(41300700001)(40460700003)(5660300002)(86362001)(36860700001)(82740400003)(47076005)(356005)(81166007)(54906003)(70206006)(70586007)(6916009)(316002)(26005)(2616005)(478600001)(966005)(1076003)(36756003)(6666004)(7696005)(8936002)(40480700001)(8676002)(426003)(336012)(4326008)(81973001)(36900700001); DIR:OUT; SFP:1101; X-MS-Exchange-Transport-CrossTenantHeadersStamped: AS8PR08MB6152 X-MS-Exchange-Transport-CrossTenantHeadersStripped: DU6PEPF0000B621.eurprd02.prod.outlook.com X-MS-PublicTrafficType: Email X-MS-Office365-Filtering-Correlation-Id-Prvs: da8cb988-8276-43df-b9be-08dbe12e0338 X-Microsoft-Antispam: BCL:0; X-Microsoft-Antispam-Message-Info: 1imIJWeC91FOe9zsQa8UcTas7/Za6+iq+RXWHiQZ1s7cSozfxu6GaFrBmbp8f8uIwv3aK3KVgkwC3GbTD22A9UGdln5ntD8InFPx0yNLb2JGy5g58LngWrBU1UcU1gP/G8LhY8iCQgMqa4tnzwDm5fKGv0oo+rdO/h3xP7SWjX+Vsm1nxV3OmEFk/bH03jNaDLEEgKWNvnU1HDSnAeb5tcZPNO1nTrf0hkyP02C+xwKOY2umdLtGmRF2SuV47mGdqkWSW8XF+Rodxmo7serX/o09n/SDF5WuBsXScTZdzpSvZ2aGjUa+Rkk138C0/81/0cFvY32HLPH5gbJbQwVM1WViTQDXEH2LLvhvYDUL80YJoxDW9BmaoicfcZ2PSZgGqyxDHNV2r3gxeYQoBCStGBO4b0EB2Ykl9HZwXcgxdAIS8PSaqv4OcfQLtjQlTYsof35FBrQhAVtHQejMgewEvcnPK1wbHIOlbdca65cR1Ltd7Ex2JI30BjmD7FdoRgfuhS2+TG+RlNzKdTfZsJz8X5aCikqUTNQazGmBcJkxluSO+F5DBMziM0P0CvWCvX8TVqBCav8ngw4XsD0esm3EEwK9j2EPVDGayXie066vhzg7xbkyf1+qI9PQIW2Mg+lJUAeXh3pec5aJ3h3RKYquRhxvWE3ODJggBMXJZ/iIOZ5zwYqUnSA1h6dYFkf8hVuaO/XtCx1X33HHltjM8sKZ5+4lf5mgCzu1OB/FDdhS2EaVhEim6nJa5UWmTPoou6Yr 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)(39860400002)(376002)(346002)(136003)(396003)(230922051799003)(186009)(1800799009)(451199024)(82310400011)(64100799003)(40470700004)(36840700001)(46966006)(26005)(36860700001)(40460700003)(2616005)(1076003)(7696005)(47076005)(41300700001)(426003)(336012)(70586007)(70206006)(54906003)(316002)(6916009)(5660300002)(82740400003)(81166007)(36756003)(86362001)(8936002)(4326008)(8676002)(40480700001)(6666004)(478600001)(966005)(2906002)(81973001); DIR:OUT; SFP:1101; X-OriginatorOrg: arm.com X-MS-Exchange-CrossTenant-OriginalArrivalTime: 09 Nov 2023 14:13:23.9811 (UTC) X-MS-Exchange-CrossTenant-Network-Message-Id: b1ed8f7c-2762-4377-7812-08dbe12e090f 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: DU6PEPF0000B621.eurprd02.prod.outlook.com X-MS-Exchange-CrossTenant-AuthAs: Anonymous X-MS-Exchange-CrossTenant-FromEntityHeader: HybridOnPrem X-MS-Exchange-Transport-CrossTenantHeadersStamped: DBBPR08MB6236 X-Spam-Status: No, score=-12.5 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 X-BeenThere: gcc-patches@gcc.gnu.org X-Mailman-Version: 2.1.30 Precedence: list List-Id: Gcc-patches mailing list List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , Errors-To: gcc-patches-bounces+incoming=patchwork.ozlabs.org@gcc.gnu.org Create the necessary mappings from the ACLE-defined Neon intrinsics names[1] to the internal builtin function names. [1] https://arm-software.github.io/acle/neon_intrinsics/advsimd.html gcc/ChangeLog: * gcc/config/aarch64/arm_neon.h (vldap1_lane_u64): New. (vldap1q_lane_u64): Likewise. (vldap1_lane_s64): Likewise. (vldap1q_lane_s64): Likewise. (vldap1_lane_f64): Likewise. (vldap1q_lane_f64): Likewise. (vldap1_lane_p64): Likewise. (vldap1q_lane_p64): Likewise. (vstl1_lane_u64): Likewise. (vstl1q_lane_u64): Likewise. (vstl1_lane_s64): Likewise. (vstl1q_lane_s64): Likewise. (vstl1_lane_f64): Likewise. (vstl1q_lane_f64): Likewise. (vstl1_lane_p64): Likewise. (vstl1q_lane_p64): Likewise. --- gcc/config/aarch64/arm_neon.h | 129 ++++++++++++++++++++++++++++++++++ 1 file changed, 129 insertions(+) diff --git a/gcc/config/aarch64/arm_neon.h b/gcc/config/aarch64/arm_neon.h index 349f3167699..ef0d75e07ce 100644 --- a/gcc/config/aarch64/arm_neon.h +++ b/gcc/config/aarch64/arm_neon.h @@ -13446,6 +13446,135 @@ vld1q_lane_u64 (const uint64_t *__src, uint64x2_t __vec, const int __lane) return __aarch64_vset_lane_any (*__src, __vec, __lane); } +#pragma GCC push_options +#pragma GCC target ("+nothing+rcpc3+simd") + +/* vldap1_lane. */ + +__extension__ extern __inline uint64x1_t +__attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) +vldap1_lane_u64 (const uint64_t *__src, uint64x1_t __vec, const int __lane) +{ + return __builtin_aarch64_vec_ldap1_lanev1di_usus ( + (__builtin_aarch64_simd_di *) __src, __vec, __lane); +} + +__extension__ extern __inline uint64x2_t +__attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) +vldap1q_lane_u64 (const uint64_t *__src, uint64x2_t __vec, const int __lane) +{ + return __builtin_aarch64_vec_ldap1_lanev2di_usus ( + (__builtin_aarch64_simd_di *) __src, __vec, __lane); +} + +__extension__ extern __inline int64x1_t +__attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) +vldap1_lane_s64 (const int64_t *__src, int64x1_t __vec, const int __lane) +{ + return __builtin_aarch64_vec_ldap1_lanev1di (__src, __vec, __lane); +} + +__extension__ extern __inline int64x2_t +__attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) +vldap1q_lane_s64 (const int64_t *__src, int64x2_t __vec, const int __lane) +{ + return __builtin_aarch64_vec_ldap1_lanev2di (__src, __vec, __lane); +} + +__extension__ extern __inline float64x1_t +__attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) +vldap1_lane_f64 (const float64_t *__src, float64x1_t __vec, const int __lane) +{ + return __builtin_aarch64_vec_ldap1_lanev1df (__src, __vec, __lane); +} + +__extension__ extern __inline float64x2_t +__attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) +vldap1q_lane_f64 (const float64_t *__src, float64x2_t __vec, const int __lane) +{ + return __builtin_aarch64_vec_ldap1_lanev2df (__src, __vec, __lane); +} + +__extension__ extern __inline poly64x1_t +__attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) +vldap1_lane_p64 (const poly64_t *__src, poly64x1_t __vec, const int __lane) +{ + return __builtin_aarch64_vec_ldap1_lanev1di_psps ( + (__builtin_aarch64_simd_di *) __src, __vec, __lane); +} + +__extension__ extern __inline poly64x2_t +__attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) +vldap1q_lane_p64 (const poly64_t *__src, poly64x2_t __vec, const int __lane) +{ + return __builtin_aarch64_vec_ldap1_lanev2di_psps ( + (__builtin_aarch64_simd_di *) __src, __vec, __lane); +} + +/* vstl1_lane. */ + +__extension__ extern __inline void +__attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) +vstl1_lane_u64 (const uint64_t *__src, uint64x1_t __vec, const int __lane) +{ + __builtin_aarch64_vec_stl1_lanev1di_sus ((__builtin_aarch64_simd_di *) __src, + __vec, __lane); +} + +__extension__ extern __inline void +__attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) +vstl1q_lane_u64 (uint64_t *__src, uint64x2_t __vec, const int __lane) +{ + __builtin_aarch64_vec_stl1_lanev2di_sus ((__builtin_aarch64_simd_di *) __src, + __vec, __lane); +} + +__extension__ extern __inline void +__attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) +vstl1_lane_s64 (int64_t *__src, int64x1_t __vec, const int __lane) +{ + __builtin_aarch64_vec_stl1_lanev1di (__src, __vec, __lane); +} + +__extension__ extern __inline void +__attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) +vstl1q_lane_s64 (int64_t *__src, int64x2_t __vec, const int __lane) +{ + __builtin_aarch64_vec_stl1_lanev2di (__src, __vec, __lane); +} + +__extension__ extern __inline void +__attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) +vstl1_lane_f64 (float64_t *__src, float64x1_t __vec, const int __lane) +{ + __builtin_aarch64_vec_stl1_lanev1df (__src, __vec, __lane); +} + +__extension__ extern __inline void +__attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) +vstl1q_lane_f64 (float64_t *__src, float64x2_t __vec, const int __lane) +{ + __builtin_aarch64_vec_stl1_lanev2df (__src, __vec, __lane); +} + +__extension__ extern __inline void +__attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) +vstl1_lane_p64 (poly64_t *__src, poly64x1_t __vec, const int __lane) +{ + __builtin_aarch64_vec_stl1_lanev1di_sps ((__builtin_aarch64_simd_di *) __src, + __vec, __lane); +} + +__extension__ extern __inline void +__attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) +vstl1q_lane_p64 (poly64_t *__src, poly64x2_t __vec, const int __lane) +{ + __builtin_aarch64_vec_stl1_lanev2di_sps ((__builtin_aarch64_simd_di *) __src, + __vec, __lane); +} + +#pragma GCC pop_options + /* vldn */ __extension__ extern __inline int64x1x2_t From patchwork Thu Nov 9 14:12:48 2023 Content-Type: text/plain; charset="utf-8" MIME-Version: 1.0 Content-Transfer-Encoding: 7bit X-Patchwork-Submitter: Victor Do Nascimento X-Patchwork-Id: 1862107 Return-Path: X-Original-To: incoming@patchwork.ozlabs.org Delivered-To: patchwork-incoming@legolas.ozlabs.org Authentication-Results: legolas.ozlabs.org; dkim=pass (1024-bit key; unprotected) header.d=armh.onmicrosoft.com header.i=@armh.onmicrosoft.com header.a=rsa-sha256 header.s=selector2-armh-onmicrosoft-com header.b=dg6/YE5W; dkim=pass (1024-bit key) header.d=armh.onmicrosoft.com header.i=@armh.onmicrosoft.com header.a=rsa-sha256 header.s=selector2-armh-onmicrosoft-com header.b=dg6/YE5W; dkim-atps=neutral Authentication-Results: legolas.ozlabs.org; spf=pass (sender SPF authorized) smtp.mailfrom=gcc.gnu.org (client-ip=8.43.85.97; helo=server2.sourceware.org; envelope-from=gcc-patches-bounces+incoming=patchwork.ozlabs.org@gcc.gnu.org; receiver=patchwork.ozlabs.org) Received: from server2.sourceware.org (server2.sourceware.org [8.43.85.97]) (using TLSv1.3 with cipher TLS_AES_256_GCM_SHA384 (256/256 bits) key-exchange X25519 server-signature ECDSA (secp384r1) server-digest SHA384) (No client certificate requested) by legolas.ozlabs.org (Postfix) with ESMTPS id 4SR3rM35nsz1yQK for ; Fri, 10 Nov 2023 01:15:15 +1100 (AEDT) Received: from server2.sourceware.org (localhost [IPv6:::1]) by sourceware.org (Postfix) with ESMTP id 752E03858D35 for ; Thu, 9 Nov 2023 14:15:13 +0000 (GMT) X-Original-To: gcc-patches@gcc.gnu.org Delivered-To: gcc-patches@gcc.gnu.org Received: from EUR04-HE1-obe.outbound.protection.outlook.com (mail-he1eur04on2043.outbound.protection.outlook.com [40.107.7.43]) by sourceware.org (Postfix) with ESMTPS id C917B385C6F6 for ; Thu, 9 Nov 2023 14:13:34 +0000 (GMT) DMARC-Filter: OpenDMARC Filter v1.4.2 sourceware.org C917B385C6F6 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 C917B385C6F6 Authentication-Results: server2.sourceware.org; arc=pass smtp.remote-ip=40.107.7.43 ARC-Seal: i=3; a=rsa-sha256; d=sourceware.org; s=key; t=1699539216; cv=pass; b=D3eEKAHdgkQs5qAmonxrLKUedhnMMEY8Ms3s8Gk8N4LQCL+T/0KWET11aryddavAnM5FsOes3ZmZqKA/rx+0a7GbgpyC8tD84L9ZNCs18YFGoi0Z6XR5MQwPz7lpLUGHPsfDd6zrcGNM2ca7VBkJvAXiA/OdRRpNp9SYY5HkkPE= ARC-Message-Signature: i=3; a=rsa-sha256; d=sourceware.org; s=key; t=1699539216; c=relaxed/simple; bh=1X2qVCqw6oNNl36GZLNjaqmWVRCG/tpqWNKt0QS9rNw=; h=DKIM-Signature:DKIM-Signature:From:To:Subject:Date:Message-ID: MIME-Version; b=kF+kEKirSxND9DI/WXS9PEuCEtkHVmqAYqc2CP8VBNcrYBnV4fTGqD0h/7ymABSqCepqcZBdKLxOChZdOrqLzT2KXIQ2IRUwgYwhFZ1XCpiYNrXzMD6vKqXk1x4Tfk4DGBys0gniRDsHUduN9MyIB1heqkdbY/dwJ1ri/W/fcQo= ARC-Authentication-Results: i=3; server2.sourceware.org ARC-Seal: i=2; a=rsa-sha256; s=arcselector9901; d=microsoft.com; cv=pass; b=QNh8uweWs8iNmvhShjfFoqa7m9yuNGbAaBcxyDlF2wAdrdskYziZNFPdHKHjGfScHFioAK8MZEQxUyLT8ivkgxVISsQF7jfDHt9eYcXocHBO2XvxszR5ZKmoQ31c/qB4CqL262GHpcgzSxmpYUFbqt28KPNsIjWn4B5FFjil/GF3QPlWpWDnKNXPvFJhK6oYY/4/TLiS1GMMILsyqgW/aNJnP4+1HF+kXTxM30Xhp5kVtJAxFFHvZ8CcKrzznsSYy1CA64Y69YCaL4jVtU4LzzxK2e+cFZfiz68SDr0qBWdSc0KJ2kOx9ThBml6F2j/Z8chHHlem7AkJsSbc+PwXdg== 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=PR9Tm7k811DgZzfosxmvICDrq/m1ZOICfLOvCXCPAms=; b=GV91HZlcImI2t/nlAVk6Gu6AWfBfLYcJvFj9TrS9jKw6hxa9mWPWmNEQKKKiiGm8wfwcKByFoNP+M02ljamSPThq8CTgeaiYHbt7mTBUpsghmrUAEwIkcw+7jq9KLVXgwKemYkMi6AR+coIqdO7ka3K9Ac3F2VG3gVTVKWAp6JCudjhH/YiITDZ/QagC6gynubksf6spjVGWc+z9xu7tb+iB5f+N1t3zzIPA3RDowGoTD3UIIEm8BSnuLNn1As9419fhrcxv40NBTrOTitZ2dh3DZ5GgHOoJSfScpLWyuM58w2kOc/ZJwjcGSSZsNPKcz9VKF8aKYW1GOwHtw4zeag== 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=PR9Tm7k811DgZzfosxmvICDrq/m1ZOICfLOvCXCPAms=; b=dg6/YE5WiYvSBVOgMgtBA2c3FUghESdpjiQLtYEfz/PKkJ6XInaw79+DNob9ZQtDKDGAc+AcknZmFg7KPqxBtT1jUxZBXg5rLaNhz/WJ+ugCq2RqLY/cEyvEzp1V5L7tRYGCUzniHrdwd71nivM4xVNi3MzhS8oXo/fKx5l6utA= Received: from AM6P194CA0068.EURP194.PROD.OUTLOOK.COM (2603:10a6:209:84::45) by DB8PR08MB5353.eurprd08.prod.outlook.com (2603:10a6:10:112::21) 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:31 +0000 Received: from AM2PEPF0001C70A.eurprd05.prod.outlook.com (2603:10a6:209:84:cafe::3c) by AM6P194CA0068.outlook.office365.com (2603:10a6:209:84::45) 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:31 +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 AM2PEPF0001C70A.mail.protection.outlook.com (10.167.16.198) 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:31 +0000 Received: ("Tessian outbound e243565b0037:v228"); Thu, 09 Nov 2023 14:13:31 +0000 X-CheckRecipientChecked: true X-CR-MTA-CID: 1f5ffb1a23708773 X-CR-MTA-TID: 64aa7808 Received: from 53880ee984d9.1 by 64aa7808-outbound-1.mta.getcheckrecipient.com id AE104DB4-1B46-4925-BD67-558F8773C55F.1; Thu, 09 Nov 2023 14:13:24 +0000 Received: from EUR04-HE1-obe.outbound.protection.outlook.com by 64aa7808-outbound-1.mta.getcheckrecipient.com with ESMTPS id 53880ee984d9.1 (version=TLSv1.2 cipher=ECDHE-RSA-AES256-GCM-SHA384); Thu, 09 Nov 2023 14:13:24 +0000 ARC-Seal: i=1; a=rsa-sha256; s=arcselector9901; d=microsoft.com; cv=none; b=eIu3/Ty7GstMZoUmhXV3LbPs2120Ax2h1ux8rCqGEC7YliGLJrW9T9WmZS98pQQS76zj3lnJyVGBp4Jwcu2D1zy3H9reENt0kC7imi3V6tFIyTOdIP9V4T7apyujxTdIHnIlFoPjU2Dvb0hNcSj44b0YMfgpNTSscMhxvtaCLbbj9FWpjMWIoZoLe6leyBmw2Gz4Jmn+llRkKT8bnMwFT04LLvuglkRrwMa4lstrjGoerzLfbrT37ZRl8QDgO8KDu+hHyvjadQkQ6aKqicOTgdl4heSqIXQbIT0Kl7kS5eoqCVtrBZ294pVIoSHkY9EP9Y2xzoA1Ou8mGGB5WGIZQw== 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=PR9Tm7k811DgZzfosxmvICDrq/m1ZOICfLOvCXCPAms=; b=OuCaXquuc12WXFf9Rh9rZkuyYqrh88az8XpQclahXexs8tC1zb0Q9xFYOyNUFPf2GA/YVFs6vIZQneZiglCdJ3JDMFlCYEn5mhgOYvpwVND7hfBTMyECjLgQfzLs0NjPBGyrXC6RSzLVJXFIJJqzVZAaC6dm17dc37P3Hvj5WsSRgeqZm9t7TPytlxbj5H6xX/msnTsNBACBcWzTyrSVBfzj04WYx3ZSrx2z0oBMj943fxRm19s7+EJVyBzjriRON+vqTHZkvBimO5+fb48fb1/HlhCYHFOSfgqxRUN7tQXTFJfWbgUc2NRkZb6o8YZE1YVe4al2wtN15QMvlNNf2Q== 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=PR9Tm7k811DgZzfosxmvICDrq/m1ZOICfLOvCXCPAms=; b=dg6/YE5WiYvSBVOgMgtBA2c3FUghESdpjiQLtYEfz/PKkJ6XInaw79+DNob9ZQtDKDGAc+AcknZmFg7KPqxBtT1jUxZBXg5rLaNhz/WJ+ugCq2RqLY/cEyvEzp1V5L7tRYGCUzniHrdwd71nivM4xVNi3MzhS8oXo/fKx5l6utA= Received: from DB7PR03CA0097.eurprd03.prod.outlook.com (2603:10a6:10:72::38) by GV2PR08MB8653.eurprd08.prod.outlook.com (2603:10a6:150:b9::7) 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:21 +0000 Received: from DB5PEPF00014B9B.eurprd02.prod.outlook.com (2603:10a6:10:72:cafe::b9) by DB7PR03CA0097.outlook.office365.com (2603:10a6:10:72::38) 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:21 +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 DB5PEPF00014B9B.mail.protection.outlook.com (10.167.8.168) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_128_GCM_SHA256) id 15.20.6977.19 via Frontend Transport; Thu, 9 Nov 2023 14:13:20 +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:10 +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:10 +0000 From: Victor Do Nascimento To: CC: , , , Victor Do Nascimento Subject: [PATCH 5/5] aarch64: rcpc3: Add intrinsics tests Date: Thu, 9 Nov 2023 14:12:48 +0000 Message-ID: <20231109141300.3542453-6-victor.donascimento@arm.com> X-Mailer: git-send-email 2.41.0 In-Reply-To: <20231109141300.3542453-1-victor.donascimento@arm.com> References: <20231109141300.3542453-1-victor.donascimento@arm.com> MIME-Version: 1.0 X-EOPAttributedMessage: 1 X-MS-TrafficTypeDiagnostic: DB5PEPF00014B9B:EE_|GV2PR08MB8653:EE_|AM2PEPF0001C70A:EE_|DB8PR08MB5353:EE_ X-MS-Office365-Filtering-Correlation-Id: 9a3b425f-5fd7-4585-2c0b-08dbe12e0daa 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: Cwo2UcalQzXGLVWJT4rQdmSu9zeS8lOC6ZfUGa9cAeakDBtlDb2rviKtAnHNwcOC9VH/ViDZ9hRZ1/UKaFlyM887CDVFqCfNAIfRhrEFfDDXx6wgIK6nFnMlrN2K59BXpALK4vL2MQ5cGoARHJOdxeETXH4yi1XflfikSmvGtrTVLRVd3Mk65OTQn2xh/gfXqV8v1bKC37ExmUUhM2I+YG7YycVyrNc467R46/PeUPSiYN1PN6NtZKXyBLBjgjD5Ob2JW1saYJwpipZHJ6d71SQjlgnQFTMdpB0hNaZWne0VmvrYRXN+uAxkvSdi/3U1UHhCb5Vowze9FghygmjEgxUWLS/c/t/vi3DT+5vCJciYNMA8NLzv5DeNCMtUWHwt8RD88KYkXx3ZCBW0hIdc1IZzanGWWx6O4VFlkMfIYPsmbyMCcYTxITE/mbQNfQWfP5U8xRw4PNDZ/alKDX2uGPDKn38wmNrKVzJPBUXh7Y5qArXMrZuAQuAoLv7sTztRi/y1K5oFQrIi9C8inquVEZTUYZ6mEYC6w9dUNdmQy8Dle4dSMf7QOoZ9c5DXJXVxKA3f7P49DahdY40IELzwLedL42nj7tqOb4gWEhN2/VO1wg1ZguKl7HMB0/p0jOp2+LWr9qxVpmsjBT+z0S4dBhjzVYYRZwD8LyQlA4mU19w5MeQBToVX0mCSL6CgM7gZEXtg6iZOQ9tYKomWdo7Su/kWoRTDj3m0w4U5LyJxBWTcFBzXjJOdRlt/LwTZHRxJVLg1n7grnSWF5Qe16Y/5/Q== 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)(346002)(39860400002)(396003)(136003)(376002)(230922051799003)(451199024)(64100799003)(82310400011)(186009)(1800799009)(40470700004)(46966006)(36840700001)(84970400001)(40480700001)(40460700003)(41300700001)(1076003)(7696005)(426003)(2616005)(47076005)(6666004)(26005)(336012)(81166007)(36756003)(356005)(82740400003)(86362001)(5660300002)(8676002)(6916009)(4326008)(2906002)(8936002)(316002)(36860700001)(54906003)(478600001)(70586007)(70206006)(36900700001); DIR:OUT; SFP:1101; X-MS-Exchange-Transport-CrossTenantHeadersStamped: GV2PR08MB8653 X-MS-Exchange-Transport-CrossTenantHeadersStripped: AM2PEPF0001C70A.eurprd05.prod.outlook.com X-MS-PublicTrafficType: Email X-MS-Office365-Filtering-Correlation-Id-Prvs: 00ea771b-ed41-4c7f-6cd3-08dbe12e0744 X-Microsoft-Antispam: BCL:0; X-Microsoft-Antispam-Message-Info: vCKJesO362no1F0E0EFP9GYtDWTVlj4Lwx5qdN+VO5cep1PssgmHKdkYrnuXUduUSIPKFTJNqzBxXoZhSzzScq9QjylIddD2dsgTCTblapBPl7UBrZQYwJ0wVxrPtSJb1E1m2zZz8iDTMMvrIpe+V5Uq8WbR0Hn+BCbgTIJEOWZvGcKLbi4K9wth2SLhvNrUPwIfRipioBxZduhTHedZwFR6xYQUFUlSng/z0A4VB+VmCY3M4tLFQrHdnxXcgXNCTZ2hcrygznVMzdZkrbuc2i8WMyDm5O7UmKYrk/jvoED3kPgpxSo9SCcKmPSVAtLXD2if/oYrM4r2jSHUvj6t72DnAMPo6DrdlwF7W1491tlwEN/RzCB9IFQNjz/0dF7vzErMZz1+FMdSawQfR9UvH6LczWYRUc2HW7ww8YI5AROPVpweA8mZT3rWFYDsqQf7x/Qy6vHd4i9afazvgkiOSkqYw/+D+lcyA2cHm4ERJPScmTEPgF0xG/CQDJM3zoVvN/IcMeDqPXWqxB6wsc5a1i1fKK0O+owdvqlgnTZcrwIwoWCsYvOSft53NT5U+ivWi9OmdmReGy70kf3M4liXoN6yiDEhJEL92ATtX2KdIKCsUk8qMo4628XzK3L3PaZ8ElrcAjdFTSFOMUdKF9aPh/Q1lazBRdfuAWZ+Zj5hBMJVquD9DCs68ubysRlxipXh44Uei19ETJRAD/JLQUFqSZMoRwZrXKydOvCBg17+5gk= 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)(39860400002)(136003)(376002)(396003)(346002)(230922051799003)(1800799009)(186009)(451199024)(64100799003)(82310400011)(40470700004)(46966006)(36840700001)(84970400001)(82740400003)(81166007)(40460700003)(40480700001)(7696005)(478600001)(70206006)(70586007)(36756003)(86362001)(6666004)(47076005)(426003)(336012)(26005)(2616005)(1076003)(6916009)(2906002)(5660300002)(54906003)(316002)(41300700001)(4326008)(8676002)(36860700001)(8936002); DIR:OUT; SFP:1101; X-OriginatorOrg: arm.com X-MS-Exchange-CrossTenant-OriginalArrivalTime: 09 Nov 2023 14:13:31.6589 (UTC) X-MS-Exchange-CrossTenant-Network-Message-Id: 9a3b425f-5fd7-4585-2c0b-08dbe12e0daa 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: AM2PEPF0001C70A.eurprd05.prod.outlook.com X-MS-Exchange-CrossTenant-AuthAs: Anonymous X-MS-Exchange-CrossTenant-FromEntityHeader: HybridOnPrem X-MS-Exchange-Transport-CrossTenantHeadersStamped: DB8PR08MB5353 X-Spam-Status: No, score=-12.5 required=5.0 tests=BAYES_00, DKIM_SIGNED, DKIM_VALID, FORGED_SPF_HELO, GIT_PATCH_0, 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=ham autolearn_force=no version=3.4.6 X-Spam-Checker-Version: SpamAssassin 3.4.6 (2021-04-09) on server2.sourceware.org X-BeenThere: gcc-patches@gcc.gnu.org X-Mailman-Version: 2.1.30 Precedence: list List-Id: Gcc-patches mailing list List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , Errors-To: gcc-patches-bounces+incoming=patchwork.ozlabs.org@gcc.gnu.org Add unit test to ensure that added intrinsics compile to the correct `LDAP1 {Vt.D}[lane],[Xn]' and `STL1 {Vt.d}[lane],[Xn]' instructions. gcc/testsuite/ChangeLog: * gcc.target/aarch64/acle/rcpc3.c: New. --- gcc/testsuite/gcc.target/aarch64/acle/rcpc3.c | 47 +++++++++++++++++++ 1 file changed, 47 insertions(+) create mode 100644 gcc/testsuite/gcc.target/aarch64/acle/rcpc3.c diff --git a/gcc/testsuite/gcc.target/aarch64/acle/rcpc3.c b/gcc/testsuite/gcc.target/aarch64/acle/rcpc3.c new file mode 100644 index 00000000000..689d047ab91 --- /dev/null +++ b/gcc/testsuite/gcc.target/aarch64/acle/rcpc3.c @@ -0,0 +1,47 @@ +/* Test the rcpc3 ACLE intrinsics. */ +/* { dg-do compile } */ +/* { dg-options "-O2 -march=armv8.2-a+rcpc3" } */ +#include +#include + +#define TEST_LDAP(TYPE, T) \ + TYPE##x##1_t T##1_test (TYPE##_t const * ptr, TYPE##x##1_t src) { \ + return vldap1_lane_##T##64 (ptr, src, 0); \ + } + +#define TEST_LDAPQ(TYPE, T) \ + TYPE##x##2_t T##2_test (TYPE##_t const * ptr, TYPE##x##2_t src) { \ + return vldap1q_lane_##T##64 (ptr, src, 1); \ + } + +#define TEST_STL(TYPE, T) \ + void T##1s_test (TYPE##_t * ptr, TYPE##x##1_t src) { \ + vstl1_lane_##T##64 (ptr, src, 0); \ + } + +#define TEST_STLQ(TYPE, T) \ + void T##2s_test (TYPE##_t * ptr, TYPE##x##2_t src) { \ + vstl1q_lane_##T##64 (ptr, src, 1); \ + } + +TEST_LDAP (uint64, u); +TEST_LDAP (int64, s); +TEST_LDAP (float64, f); +TEST_LDAP (poly64, p); +/* { dg-final { scan-assembler-times {ldap1\t\{v\d.d\}\[0\], \[x\d\]} 4 } } */ +TEST_LDAPQ (uint64, u); +TEST_LDAPQ (int64, s); +TEST_LDAPQ (float64, f); +TEST_LDAPQ (poly64, p); +/* { dg-final { scan-assembler-times {ldap1\t\{v\d.d\}\[1\], \[x\d\]} 4 } } */ + +TEST_STL (uint64, u); +TEST_STL (int64, s); +TEST_STL (float64, f); +TEST_STL (poly64, p); +/* { dg-final { scan-assembler-times {stl1\t\{v\d.d\}\[0\], \[x\d\]} 4 } } */ +TEST_STLQ (uint64, u); +TEST_STLQ (int64, s); +TEST_STLQ (float64, f); +TEST_STLQ (poly64, p); +/* { dg-final { scan-assembler-times {stl1\t\{v\d.d\}\[1\], \[x\d\]} 4 } } */