From patchwork Fri Oct 4 17:51:49 2024 Content-Type: text/plain; charset="utf-8" MIME-Version: 1.0 Content-Transfer-Encoding: 7bit X-Patchwork-Submitter: Andrew Carlotti X-Patchwork-Id: 1992939 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=arm.com header.i=@arm.com header.a=rsa-sha256 header.s=selector1 header.b=DTf3DKdn; dkim=pass (1024-bit key) header.d=arm.com header.i=@arm.com header.a=rsa-sha256 header.s=selector1 header.b=DTf3DKdn; 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 4XKx2f6H2hz1xtH for ; Sat, 5 Oct 2024 03:52:26 +1000 (AEST) Received: from server2.sourceware.org (localhost [IPv6:::1]) by sourceware.org (Postfix) with ESMTP id 1C4A5385E83E for ; Fri, 4 Oct 2024 17:52:25 +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-db8eur05on20600.outbound.protection.outlook.com [IPv6:2a01:111:f403:2614::600]) by sourceware.org (Postfix) with ESMTPS id EC1F5385841E for ; Fri, 4 Oct 2024 17:52:03 +0000 (GMT) DMARC-Filter: OpenDMARC Filter v1.4.2 sourceware.org EC1F5385841E 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 EC1F5385841E Authentication-Results: server2.sourceware.org; arc=pass smtp.remote-ip=2a01:111:f403:2614::600 ARC-Seal: i=3; a=rsa-sha256; d=sourceware.org; s=key; t=1728064325; cv=pass; b=sG/FOf5JYt5U7O3/h9gLBxIEDXLU8Pv3Ovz6PIk1aSHwyPIunwfD9C78wWsbh8ipA+JHL9zZRvR4p1WSSIHlfwQduKu+TsIhkJdRCWUbk9u+pIjdrqS6w47WoRCJ8DxEKH+Vomk+OvgOBNyO8ob4INU2vkER/nauw+HfLsGUEeI= ARC-Message-Signature: i=3; a=rsa-sha256; d=sourceware.org; s=key; t=1728064325; c=relaxed/simple; bh=Rs6ZQotwUHmohYnRbd4+PLVboG7EDVPiYwpeEWK2yvk=; h=DKIM-Signature:DKIM-Signature:Date:From:To:Subject:Message-ID: MIME-Version; b=TrYWDZa1ulWgImprqr0Ne1EF7kPqs0d3tXzEDaWydzTQYPXXFaO4cgv1Z5R1O4Mcmjva1OnHS2Fnts8f62AEX4OBtraKkgIx6lNPiGK9408qV89bDClYEqT7jhIf6jsGbffG50BhGCpaZ1Eqh8UkElhy65zg+6M8qTDKEbz8ZyA= ARC-Authentication-Results: i=3; server2.sourceware.org ARC-Seal: i=2; a=rsa-sha256; s=arcselector10001; d=microsoft.com; cv=pass; b=wCPWNyPLT5orzjucB3GYgJ2ggXrnvlEASn65/ofQn6b57jjmvJzWDLWx39QCXnhWl1553gwxwyK6zNB51JTRHN6RT4IW8ZON0o2lLVJ58aXt/IEdccWkBrJEjlyZh5kj6HYhfXAi/B5v/vAo+M9rQ48/CqTpfFrobqcX+RRXL8XMiP08oPFcSb+nIf4ZmPE/D+RxVrNNdUYA1GD2xalsfKs+wr2rNn3akkb+3jeI3zU2VGPt2gL+KhBTLAFDh7GDMVHO3zPEhAJGlo9Oiz++bl1tbuZre1i0P3NHXktX17rkvXuq8/bef15tIAEcwcBs4Cb5MR6quCIXkyZHQdI4+g== ARC-Message-Signature: i=2; a=rsa-sha256; c=relaxed/relaxed; d=microsoft.com; s=arcselector10001; 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=NAsancyR7f6oRh5oEg1FFklY9Dc0K5MtDytoLXeJ6Zs=; b=F0soQgB94cDKDfxQrK1DVZFlaltSzkMrcn2msj4etwCQembOTTe2wgt88oBGSZnYezI5v72BWPYXBYdPImxhYBByULUUPX68V/b5fDKylWn9T7ZJ+NnJhAGN66Z/qzlE5MV5ay8PVu5NhUSvbBZNt+JAAinPxbCen/rdonAU9aSC0sKpviX0rn7F0ql45V2IBOU0F9r/f+pPDzPK3Cha4i/ZhW96ek3K8Zr/zFnHZ/nRiB8Ls4/Dxw+jcwfnWJxQnlGZACprFFnCmd9+Aoaaq+iEKbnMhLScuFZh7+Ita+zHXAMepFiK8pIveMnJkV38f/4UrMmwxJJ9U25AQaCFtA== 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=arm.com; arc=pass (0 oda=1 ltdi=1 spf=[1,1,smtp.mailfrom=arm.com] dkim=[1,1,header.d=arm.com] dmarc=[1,1,header.from=arm.com]) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=arm.com; s=selector1; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-SenderADCheck; bh=NAsancyR7f6oRh5oEg1FFklY9Dc0K5MtDytoLXeJ6Zs=; b=DTf3DKdniYDh0PRVJ82AeH0Kc4g8OhUhMAP8c2K4FTvVBdWWcSs8NczTkqijYyz78lM3/+pNK/tO0FpCawyy8f18pGBiULNBEdyqJ0c8H7Ws2kg33muzvBU6hGczB8ufBOwl6gKKWDN/fC7xFJAStclxA9Bt1NSUZ4n4k68zVUA= Received: from DB8P191CA0027.EURP191.PROD.OUTLOOK.COM (2603:10a6:10:130::37) by DU0PR08MB9726.eurprd08.prod.outlook.com (2603:10a6:10:446::17) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.8026.18; Fri, 4 Oct 2024 17:52:00 +0000 Received: from DB1PEPF000509E3.eurprd03.prod.outlook.com (2603:10a6:10:130:cafe::b8) by DB8P191CA0027.outlook.office365.com (2603:10a6:10:130::37) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.8026.19 via Frontend Transport; Fri, 4 Oct 2024 17:52:00 +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=arm.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 DB1PEPF000509E3.mail.protection.outlook.com (10.167.242.53) with Microsoft SMTP Server (version=TLS1_3, cipher=TLS_AES_256_GCM_SHA384) id 15.20.8005.15 via Frontend Transport; Fri, 4 Oct 2024 17:51:59 +0000 Received: ("Tessian outbound 1cf41b4bd505:v473"); Fri, 04 Oct 2024 17:51:59 +0000 X-CheckRecipientChecked: true X-CR-MTA-CID: 1ccb56302180f196 X-TessianGatewayMetadata: Q8vMEOZ2pW7cz0wzB2U2Kd22WalBhkQLLAeuWZiTb7q4plOccJClDZZHg9kWeW9bJ36HnS0ibpT/sYvfmIx0znbaOHFODhRAF5jU493bmAuj/uUpwRqHX9EebgpRAMdrzOsVOCDoWTEiZYUND3qQHwNhL66zq5KIfxkad6C+MbjdimZqdFOEC320G8FDrJZ8 X-CR-MTA-TID: 64aa7808 Received: from Lb5e9ba60031a.1 by 64aa7808-outbound-1.mta.getcheckrecipient.com id 4C77731A-F15A-4EC8-AACD-157C9BFB34E4.1; Fri, 04 Oct 2024 17:51:53 +0000 Received: from EUR02-DB5-obe.outbound.protection.outlook.com by 64aa7808-outbound-1.mta.getcheckrecipient.com with ESMTPS id Lb5e9ba60031a.1 (version=TLSv1.2 cipher=ECDHE-RSA-AES256-GCM-SHA384); Fri, 04 Oct 2024 17:51:53 +0000 ARC-Seal: i=1; a=rsa-sha256; s=arcselector10001; d=microsoft.com; cv=none; b=lqDDOe3ue2tIOAmdPAuwqn33nzVz3zLc2txBJtqRypRqciWxrde6pvLcBG0pQA5CIgJtSFvC1VLHgnRHsu2f5ywk1H2pUO/mVfPI4rj91TGfb2Q7Lt8g72F9XaevkdkY4CuNY2bDBi9SFYg7MpNe0jLdWy0dxSVKdDNCUf/eTSAOE08387kzU+g0wTmtREPlB2Y6l+sYh9GfwBKRaj165uS13eTH64Mz6JEk1bkh4Hb4JObagyC06Cd5PrAcB4RmXo1ABT372xjjwISh/98x0DtasSGwmSGx6weWLPCB+I5hLebQhypP/29xjZKiA6KMMzlqwh/EwLPk+QD+Loabaw== ARC-Message-Signature: i=1; a=rsa-sha256; c=relaxed/relaxed; d=microsoft.com; s=arcselector10001; 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=NAsancyR7f6oRh5oEg1FFklY9Dc0K5MtDytoLXeJ6Zs=; b=cWH8J4e9g0czIxjnFJparf/iYoDczPMv1I/pqEHArt64DCFM2Q9EZ49e9Kw6VmQX2F3UM+zdKYwsEorxgm8i6sK3jMTuGPuOGLsjZgZm6eBsvnqLl/8/6eu1yS4pcXLKHzDNnpNvBlBzT5TfmNe+BUYQSX5FeZAMdeNAFJdC0rRsZlnYTca0po0UKJQSXeD/GS46axc7UPyIPhmCR/XTYwcG1YbBn8OmtMAIgBK1r96XIhPGBXdywhAPUAjGMcUztFCpQQZF6/0+kLY7+BzPxvOsecKfvrXylK4BzUdBUw4gCErmZXl/eBvmqjzu+yp3GZemz+TO8xi0tt5Yl02v/g== ARC-Authentication-Results: i=1; mx.microsoft.com 1; spf=pass smtp.mailfrom=arm.com; dmarc=pass action=none header.from=arm.com; dkim=pass header.d=arm.com; arc=none DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=arm.com; s=selector1; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-SenderADCheck; bh=NAsancyR7f6oRh5oEg1FFklY9Dc0K5MtDytoLXeJ6Zs=; b=DTf3DKdniYDh0PRVJ82AeH0Kc4g8OhUhMAP8c2K4FTvVBdWWcSs8NczTkqijYyz78lM3/+pNK/tO0FpCawyy8f18pGBiULNBEdyqJ0c8H7Ws2kg33muzvBU6hGczB8ufBOwl6gKKWDN/fC7xFJAStclxA9Bt1NSUZ4n4k68zVUA= Authentication-Results-Original: dkim=none (message not signed) header.d=none;dmarc=none action=none header.from=arm.com; Received: from DU0PR08MB8255.eurprd08.prod.outlook.com (2603:10a6:10:411::9) by AS8PR08MB9527.eurprd08.prod.outlook.com (2603:10a6:20b:61d::7) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.8026.8; Fri, 4 Oct 2024 17:51:51 +0000 Received: from DU0PR08MB8255.eurprd08.prod.outlook.com ([fe80::cbc8:c020:6a1b:d27a]) by DU0PR08MB8255.eurprd08.prod.outlook.com ([fe80::cbc8:c020:6a1b:d27a%5]) with mapi id 15.20.8026.017; Fri, 4 Oct 2024 17:51:51 +0000 Date: Fri, 4 Oct 2024 18:51:49 +0100 From: Andrew Carlotti To: gcc-patches@gcc.gnu.org Cc: Richard Sandiford Subject: [PATCH 1/8] aarch64: Use PAUTH instead of V8_3A in some places Message-ID: <705937e6-c27e-fcb0-9b1b-203770a3c89e@e124511.cambridge.arm.com> References: Content-Disposition: inline In-Reply-To: X-ClientProxiedBy: LO2P265CA0424.GBRP265.PROD.OUTLOOK.COM (2603:10a6:600:a0::28) To DU0PR08MB8255.eurprd08.prod.outlook.com (2603:10a6:10:411::9) MIME-Version: 1.0 X-MS-TrafficTypeDiagnostic: DU0PR08MB8255:EE_|AS8PR08MB9527:EE_|DB1PEPF000509E3:EE_|DU0PR08MB9726:EE_ X-MS-Office365-Filtering-Correlation-Id: 5fc395ce-3e81-4acc-7eee-08dce49d3ef9 x-checkrecipientrouted: true NoDisclaimer: true X-MS-Exchange-SenderADCheck: 1 X-MS-Exchange-AntiSpam-Relay: 0 X-Microsoft-Antispam-Untrusted: BCL:0;ARA:13230040|366016|376014|1800799024; X-Microsoft-Antispam-Message-Info-Original: Nqn1dLRe7SbmezxEikHXSozU3NX/uqGTxveN4/0StFNiHc2ExYoYrwVmfn0axpI6us7FC8ZNyyWeYMpFS6+eEnM6mEGlZKFG+RVw696VgsgGdOHKQtbh7VE8dMI4yONXAxIzl7m+6rwsU4Y4qhnXrw/kOD0qOH6JGHhXBKLuxYL7FnkQrr769vtCnXdwlOIp0+a1PyNjWm5PvxfYacGd7wbY5G+urvAH4WGVXIrfoPXnoVTHtyPXPMfcwSGZw7DFVDqdG+3yzP0rYqOvmntjOtyhFyAYiyVby74fc+HbKaRauTPKDS1BYiFyGMDF78Blb0seR/Xg/mJztrAGL4oSWE2HmcRHUS2K2s6PMeroLh2KnyqRUgMZ/RY1BtF6dsNF4NQU6xm7rgK3iygmxt2NMLfZv7RBrUCm6Uiu5JUTU6CqhE5wAnPgYvtHqGYh9itk7DSn0hJJS9S2zlYvBiLOhV7QFaFrZOM6YwJ0EE1bsaH+eBcYTnGzF+3KLLlBNfnQNeWBIixeTfEKe7492mnxuMwUqulhVICDnJkhZVW3powk1mR1acHUMjlYlJonsD/vb1YwXTppsNMk0gwYs4F2kh1SXQ3fHS+VJYzdufguZf8fYVwUCqDhHf8+pa+l5dpyZNiJdOSbTvmwnCYu+txrbPCiQo0mgpHRZgd2bHL2MQcD2/AhZDn+c23Mgcq8QrUbK3mkUBLZ135ApysdoOW2psSEundBh4lFqt5NRpr1m2foHnSzFIfI2jfQ8uYOfJ4KO6w1y2V7ET78FjaJry+bT9m1/ANKpNwXYjpRFPuoHQQuVJIlSGqKXS1O6yTyldiKEeCYVIaV9w/pls0Ye8VN83YABQwODq+6g+iNMmGpN6fIHivdw5FeDgGyHH/ZdbSLuc3m6vfLFDxbAmiKIFwvU0Lf2mwcRI1ZnUKe/Uc8aWYcr0gsI0qpdMVXhillLIxcKXaIUfoC3m8TablRyhI3Uxc2dj3qRnTdzANwTnyrd96+kPbmFj7zhBnXkUvK1lGLb7Foqagm99l9uG7VOQODQU+/K+xpOOwrbR5EUJ/m3MlFMd1mblmBng3TEWM2Jxny/PC7U7r32OfE/DRGbFjo0hzPDM/i0zsiUalUO3ckbFHf8BiM0SDNzsvOVva0botiuNZ2k/kcvpLCtrvNxWk3I8TVe04VsqtDWO2iIoyJ2YP5NjdrqTpLr3WcpUpjPYebERDbTHeiwZxgdh/K0ZIvIrCR7QkzHefIbqpSO7d5zoaKSv1zjWomH9YWgNvs5jgJTQ4Nk9xbFMYtcYEjPzfwpA== X-Forefront-Antispam-Report-Untrusted: CIP:255.255.255.255; CTRY:; LANG:en; SCL:1; SRV:; IPV:NLI; SFV:NSPM; H:DU0PR08MB8255.eurprd08.prod.outlook.com; PTR:; CAT:NONE; SFS:(13230040)(366016)(376014)(1800799024); DIR:OUT; SFP:1101; X-MS-Exchange-Transport-CrossTenantHeadersStamped: AS8PR08MB9527 Original-Authentication-Results: dkim=none (message not signed) header.d=none;dmarc=none action=none header.from=arm.com; X-EOPAttributedMessage: 0 X-MS-Exchange-SkipListedInternetSender: ip=[2603:10a6:10:411::9]; domain=DU0PR08MB8255.eurprd08.prod.outlook.com X-MS-Exchange-Transport-CrossTenantHeadersStripped: DB1PEPF000509E3.eurprd03.prod.outlook.com X-MS-PublicTrafficType: Email X-MS-Office365-Filtering-Correlation-Id-Prvs: 4f052374-004f-48fc-80c6-08dce49d3a36 X-Microsoft-Antispam: BCL:0; ARA:13230040|376014|82310400026|35042699022|1800799024|36860700013; X-Microsoft-Antispam-Message-Info: Fy/+9RV/Cg8KYHyezpWUEI9AThnfUXaSsnGbnYuCJXeg28W+J5DLEMLIPbpChqQJJi/mWN7JnaBTq6lHZ5Yk8Dk/b2dz4CdvTURLcIuY93u3/RDI1qi/GJIrX9q0gSNXiWDJN8Q2st0R5Hig3TsyaaS4oyYVKBPKr0zyql5z32ga1EF5Yohk+PaVsMPSeXA0f4x+VB3jSj1dWJ5ZFm4mr89mci6wew/hZWbU8xjz5BUsS+s6rw49r4lbkvCcuNtAN4hiBpgOHR7WMgnuny220suHniRilQO7L3I8SWgFQdtvVuBOF3Kc7bYPF0NebD/AohSp9QU5pWrWYpWIwimyUzLHWE7e/CoxyGi597KzQAmXGvQ7OIJezCB+hrjD2HO6tGFWHCxoj4Bi7MpX/z4I3V6RY1UYcKaNThVWR/O6zU+lS0PjIFUt7SJmKCGBxDGyaQg0PxVHd85ZbT7k2DQZaorAUqFedEc3qVWR47yV88LwI46RaVOdGFv68ubWPxOy7FmP/NFrjDbnYkiCbo0ZcXy/3A5zHwsS5ClyZ1scDBqAh2RkUhH9u8O6F+3Xag3G+lj9OPWEcY+Fy3BXEhaszLdpzCc0ab/Tnm2doPEttUUQZ/dRPMZJ9v80pEw63UBo5+hBSYH5rk2fc61xhaAR+ftLqg/qU9OQ79aFJ62vm667l6rJwr2/nFPB2U0VISGDiEUOyRHA7jyAv7XQl6tiVpDxzInoqrskNXeP+zcqoFHVrDZ/o0h3eDkMnUwneXp2PZ+UD5X8OTnsD+p8ZpHEgrdGwVxOBbT2FXj7vVMjmNyXr19PAIXf/Jq+4QqR3f62FBO7Z3BKDLgEhDZqcEF8nGctcIT/R4+WcTm6CteQSkMfuBsnXqqoDQTUP/3pSQPJdrm5rob4DxrtR/K35i+5aFcrqHNRZbPx06A99E73VcgLbpDeHB6z+cAp+PpVlpxoO0tosFvPrjfGb45Xn7HeyrVQksiAC4Lrzh5kMFJnPAfoaDZw9r0LA8BsNBM2kPhd+LVy5ENGmmnslBzYfy+4hcwKmzvWCdcL0+J4M+pG3FAsZ6rLaIT/kleaNv1NLDfJul9ntsNhpN/13HrukcdT2lG6LPNiTo/cjqSUjbKCFL6mWY5QMH8kJHXNgcjfou0CWWb/LXJcN53azO0en2fKWnQ2u+1yYOzpBwiTb/9SryGhoGUT5c6ForrSUEReLSfd4uyH4zYiE3KFxcQedgw64k5ojilKmt2mgM1nQifE9iZhRgY78h7Hx62za6IG/Ho66KTDFD6H+ypcVZTZcg3hgB04fxq9yKFBGkVaGkuvJ4M1MqUmsa5biRR5vqZX1G9bcNyTlKoaG4Lk2z5qRTBYpT0SEjgOGvj2fFmLNYf8VyQ= 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:(13230040)(376014)(82310400026)(35042699022)(1800799024)(36860700013); DIR:OUT; SFP:1101; X-OriginatorOrg: arm.com X-MS-Exchange-CrossTenant-OriginalArrivalTime: 04 Oct 2024 17:51:59.7148 (UTC) X-MS-Exchange-CrossTenant-Network-Message-Id: 5fc395ce-3e81-4acc-7eee-08dce49d3ef9 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: DB1PEPF000509E3.eurprd03.prod.outlook.com X-MS-Exchange-CrossTenant-AuthAs: Anonymous X-MS-Exchange-CrossTenant-FromEntityHeader: HybridOnPrem X-MS-Exchange-Transport-CrossTenantHeadersStamped: DU0PR08MB9726 X-Spam-Status: No, score=-12.2 required=5.0 tests=BAYES_00, DKIM_SIGNED, DKIM_VALID, DKIM_VALID_AU, DKIM_VALID_EF, FORGED_SPF_HELO, GIT_PATCH_0, SPF_HELO_PASS, SPF_NONE, TXREP, 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 gcc/ChangeLog: * config/aarch64/aarch64.cc (aarch64_expand_epilogue): Use TARGET_PAUTH. * config/aarch64/aarch64.md: Update comment. diff --git a/gcc/config/aarch64/aarch64.cc b/gcc/config/aarch64/aarch64.cc index e7bb3278a27eca44c46afd26069d608218198a54..cf1107127fd5d9e12ad42441528666bf6b733f73 100644 --- a/gcc/config/aarch64/aarch64.cc +++ b/gcc/config/aarch64/aarch64.cc @@ -10042,12 +10042,12 @@ aarch64_expand_epilogue (rtx_call_insn *sibcall) 1) Sibcalls don't return in a normal way, so if we're about to call one we must authenticate. - 2) The RETAA instruction is not available before ARMv8.3-A, so if we are - generating code for !TARGET_ARMV8_3 we can't use it and must + 2) The RETAA instruction is not available without FEAT_PAuth, so if we + are generating code for !TARGET_PAUTH we can't use it and must explicitly authenticate. */ if (aarch64_return_address_signing_enabled () - && (sibcall || !TARGET_ARMV8_3)) + && (sibcall || !TARGET_PAUTH)) { switch (aarch64_ra_sign_key) { diff --git a/gcc/config/aarch64/aarch64.md b/gcc/config/aarch64/aarch64.md index c54b29cd64b9e0dc6c6d12735049386ccedc5408..0940a84f9295ee2bc07282b150095fdb5af11a4d 100644 --- a/gcc/config/aarch64/aarch64.md +++ b/gcc/config/aarch64/aarch64.md @@ -7672,10 +7672,10 @@ ) ;; Pointer authentication patterns are always provided. In architecture -;; revisions prior to ARMv8.3-A these HINT instructions operate as NOPs. +;; revisions prior to FEAT_PAuth these HINT instructions operate as NOPs. ;; This lets the user write portable software which authenticates pointers -;; when run on something which implements ARMv8.3-A, and which runs -;; correctly, but does not authenticate pointers, where ARMv8.3-A is not +;; when run on something which implements FEAT_PAuth, and which runs +;; correctly, but does not authenticate pointers, where FEAT_PAuth is not ;; implemented. ;; Signing/Authenticating R30 using SP as the salt. From patchwork Fri Oct 4 17:52:11 2024 Content-Type: text/plain; charset="utf-8" MIME-Version: 1.0 Content-Transfer-Encoding: 7bit X-Patchwork-Submitter: Andrew Carlotti X-Patchwork-Id: 1992940 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=arm.com header.i=@arm.com header.a=rsa-sha256 header.s=selector1 header.b=QP4PGSrS; dkim=pass (1024-bit key) header.d=arm.com header.i=@arm.com header.a=rsa-sha256 header.s=selector1 header.b=QP4PGSrS; 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 4XKx394DxLz1xtH for ; Sat, 5 Oct 2024 03:52:53 +1000 (AEST) Received: from server2.sourceware.org (localhost [IPv6:::1]) by sourceware.org (Postfix) with ESMTP id 57918385E83D for ; Fri, 4 Oct 2024 17:52:51 +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-dbaeur03on20623.outbound.protection.outlook.com [IPv6:2a01:111:f403:260d::623]) by sourceware.org (Postfix) with ESMTPS id 30E18385EC05 for ; Fri, 4 Oct 2024 17:52:26 +0000 (GMT) DMARC-Filter: OpenDMARC Filter v1.4.2 sourceware.org 30E18385EC05 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 30E18385EC05 Authentication-Results: server2.sourceware.org; arc=pass smtp.remote-ip=2a01:111:f403:260d::623 ARC-Seal: i=3; a=rsa-sha256; d=sourceware.org; s=key; t=1728064349; cv=pass; b=lABdElg/GHTeqGN6B4olV/tw2trwkiDdjzLW83x2bP7w/YJIAjwTBQ7Bt1VIOKJwTEiFLIxqtmszCCOuP5Jc4qA+IbEQxzy9uGlQp4eF5PqYNntSIvpIp2Zm5lSuWuFUQJXRyRUQDud1tbqWGJHljIR5z5n6SWV4Ig3aHMDpUN8= ARC-Message-Signature: i=3; a=rsa-sha256; d=sourceware.org; s=key; t=1728064349; c=relaxed/simple; bh=8ss012gedSBPBPRMylulq43hYr7JXoMd/MwW6DpgFeg=; h=DKIM-Signature:DKIM-Signature:Date:From:To:Subject:Message-ID: MIME-Version; b=XAui5odq+rNqyHfbng/bWNOp5ZacsnxES/VzvWgUVpbWstiVhCnIlQ+1pLX+GK2WvS7kXaMqdBH3MDOIvg1fseJolVyXkSHLm5KPfFkVyf4ayHHhGT3kc0ek7AnToTPvQFxZDp71XfVSOBl7fgW1B8kuonNjQ68+n3KZxuAi/ks= ARC-Authentication-Results: i=3; server2.sourceware.org ARC-Seal: i=2; a=rsa-sha256; s=arcselector10001; d=microsoft.com; cv=pass; b=KjIEQatTUn+TejQixsj/Coac0N3+mG5c944EdirzHDoSySaxflrIepMmMuCO9/yW+8/7ywZAWqND8J8pPdCeWS4hx2jROjzqZVJv1UFoZnjR7Kf4BupYquRb6jglIvCtxhE6udBE+1hIQFI3Ia212zZutDldKqA+tL+5TerIbqOnZxGmBr9m83mQW63OXjAvHrPvGllAO/QmoWW0rO35OGnjukoEE+gmZaueAusoEfxpgremImMto1u0vYzLZxEj26odjsDpSJfgrH/HwythYZF4MBiccmSZ4afz6M/ZX+IO99czOWJz0WJwAo3cgaw7lD+MU0MHRBQOxpDW2MkvUw== ARC-Message-Signature: i=2; a=rsa-sha256; c=relaxed/relaxed; d=microsoft.com; s=arcselector10001; 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=y/jigiR+nh0potAum7k/O0P/eZHARAO7GuEl0jbitnU=; b=Z9BygD7rIK45mmTKEjXW2ludJcGyG2WqE8hGEUe0SSEKCryZ9PDmYmT3OIF6kv5gEy5d4ZlKYR2i7huDR6cwnEowsOptS9AmBJwKNi2bro0oyR14LQ/q9u0gSHsqh97Tc5LKofpm45CsQ3E2Wh7uyjmH7DABxnj3h2VJVYeBZFBztmlfIOd0ydOlWkFWhum0A7YprcTmoDGfgi8IalVzVfOb0fIeqecEWGrb0e8x77EM/TJCQ1gfKoRpHWWAu+BbWrFoU5LEYh6Jq1jp+oaDMOHPeUrnkvM9mNNXUWGosCVkYf7ViPR2SVNyXlDi1h19WC5k/H+085qvwtcJns7uUA== 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=arm.com; arc=pass (0 oda=1 ltdi=1 spf=[1,1,smtp.mailfrom=arm.com] dkim=[1,1,header.d=arm.com] dmarc=[1,1,header.from=arm.com]) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=arm.com; s=selector1; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-SenderADCheck; bh=y/jigiR+nh0potAum7k/O0P/eZHARAO7GuEl0jbitnU=; b=QP4PGSrSHEv20Jbsk6otUvZ9V+xW+JhfEIdOUnq7ab99pNW97JwQBSgp1xTVDxt5kcOB9tmmAPSct9Naos8SMcWvSh2kVKYvcIeUYbRl/l9i0Keza1geisTOzl4a1O2HEyBxoZbvqIpu8UyRbfn7OXv/JFabuCH050HJJ3qf4do= Received: from DU6P191CA0068.EURP191.PROD.OUTLOOK.COM (2603:10a6:10:53e::20) by AS8PR08MB9866.eurprd08.prod.outlook.com (2603:10a6:20b:5aa::8) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.8026.18; Fri, 4 Oct 2024 17:52:21 +0000 Received: from DB1PEPF000509F3.eurprd02.prod.outlook.com (2603:10a6:10:53e:cafe::8a) by DU6P191CA0068.outlook.office365.com (2603:10a6:10:53e::20) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.8026.18 via Frontend Transport; Fri, 4 Oct 2024 17:52: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=arm.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 DB1PEPF000509F3.mail.protection.outlook.com (10.167.242.149) with Microsoft SMTP Server (version=TLS1_3, cipher=TLS_AES_256_GCM_SHA384) id 15.20.8026.11 via Frontend Transport; Fri, 4 Oct 2024 17:52:21 +0000 Received: ("Tessian outbound 994fc319cf83:v473"); Fri, 04 Oct 2024 17:52:21 +0000 X-CheckRecipientChecked: true X-CR-MTA-CID: bd679af59e0769bd X-TessianGatewayMetadata: XOtDrcsIjjb4tSDDETFjW3eyakHW4tZA4nwHPwWaNaBVkfMRj6ep/GT5d+PJQ4sRkzZcZKOPKTCO4N9zMjXDVMLhmZmFwI897TjJJUmnQ2WmJe2wrKp9aMmQs13TwLv9qu3GM1PDwweMLlcKkXM4orVBTrV7QZ577JRoVfem6oHkKfNH83On8mW5bEqFGnHx X-CR-MTA-TID: 64aa7808 Received: from L0c6ef2ca2e21.2 by 64aa7808-outbound-1.mta.getcheckrecipient.com id 1C49EDAD-2183-4896-A6D9-DFB867B0B015.1; Fri, 04 Oct 2024 17:52:15 +0000 Received: from EUR02-AM0-obe.outbound.protection.outlook.com by 64aa7808-outbound-1.mta.getcheckrecipient.com with ESMTPS id L0c6ef2ca2e21.2 (version=TLSv1.2 cipher=ECDHE-RSA-AES256-GCM-SHA384); Fri, 04 Oct 2024 17:52:14 +0000 ARC-Seal: i=1; a=rsa-sha256; s=arcselector10001; d=microsoft.com; cv=none; b=W0/uuU39lpRhoGnQEDhrm8zE8orUkKkjbvFlBiz9LMwBRyYnhNfdjqMeg/DjdMu6tKHA9f9MQinGyxJ72H4E8q/u8JbuMLezXu59sdeAQF3BeDslbrl7rrr9T1LO+759ja6h+HFFz4+UFm8/fKBfxhYm1EFVE3KMYPi/iuBEmI1C/rSrLXF+pidA19qcOH3qs9Y72wPVbbSWr30bcHqM5HUu0zSrTsvuIPsyFIfDEj0Faz2GGPQ+cSwZQix2hlzwUMJSB3QfCBPCb4uaAWAm5syHoqkIIkKnfIeoCvfNFOtM5SAbwLOXF0PvO3t4hFTpknZ5jLkJ6bSevUA/BQqvHA== ARC-Message-Signature: i=1; a=rsa-sha256; c=relaxed/relaxed; d=microsoft.com; s=arcselector10001; 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=y/jigiR+nh0potAum7k/O0P/eZHARAO7GuEl0jbitnU=; b=AtPCb2UBQTCjp7fJMX8gjHjsW+Vle8+oRsVU/KR81M5JnJFfDvi2hCi3aH1X5aGS1tC8lQhSroumKRAK6cAy9Duobm+Mf+Si+jl64dllkIx8iCzNy7VF9r8z0b5kZqhvIumlDVsu1UCbFiUQqX16YS8rDsyN++vz0FFzF6BJmhcJPTL7NkPJkon10yF/cPKsbqcF7BWBUq6QEz+RvXZp+qPmvWt+gZbDbV7DGPtmfaZq9RhM43wkn2PgDaaX6F1gyZwBuyXx6QJ4mSNfMW1aPCRRIs/+mrxXZxmm98YjQjVXMZ0LqFV1wdvmQqwmVsMaYTOqGOOKPeJmmbkhN40ZUA== ARC-Authentication-Results: i=1; mx.microsoft.com 1; spf=pass smtp.mailfrom=arm.com; dmarc=pass action=none header.from=arm.com; dkim=pass header.d=arm.com; arc=none DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=arm.com; s=selector1; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-SenderADCheck; bh=y/jigiR+nh0potAum7k/O0P/eZHARAO7GuEl0jbitnU=; b=QP4PGSrSHEv20Jbsk6otUvZ9V+xW+JhfEIdOUnq7ab99pNW97JwQBSgp1xTVDxt5kcOB9tmmAPSct9Naos8SMcWvSh2kVKYvcIeUYbRl/l9i0Keza1geisTOzl4a1O2HEyBxoZbvqIpu8UyRbfn7OXv/JFabuCH050HJJ3qf4do= Authentication-Results-Original: dkim=none (message not signed) header.d=none;dmarc=none action=none header.from=arm.com; Received: from DU0PR08MB8255.eurprd08.prod.outlook.com (2603:10a6:10:411::9) by AS8PR08MB9527.eurprd08.prod.outlook.com (2603:10a6:20b:61d::7) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.8026.8; Fri, 4 Oct 2024 17:52:13 +0000 Received: from DU0PR08MB8255.eurprd08.prod.outlook.com ([fe80::cbc8:c020:6a1b:d27a]) by DU0PR08MB8255.eurprd08.prod.outlook.com ([fe80::cbc8:c020:6a1b:d27a%5]) with mapi id 15.20.8026.017; Fri, 4 Oct 2024 17:52:13 +0000 Date: Fri, 4 Oct 2024 18:52:11 +0100 From: Andrew Carlotti To: gcc-patches@gcc.gnu.org Cc: Richard Sandiford Subject: [PATCH 2/8] aarch64: Add new +fcma flag Message-ID: <315e352d-c384-d69a-dc2a-b0dcb8788c7c@e124511.cambridge.arm.com> References: Content-Disposition: inline In-Reply-To: X-ClientProxiedBy: LO4P123CA0306.GBRP123.PROD.OUTLOOK.COM (2603:10a6:600:196::23) To DU0PR08MB8255.eurprd08.prod.outlook.com (2603:10a6:10:411::9) MIME-Version: 1.0 X-MS-TrafficTypeDiagnostic: DU0PR08MB8255:EE_|AS8PR08MB9527:EE_|DB1PEPF000509F3:EE_|AS8PR08MB9866:EE_ X-MS-Office365-Filtering-Correlation-Id: 5bc17ad3-e085-4b29-88a7-08dce49d4c06 x-checkrecipientrouted: true NoDisclaimer: true X-MS-Exchange-SenderADCheck: 1 X-MS-Exchange-AntiSpam-Relay: 0 X-Microsoft-Antispam-Untrusted: BCL:0;ARA:13230040|366016|376014|1800799024; X-Microsoft-Antispam-Message-Info-Original: u8K2S3i+yzlj7l95bm+KDEWFPZen1oWpsdb4eUCitLJVncngA98pMOyoaPp92UVsAVNKZX1sO79LM+jiBrwm8OfQG02QBWbUQxQqZim6lEsg585GaUNopMikfYxgVR3TUr06N2h1TlNgZGFT2KyElkvPXPtu/UrxiDRmPhyNYMO4C5qoorRbcrvKzi7SlnE3wF3EbzbS1nqMIR0aY91/V1bv+Kgb3gAn9uGnC+Y32NAvJLGOGWFhHpAWb72lSVEbj3gMm62aSKdN7F5+bKX+QBt9r3oOH+IQMqCSsi7DjgyWDnJ4IlpXzg+Zs1krlfOCvCeTTeRh4KHQ0UTL3SnZe1QcHGv43Kvj+nRmemhCVV24C4H1RP+Pt6LgWgyJbi65M0+g3AoGhkZQqORqqgUUcscqVfE2srhGwCtLq7SzlF7Ttm8qA20qoUUHiQ3E2dinOTt2LiZxiznv4Z+cxp/5QR27FklGul3zcc2sNkOpeka7lnL65Ncqniq9EBtl0MrkvotjZfKafARFPo20OD9KWtdtvIL/CDqnULujJDPIkj0NRqaxsXMSlgwnVRGpIULkHnQWYbkxurxb9Ndmt1LSdqKTVJOj6uw8flZ5006tN+6WieS+6tsti5fh82ISdcemuEV1tetXo910H/IahFV8CBW+D4bruZ7SmbIWtdAHOFC56jdx60qglKnSjt6QhkSOWDb2cBl4NNxxv7xIfaudHrFpVUvx8JOW6gxtx0L8tfoKBrSBFH5WXBXFdVHcS5cTotT66xG1qYW5AIqZ8tEIRhwRTI/daSfS6g4JOoHl7JuJZXunlVvEuLixHNI2CbEjneBzwbcOf3apoVBN/eTgarQYQ2NgXD8itiIs4CXN8nM3rw/D6hmSHAj2dZBDRR5Nr6AmAKG0GUnSWw+AS584ee2PsgULToi7kGBRXiU9l1yhzV+pHazraeZjP0fObyms3wmTzddys9903W0Qyqhj6l/YttVtlWf5ejaWFjFx9OYqB/8zKFPjGbaYa9hj2hQhviVEcjPqo7dLlCcndgZIK3t+kv6ak84lcueEG7M8nxhbPdECcFGpC5kgTblSVFxCGUygH4JYLuDEZsNv4Vn6YEyOh8GZVs2oprSK0+4aNbv/k6++TxQbYKvtlHUkiF6P9rr6JVE5qBAGQACS3kQaxqGJro2cmEkxYKD/6Q+Fyy3my/P73GStqJ7pfk0r6flamyT97o5LMfZWRz8zmio010G5SOxXSpRRHvcvBIdj2KI= X-Forefront-Antispam-Report-Untrusted: CIP:255.255.255.255; CTRY:; LANG:en; SCL:1; SRV:; IPV:NLI; SFV:NSPM; H:DU0PR08MB8255.eurprd08.prod.outlook.com; PTR:; CAT:NONE; SFS:(13230040)(366016)(376014)(1800799024); DIR:OUT; SFP:1101; X-MS-Exchange-Transport-CrossTenantHeadersStamped: AS8PR08MB9527 Original-Authentication-Results: dkim=none (message not signed) header.d=none;dmarc=none action=none header.from=arm.com; X-EOPAttributedMessage: 0 X-MS-Exchange-SkipListedInternetSender: ip=[2603:10a6:10:411::9]; domain=DU0PR08MB8255.eurprd08.prod.outlook.com X-MS-Exchange-Transport-CrossTenantHeadersStripped: DB1PEPF000509F3.eurprd02.prod.outlook.com X-MS-PublicTrafficType: Email X-MS-Office365-Filtering-Correlation-Id-Prvs: 9bb14d85-5d33-4cd6-7a6c-08dce49d46e3 X-Microsoft-Antispam: BCL:0; ARA:13230040|82310400026|35042699022|36860700013|376014|1800799024; X-Microsoft-Antispam-Message-Info: xtl6dm06AMMyivNXy+zgaVadGRFLuwBjUQAUYT/PuLlm5eR1+lwISBASuTRBavELMTMVZiXXRrax7evUqD5scur95hmOoROrTt+HRZXQsbJSpq6B3gCv/hOg+t0SFuWU4eewA3Ry/rKCvJmItZLA0SmjhUxR8f65PaHF9Hpiyu1NZsM8BXiUnHm9UonVkVUOaBK2V6fk0n2K+01B+lGOv4DJvb+FTtfC9ffcQxkwxjIxbqQ9t0ryPWKdmbyRSULvvqZegg//2vfpS1nApiIxsTQ7pVUHTKzxDn/LuxBlu1Pz9yQQFNfqKE1usHMin2mFNAgAf1ABdABh28VDkUxCwLUq/oTkZFrFOSWKYEgzCaF3hyN+jxHEPnc4U9BZ0j+rYMz4ZIZgawnztTdhMyuJmwDCdWaCcx1FwqG+MKlS2hD6o4VGewUyj3pMioyhsWifLITrnH4vN9d9mNeTZDL/TglpEZeNJoYsMEb0MhUjMVknda9kAoP+gU3L+wyWxsHbARG/HUSkTYQpQp6zwKocMf2djsikzB5hAURIvMyDbPyRIZK57NRJF+gA6NP5cjMeI80fVlOWPYMRl5yxrKLJQYe+E0uehkWWqdm9e8p+Pg+QQirCpsVeXlUaQ2ldEDWZPH9YAxNS9XVyX68qcw1jmnAmpJRrYQhTkGXZQBxRkDKZnLyi5cqGPK0nQw+deEZlOlMK5hRWTYD8vFzXQDRjmOdo6cIxC066zz3lmec8pOKmvSOhkP8t4cZX7jZ4fwvESPC0M3ZDOyBLlqrX6UG4Mpw8MOPG/N52438RYLKt/EfErGg++0hyHiPsfBKRuoewwWzTSFTP120MWhyKOv7U/YJ4EM7g7rNI0Mb08dLuSXJtbs1th/sj895CPfjqIbikiRcyOhma3Fz1qFSxRIvQ364eNmvoFSYamSmIZ+4uB/HxBBIJCzNlZZYgI2DyxxfGzs68JtzI/ScXvIZ6hrDM9D4d5YxmBw6Yq1EHX5JmFH5DM+Rootj6ZQMGXXDnl16MEC4rTUW3VKHAiY3wRI54KhAkmX8EJDEA0zlwtWvRuhqgBYwhOXAiUbfTPVnv0C20Al8CWYN5lb6mHg+GsBLMhh8nLQshnK0H5ydm3i1lXwx8Rg9kOYC+bVHoKSx8sA800eQ32G5+pdGo5J6PbcPntX4iPoLvDXR8B7qrJ72OC+qI2bPpOkOY1LuRoIwzX9hwWAQxXnUqivomKrPHLThUBj7dwQsUySLyPMqIHBByswo1JRmJJZ/AlFITmxI221FxzxlPodlKCnkmCa2YspWX7bj/HHVFAhU4qWhI7jcLgO3osdxHqJIpNwkFYydbG7PFkXJpne63G61STzLZn9EASg== 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:(13230040)(82310400026)(35042699022)(36860700013)(376014)(1800799024); DIR:OUT; SFP:1101; X-OriginatorOrg: arm.com X-MS-Exchange-CrossTenant-OriginalArrivalTime: 04 Oct 2024 17:52:21.5950 (UTC) X-MS-Exchange-CrossTenant-Network-Message-Id: 5bc17ad3-e085-4b29-88a7-08dce49d4c06 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: DB1PEPF000509F3.eurprd02.prod.outlook.com X-MS-Exchange-CrossTenant-AuthAs: Anonymous X-MS-Exchange-CrossTenant-FromEntityHeader: HybridOnPrem X-MS-Exchange-Transport-CrossTenantHeadersStamped: AS8PR08MB9866 X-Spam-Status: No, score=-12.6 required=5.0 tests=BAYES_00, DKIM_SIGNED, DKIM_VALID, DKIM_VALID_AU, DKIM_VALID_EF, GIT_PATCH_0, KAM_LOTSOFHASH, KAM_SHORT, SPF_HELO_NONE, SPF_NONE, TXREP, 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 This includes +fcma as a dependency of +sve, and means that we can finally support fcma intrinsics on a64fx. Also add fcma to the Features list in several cpunative testcases that incorrectly included sve without fcma. gcc/ChangeLog: * config/aarch64/aarch64-arches.def (V8_3A): Add FCMA. * config/aarch64/aarch64-option-extensions.def (FCMA): New flag. (SVE): Add FCMA dependency. * config/aarch64/aarch64.h (TARGET_COMPLEX): Use new flag. * config/aarch64/arm_neon.h: Use new flag for fcma intrinsics. gcc/testsuite/ChangeLog: * gcc.target/aarch64/cpunative/info_15: Add fcma to Features. * gcc.target/aarch64/cpunative/info_16: Ditto. * gcc.target/aarch64/cpunative/info_17: Ditto. * gcc.target/aarch64/cpunative/info_8: Ditto. * gcc.target/aarch64/cpunative/info_9: Ditto. diff --git a/gcc/config/aarch64/aarch64-arches.def b/gcc/config/aarch64/aarch64-arches.def index 4634b272e28006b5c6c2d6705a2f1010cbd9ab9b..fadf9c36b03865a3af9b25888a50f5bf3abe37b7 100644 --- a/gcc/config/aarch64/aarch64-arches.def +++ b/gcc/config/aarch64/aarch64-arches.def @@ -33,7 +33,7 @@ AARCH64_ARCH("armv8-a", generic_armv8_a, V8A, 8, (SIMD)) AARCH64_ARCH("armv8.1-a", generic_armv8_a, V8_1A, 8, (V8A, LSE, CRC, RDMA)) AARCH64_ARCH("armv8.2-a", generic_armv8_a, V8_2A, 8, (V8_1A)) -AARCH64_ARCH("armv8.3-a", generic_armv8_a, V8_3A, 8, (V8_2A, PAUTH, RCPC)) +AARCH64_ARCH("armv8.3-a", generic_armv8_a, V8_3A, 8, (V8_2A, PAUTH, RCPC, FCMA)) AARCH64_ARCH("armv8.4-a", generic_armv8_a, V8_4A, 8, (V8_3A, F16FML, DOTPROD, FLAGM)) AARCH64_ARCH("armv8.5-a", generic_armv8_a, V8_5A, 8, (V8_4A, SB, SSBS, PREDRES)) AARCH64_ARCH("armv8.6-a", generic_armv8_a, V8_6A, 8, (V8_5A, I8MM, BF16)) diff --git a/gcc/config/aarch64/aarch64-option-extensions.def b/gcc/config/aarch64/aarch64-option-extensions.def index 8279f5a76eae7d787b8126044c5b4b4b78e97324..12640ed970d0475b9e28f1c4f1c6295e88e1ab97 100644 --- a/gcc/config/aarch64/aarch64-option-extensions.def +++ b/gcc/config/aarch64/aarch64-option-extensions.def @@ -151,6 +151,8 @@ AARCH64_OPT_EXTENSION("fp16fml", F16FML, (), (F16), (), "asimdfhm") AARCH64_FMV_FEATURE("fp16fml", FP16FML, (F16FML)) +AARCH64_OPT_FMV_EXTENSION("fcma", FCMA, (SIMD), (), (), "fcma") + AARCH64_OPT_FMV_EXTENSION("rcpc", RCPC, (), (), (), "lrcpc") AARCH64_OPT_FMV_EXTENSION("rcpc3", RCPC3, (RCPC), (), (), "lrcpc3") @@ -163,7 +165,7 @@ AARCH64_OPT_FMV_EXTENSION("bf16", BF16, (FP), (SIMD), (), "bf16") AARCH64_FMV_FEATURE("rpres", RPRES, ()) -AARCH64_OPT_FMV_EXTENSION("sve", SVE, (SIMD, F16), (), (), "sve") +AARCH64_OPT_FMV_EXTENSION("sve", SVE, (SIMD, F16, FCMA), (), (), "sve") AARCH64_OPT_EXTENSION("f32mm", F32MM, (SVE), (), (), "f32mm") diff --git a/gcc/config/aarch64/aarch64.h b/gcc/config/aarch64/aarch64.h index 030cffb17606c1062af62398dd631bae50b448af..0c3d7baf7c85e54f7dd63fedb2da80d654c9ea50 100644 --- a/gcc/config/aarch64/aarch64.h +++ b/gcc/config/aarch64/aarch64.h @@ -364,7 +364,7 @@ constexpr auto AARCH64_FL_DEFAULT_ISA_MODE ATTRIBUTE_UNUSED #define TARGET_JSCVT (TARGET_FLOAT && TARGET_ARMV8_3) /* Armv8.3-a Complex number extension to AdvSIMD extensions. */ -#define TARGET_COMPLEX (TARGET_SIMD && TARGET_ARMV8_3) +#define TARGET_COMPLEX AARCH64_HAVE_ISA (FCMA) /* Floating-point rounding instructions from Armv8.5-a. */ #define TARGET_FRINT (AARCH64_HAVE_ISA (V8_5A) && TARGET_FLOAT) diff --git a/gcc/config/aarch64/arm_neon.h b/gcc/config/aarch64/arm_neon.h index e376685489da055029def6b661132b5154886b57..0ab511a884126821ecae7d2fc7c1a3427bdfe5ac 100644 --- a/gcc/config/aarch64/arm_neon.h +++ b/gcc/config/aarch64/arm_neon.h @@ -27015,7 +27015,7 @@ vbcaxq_s64 (int64x2_t __a, int64x2_t __b, int64x2_t __c) /* AdvSIMD Complex numbers intrinsics. */ #pragma GCC push_options -#pragma GCC target ("arch=armv8.3-a") +#pragma GCC target ("+nothing+fcma") #pragma GCC push_options #pragma GCC target ("+fp16") diff --git a/gcc/testsuite/gcc.target/aarch64/cpunative/info_15 b/gcc/testsuite/gcc.target/aarch64/cpunative/info_15 index 6b425ea201351247c7273718d9e1e52cae62b342..1a31a75d6b4842846ad6d9476df23aae5ef72f83 100644 --- a/gcc/testsuite/gcc.target/aarch64/cpunative/info_15 +++ b/gcc/testsuite/gcc.target/aarch64/cpunative/info_15 @@ -1,6 +1,6 @@ processor : 0 BogoMIPS : 100.00 -Features : Lorem ipsum dolor sit ametd rebum expetendis per at Dolor lucilius referrentur ei mei virtute eruditi eum ne Iisque verter svesm4 asimd fp sve sve2 fphp asimdhp sm3 sm4 +Features : Lorem ipsum dolor sit ametd rebum expetendis per at Dolor lucilius referrentur ei mei virtute eruditi eum ne Iisque verter svesm4 asimd fp sve sve2 fphp asimdhp sm3 sm4 fcma CPU implementer : 0x41 CPU architecture: 8 CPU variant : 0x0 diff --git a/gcc/testsuite/gcc.target/aarch64/cpunative/info_16 b/gcc/testsuite/gcc.target/aarch64/cpunative/info_16 index 26f01c4962489ab116450dd55717e4db345fdaee..cdff314be73842b434fe39ecaf5bddbb778320ce 100644 --- a/gcc/testsuite/gcc.target/aarch64/cpunative/info_16 +++ b/gcc/testsuite/gcc.target/aarch64/cpunative/info_16 @@ -1,6 +1,6 @@ processor : 0 BogoMIPS : 100.00 -Features : fp asimd evtstrm aes pmull sha1 sha2 crc32 asimddp sve sve2 fphp asimdhp +Features : fp asimd evtstrm aes pmull sha1 sha2 crc32 asimddp sve sve2 fphp asimdhp fcma CPU implementer : 0xfe CPU architecture: 8 CPU variant : 0x0 diff --git a/gcc/testsuite/gcc.target/aarch64/cpunative/info_17 b/gcc/testsuite/gcc.target/aarch64/cpunative/info_17 index 26f01c4962489ab116450dd55717e4db345fdaee..cdff314be73842b434fe39ecaf5bddbb778320ce 100644 --- a/gcc/testsuite/gcc.target/aarch64/cpunative/info_17 +++ b/gcc/testsuite/gcc.target/aarch64/cpunative/info_17 @@ -1,6 +1,6 @@ processor : 0 BogoMIPS : 100.00 -Features : fp asimd evtstrm aes pmull sha1 sha2 crc32 asimddp sve sve2 fphp asimdhp +Features : fp asimd evtstrm aes pmull sha1 sha2 crc32 asimddp sve sve2 fphp asimdhp fcma CPU implementer : 0xfe CPU architecture: 8 CPU variant : 0x0 diff --git a/gcc/testsuite/gcc.target/aarch64/cpunative/info_8 b/gcc/testsuite/gcc.target/aarch64/cpunative/info_8 index 76da16c57b545c0cf72bf96e8a56f502ecc55073..37a488946b16c5fd05434a36d58b0af4d7221c04 100644 --- a/gcc/testsuite/gcc.target/aarch64/cpunative/info_8 +++ b/gcc/testsuite/gcc.target/aarch64/cpunative/info_8 @@ -1,6 +1,6 @@ processor : 0 BogoMIPS : 100.00 -Features : asimd sve fp fphp asimdhp +Features : asimd sve fp fphp asimdhp fcma CPU implementer : 0x41 CPU architecture: 8 CPU variant : 0x0 diff --git a/gcc/testsuite/gcc.target/aarch64/cpunative/info_9 b/gcc/testsuite/gcc.target/aarch64/cpunative/info_9 index 14703dd1d0bf0c6543484d34950dc91778483b67..171ba498feabbb5ea2d392bc8ad0b11f156895ed 100644 --- a/gcc/testsuite/gcc.target/aarch64/cpunative/info_9 +++ b/gcc/testsuite/gcc.target/aarch64/cpunative/info_9 @@ -1,6 +1,6 @@ processor : 0 BogoMIPS : 100.00 -Features : asimd fp svesm4 sve sve2 fphp asimdhp sm3 sm4 +Features : asimd fp svesm4 sve sve2 fphp asimdhp sm3 sm4 fcma CPU implementer : 0x41 CPU architecture: 8 CPU variant : 0x0 From patchwork Fri Oct 4 17:53:03 2024 Content-Type: text/plain; charset="utf-8" MIME-Version: 1.0 Content-Transfer-Encoding: 7bit X-Patchwork-Submitter: Andrew Carlotti X-Patchwork-Id: 1992941 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=arm.com header.i=@arm.com header.a=rsa-sha256 header.s=selector1 header.b=QrhzdgYa; dkim=pass (1024-bit key) header.d=arm.com header.i=@arm.com header.a=rsa-sha256 header.s=selector1 header.b=QrhzdgYa; 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 4XKx493KnKz1xtH for ; Sat, 5 Oct 2024 03:53:45 +1000 (AEST) Received: from server2.sourceware.org (localhost [IPv6:::1]) by sourceware.org (Postfix) with ESMTP id 6664B385EC24 for ; Fri, 4 Oct 2024 17:53:43 +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-db8eur05on20600.outbound.protection.outlook.com [IPv6:2a01:111:f403:2614::600]) by sourceware.org (Postfix) with ESMTPS id 2E44E385DDF7 for ; Fri, 4 Oct 2024 17:53:19 +0000 (GMT) DMARC-Filter: OpenDMARC Filter v1.4.2 sourceware.org 2E44E385DDF7 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 2E44E385DDF7 Authentication-Results: server2.sourceware.org; arc=pass smtp.remote-ip=2a01:111:f403:2614::600 ARC-Seal: i=3; a=rsa-sha256; d=sourceware.org; s=key; t=1728064401; cv=pass; b=AC0KQ6g2mVvYnsE46z2oN6mlhWTKof1jAXd9beh/VVIJY0IrlOwSpDatOdaVo+Pn+kD16nvKF60zoFwyxNiES6cNvvKrm4n3xhM2DiCjU5nObwjk22TK4Sh8fcqpCa4xDZ2AQsALedyskoB0Fo95yCY2LYtVFiRRxCxoDsqNS8k= ARC-Message-Signature: i=3; a=rsa-sha256; d=sourceware.org; s=key; t=1728064401; c=relaxed/simple; bh=on7sRl/31v71Fd+81F46N0zJKtbf3OFMWmvY9OlmHtk=; h=DKIM-Signature:DKIM-Signature:Date:From:To:Subject:Message-ID: MIME-Version; b=UjXe5WiwqH47Edy5jrlpG6Eas1lQJXaiLX8Rm+XqKP7bYw1V8D3vwy1if+3WOldoNvOtAxdrLPe1WBjBH0RtdQh4xLmndrNcaqEfaO1tHV1TuSqknelPSZxAfQOzc1yZfB21fP6wO00v4WyTZadve4+1YrK2mI3zkBLSW9hBWYo= ARC-Authentication-Results: i=3; server2.sourceware.org ARC-Seal: i=2; a=rsa-sha256; s=arcselector10001; d=microsoft.com; cv=pass; b=NdYBqs9RYJyK73k2+Hc2Yomlv+5aAazwsU7ptqTmFyIVIoTkcBFskQ2w8kD8+axo7VytPMNH5LXbh+1RyiWJVZoktkKzZllrtvZboQvWOfXZ/zKWv188XqUQtYg9HEW6ve05kncOfUPIDAJ2GwRST9vrxuuoQ+hexvJYOzTkd1Pgkhbq/Z9nhOQ2U5wN05kP77blIovVM5JVgsunGmiGxFvn5zmrFbySCrYBUARsklcjp4Pz6l/oyUYcIY4PwzSwMLxjkYUL+9qZasdcza6pKCjLJGqilCIu4qUJOz7MhYdkfApUAo/StwlI4mSQuYEoZC7mRsige9ByOkqYgnbX2w== ARC-Message-Signature: i=2; a=rsa-sha256; c=relaxed/relaxed; d=microsoft.com; s=arcselector10001; 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=UiDSPIY96fHITu+zplSiDwMxjpp2r3W3iTOyKDoidYI=; b=ex7lDIHMae/wdl/qsRVX7jgcpYRW+K6H15gDZHjn+1ErzxwqbM3tiDEYVQLEgEaiwtf1R8Blv9cOLshZKJXl1e10lmRBR5az9qO41/7Ogedz5VThLXh7zWzmejT3ZzkJxafxqEcVy//47C04pdScANovVKnXNvm3Znr4pAVEfSpWLrmbiRciJ508G/Jo7QNCjFFsV9qkaYt50Ekixn56e/vniscMrhYgmDP2RGH51BozrPydu7k11LU6fFv92wk4xe2DamAwdByxi0fHKK1gIkkGKY1lf2CZNlslADWWn0m0NoQfLQB88KExpjNgmVMlYkGft8j83Np5GqoOrNrt5g== 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=arm.com; arc=pass (0 oda=1 ltdi=1 spf=[1,1,smtp.mailfrom=arm.com] dkim=[1,1,header.d=arm.com] dmarc=[1,1,header.from=arm.com]) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=arm.com; s=selector1; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-SenderADCheck; bh=UiDSPIY96fHITu+zplSiDwMxjpp2r3W3iTOyKDoidYI=; b=QrhzdgYaZuHlY4C+ibrLcoixgPqc2YWExQY/omRgiCFfy8wdYK17Y4t3g9j9zB+GKZ+GirytVqwZeigKvvBdkXgIVrOTJf1y5xisv0qKdYMKWXDva5AQ/RBN4jOLTFc+19i8qqxhhVNv7X/junKQ3HAipinMsUp2xjwzz1Flzig= Received: from DB9PR02CA0021.eurprd02.prod.outlook.com (2603:10a6:10:1d9::26) by AM9PR08MB6177.eurprd08.prod.outlook.com (2603:10a6:20b:283::16) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.8026.15; Fri, 4 Oct 2024 17:53:15 +0000 Received: from DB5PEPF00014B9E.eurprd02.prod.outlook.com (2603:10a6:10:1d9:cafe::6) by DB9PR02CA0021.outlook.office365.com (2603:10a6:10:1d9::26) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.8026.18 via Frontend Transport; Fri, 4 Oct 2024 17:53:15 +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=arm.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 DB5PEPF00014B9E.mail.protection.outlook.com (10.167.8.171) with Microsoft SMTP Server (version=TLS1_3, cipher=TLS_AES_256_GCM_SHA384) id 15.20.8026.11 via Frontend Transport; Fri, 4 Oct 2024 17:53:14 +0000 Received: ("Tessian outbound 6c9d48238f96:v473"); Fri, 04 Oct 2024 17:53:14 +0000 X-CheckRecipientChecked: true X-CR-MTA-CID: 39ebf74d49e00b15 X-TessianGatewayMetadata: iRL3ru22CZLIgNDKU7mfo/gxeDzJy3B86z+DTIr/O83xT4d00jBRxfcUHhzxUpunemivNzoWqSk/Qk1hlLarZZcq7Clpv3S1rQrHnJFqtFxk5sqhHy2gxFXcLJmMyjAjYh1wOoCqDW829k8Bd56bS6JQoctLStrBETW/A7Tyl/Ent0e4mSttun3tBHxNjKLD X-CR-MTA-TID: 64aa7808 Received: from L0c2f9c08a07b.1 by 64aa7808-outbound-1.mta.getcheckrecipient.com id AA2587F1-754B-4551-810B-4B1D501BAE33.1; Fri, 04 Oct 2024 17:53:08 +0000 Received: from EUR02-VI1-obe.outbound.protection.outlook.com by 64aa7808-outbound-1.mta.getcheckrecipient.com with ESMTPS id L0c2f9c08a07b.1 (version=TLSv1.2 cipher=ECDHE-RSA-AES256-GCM-SHA384); Fri, 04 Oct 2024 17:53:08 +0000 ARC-Seal: i=1; a=rsa-sha256; s=arcselector10001; d=microsoft.com; cv=none; b=VYaXGmFS67vn0buGmCHnZ5irJt/Vey6e5PSH0dA831RaXEo+j84bvM/FvzItgfrQhcAW9gFlhtJCvoaCOQGBfBbi0Ij/i19Vz2iKB6HYiS31yop8qqtJsBG17m1JB6mFjNViazVi9rsLE+tanxwLByDxSSm/Hgetg7bTP2JeSTjLUohKu0jpWAJ8UhYRN8YHBdbzPD8wjpo2plq+IWI13phzAUqaJTEPoV8yomHyYXFJnJCr23Tae70EIGs24Qy7Yu16dD/6PmoggzBgCTI+Hrm00aLXdLQk2co9h7dWMcDqJcww2ltCZSVtrUuxFD+h2mNaIzGXRAnwU3E+9d3ddw== ARC-Message-Signature: i=1; a=rsa-sha256; c=relaxed/relaxed; d=microsoft.com; s=arcselector10001; 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=UiDSPIY96fHITu+zplSiDwMxjpp2r3W3iTOyKDoidYI=; b=orFMyFDlQpp62FiY++WdXnKoUKS/YmDUtPxIZtNhxmrBv5Y1uUKoF8ayaNx/Yi2R5jcqvphI4UFGnJZg1M9pbC5GBoDf4GjCwt0t1jgG5jWIEdOm717KRbeqziDLPuDovzAtHK+yKfdlbwt5V+CcQrE8/BrPsrEwgjScyoZxx6B7FFvyr6dEttS0S8Y2cMpL937OcO8uYjEouMHvEBgqrE1hF/IPicHoUH9o7cVNVaKc4vReRey7BlPVYpPLHk+wIvO1eSzNcO7umHwQ1r9IByE+3iEKdyOXH5hg2JnNhVFh0zByKErokKR/WQjJycPlhY3+TrI+4pvvmdVzhlT5Pw== ARC-Authentication-Results: i=1; mx.microsoft.com 1; spf=pass smtp.mailfrom=arm.com; dmarc=pass action=none header.from=arm.com; dkim=pass header.d=arm.com; arc=none DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=arm.com; s=selector1; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-SenderADCheck; bh=UiDSPIY96fHITu+zplSiDwMxjpp2r3W3iTOyKDoidYI=; b=QrhzdgYaZuHlY4C+ibrLcoixgPqc2YWExQY/omRgiCFfy8wdYK17Y4t3g9j9zB+GKZ+GirytVqwZeigKvvBdkXgIVrOTJf1y5xisv0qKdYMKWXDva5AQ/RBN4jOLTFc+19i8qqxhhVNv7X/junKQ3HAipinMsUp2xjwzz1Flzig= Authentication-Results-Original: dkim=none (message not signed) header.d=none;dmarc=none action=none header.from=arm.com; Received: from DU0PR08MB8255.eurprd08.prod.outlook.com (2603:10a6:10:411::9) by AS8PR08MB9527.eurprd08.prod.outlook.com (2603:10a6:20b:61d::7) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.8026.8; Fri, 4 Oct 2024 17:53:06 +0000 Received: from DU0PR08MB8255.eurprd08.prod.outlook.com ([fe80::cbc8:c020:6a1b:d27a]) by DU0PR08MB8255.eurprd08.prod.outlook.com ([fe80::cbc8:c020:6a1b:d27a%5]) with mapi id 15.20.8026.017; Fri, 4 Oct 2024 17:53:06 +0000 Date: Fri, 4 Oct 2024 18:53:03 +0100 From: Andrew Carlotti To: gcc-patches@gcc.gnu.org Cc: Richard Sandiford Subject: [PATCH 3/8] aarch64: Add new +jscvt flag Message-ID: References: Content-Disposition: inline In-Reply-To: X-ClientProxiedBy: LO4P123CA0292.GBRP123.PROD.OUTLOOK.COM (2603:10a6:600:196::9) To DU0PR08MB8255.eurprd08.prod.outlook.com (2603:10a6:10:411::9) MIME-Version: 1.0 X-MS-TrafficTypeDiagnostic: DU0PR08MB8255:EE_|AS8PR08MB9527:EE_|DB5PEPF00014B9E:EE_|AM9PR08MB6177:EE_ X-MS-Office365-Filtering-Correlation-Id: 19d53892-6129-4296-4d33-08dce49d6bd0 x-checkrecipientrouted: true NoDisclaimer: true X-MS-Exchange-SenderADCheck: 1 X-MS-Exchange-AntiSpam-Relay: 0 X-Microsoft-Antispam-Untrusted: BCL:0;ARA:13230040|366016|376014|1800799024; X-Microsoft-Antispam-Message-Info-Original: iFJr/iOb3BvEyRDEwWdk6r3NGhoT7DXUmk+w53sIjAjJJLcNxWM4j7EXu6PxSgn7dH0R4+TbclpW2iwxnQ1ttqPNY8QltKxes377kje1Alt5oPN8aumiEBeVZ5h2jci6oX3/uAlaBRZ5JiEEESp/WUocV30aA2ZtdQYGU2xpyz7276Jd1tMAL6seppoWvbBouTLjDA95fEYlgImtfdvsSiVnfmgQGu3uvCorS7/F6NONayOmsBiT1XAuV+ADKN2MfFl73V+MXTYbzf8VwpMSeJSmy3hBvmDcn3Pt9jMassWmhZVi7SCgH9uShYTZ0wx2ernV0OlnntNJvxHfuvgsd210TEyysUXf4EEIInyEbU8Hz8EXlLsFgCUjrAYAqu0TFPNjsSqMn8UiTM1q+ElOfEAHx8cnS0abavNlyXkB6wApHEiyPhU9mhn419JTv0tDEwH4pmTA0L4RuqaXX3bzkRYXLEOe5dkUTdMFwkmrGMw+51SCk7AZ1lcJKQnidIA7V2RKJMsdgPqOazb7ZGdyhgnvun54WP/ApzniHrnttUDUnRRn6RRFj2Zdu00K1bdHYzTbPiVlMbvTwRPtaHNXSrGJuacHZkvAS/Vqy99Eh1z6QPD4f9n5WjBxoZYAhIGkhRj1MJ4PuzP2XAyDRoTdSkhMj6hEMGSc+HzKcXpqZkNfmWAdaSiAA2s70sZzP3N631Y9M2hOPdy4y3oP6q6KliuiqveybGWkUMD0kfljulxlvGbH1uQetz5QYlgMgnUPAGyffeelsBophHifQ/MwTh7I8dcgIN34WZDlgjGPWGE6v4F58G0+XNDLS3N1glLUu/5V+8NR3HMVgb5zqNcf8WIE5GZMqVU0QuUd2gd1GIVDe/7uwXPb0ueN6G+ICd9zk+i7tulz9xXdljRTuxaysxe+4rr0YyvLa0kHzWVhBZpgjnJjMz1qdym71DJr8U13fFwxkvFvb68vNEN/FZ3XI/v9YDm2YCsUDAHlMKKK3PqJ2TaPLRpRGtv+eCe/2pzXXBpMk1jiubLYzCjbhEH6FN1jCa2lNZleNdEkej8Pn919YFocg9RbVvxDOL9MSJsexFanjVEbNcC6Cp4zKkqLMGJPweBo3ShiQbP+tllcYryK8FGVy/C8XEWEifBh/9AlDp4XLmCGhuJdZgy6BK+oBzeHAqOdmV51VEhv0ab3W7BK8GEHIMgX2mx2Y7M1YY2RTsionymqP37cxOMKvKQG/2aJs18AdPjMChBNvzvUYVo= X-Forefront-Antispam-Report-Untrusted: CIP:255.255.255.255; CTRY:; LANG:en; SCL:1; SRV:; IPV:NLI; SFV:NSPM; H:DU0PR08MB8255.eurprd08.prod.outlook.com; PTR:; CAT:NONE; SFS:(13230040)(366016)(376014)(1800799024); DIR:OUT; SFP:1101; X-MS-Exchange-Transport-CrossTenantHeadersStamped: AS8PR08MB9527 Original-Authentication-Results: dkim=none (message not signed) header.d=none;dmarc=none action=none header.from=arm.com; X-EOPAttributedMessage: 0 X-MS-Exchange-SkipListedInternetSender: ip=[2603:10a6:10:411::9]; domain=DU0PR08MB8255.eurprd08.prod.outlook.com X-MS-Exchange-Transport-CrossTenantHeadersStripped: DB5PEPF00014B9E.eurprd02.prod.outlook.com X-MS-PublicTrafficType: Email X-MS-Office365-Filtering-Correlation-Id-Prvs: befb597c-f0fb-4be5-fb50-08dce49d6673 X-Microsoft-Antispam: BCL:0; ARA:13230040|1800799024|35042699022|376014|36860700013|82310400026; X-Microsoft-Antispam-Message-Info: /7Df1JiEb2nywD7eSTCAZeeYb5TH26kygj5pkwTHFvVY9KUBwtOrzKDYlNXQQU6KvUx+RpHZLrp57v12ECFWKs5WU/ZYRiGiORfWqMBmi6FCejQlHtwHTs5EdBp0WVC8t7tzq4vRtdf4ueC1MXbcaIEmtYIgHETj8eJMlUDlycgMjb8rqlOyAOAr2ozYKi76ZMnZYQdM579iYAdxKjhtTan/JKI+S4HIJdPOSXiGJFUDBai9IZQs1TN0690Tytquj7cgVQ50dk9oBI3XtjNAB3KthNy/2aqakiPRREMDBeA9wfaUznOZ8Subw267zjQPPZgzVZlWWNZ6RQ/DLz4D9+nXB0awhS/YEAQTkwXo+DCL4RbUdORD01/CwuCIyMCLncrnryYOoXIYxodal57XY+GGvGehzRO/qbCNhUDKX+6aYd8VUnefYwPWtmmnUzFMh7V++ZqnSQl4se18vhhU2jfkZo+bQlDAUuaEXeJnyDGkM1nKJHTCkKDnLMxv0WvxWb/TIsub+Ok1G77c+DY9qJ871O8U/Km4AXLwbNehJRBktQits/VTEJZ+6LvxFeg4sIwzvj2d9pZbLFtf8xLxdA0CI8khtEP3zGvGVM0jQ7BbPr+qwZnsAOakGxBZGbtU4U35C/jP93uKHI1y+K6KLOfwKXdg6N1uQDOf7G970MSfwJjkXQA1GP/vHBBrTE1S8QmfOexrRvHuyeLhuB1KCB0f3npCdjkXyVzuQw+eXDAwngQ9swcYVF5pFIPPdH4xHrmgpuwULLtulNcMD4QZ9AUGPbYjftxDfg/Ho3BIb3ZtsVclr3e7vzZD23KaNAC9lTq4maYcLdBon5Y4KENttpvL9vTzAGopQLEclmhC1XS6BpPCXUZK5Ut/vaDOAuprJSguAuc1pnIAk7I60iNay/xENAfPOR4yDURE5phORQnz/8i3HSujDEIjkaZV+K9OzQOm6D+30DQkdmU5JS7FzzaqaP+6xBHbHVdUo8Sjok/H5tbJxEfo3A0tgMvv77XyuBVH/VQetuG4Um5HKdmEyu0jHc6u9UsT024pnaXHGX2zKPvWcjtb88Ze43Vl4vR0slGRUjj1moIi+kf6HU5G3p/NVCXzHPJYNPAPCB2VU5QBwl6xa9LJ4JKSHhfAJMOkjae2lhyFezdqFypEVigXgi8lQs68W3Wls1flIdttNfCgIGBz/x93xwXYcn/rAS+xm2lujXTSJi9LqkR+lF0EkUDL5ZucsF9vOODj+RHrjId27/9ub2luOOdoshnL7ljPMH/fiugs56CPhOG+VwZHx9aDyxh1xVYPDh4b6rz054gK342SMCLRSLIrBHz2ofEqi1S0DlClOYUqu9QTMo23xg== 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:(13230040)(1800799024)(35042699022)(376014)(36860700013)(82310400026); DIR:OUT; SFP:1101; X-OriginatorOrg: arm.com X-MS-Exchange-CrossTenant-OriginalArrivalTime: 04 Oct 2024 17:53:14.9423 (UTC) X-MS-Exchange-CrossTenant-Network-Message-Id: 19d53892-6129-4296-4d33-08dce49d6bd0 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: DB5PEPF00014B9E.eurprd02.prod.outlook.com X-MS-Exchange-CrossTenant-AuthAs: Anonymous X-MS-Exchange-CrossTenant-FromEntityHeader: HybridOnPrem X-MS-Exchange-Transport-CrossTenantHeadersStamped: AM9PR08MB6177 X-Spam-Status: No, score=-12.1 required=5.0 tests=BAYES_00, DKIM_SIGNED, DKIM_VALID, DKIM_VALID_AU, DKIM_VALID_EF, FORGED_SPF_HELO, GIT_PATCH_0, KAM_LOTSOFHASH, KAM_SHORT, SPF_HELO_PASS, SPF_NONE, TXREP, 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 gcc/ChangeLog: * config/aarch64/aarch64-arches.def (V8_3A): Add JSCVT. * config/aarch64/aarch64-option-extensions.def (JSCVT): New flag. * config/aarch64/aarch64.h (TARGET_JSCVT): Use new flag. * config/aarch64/arm_acle.h: Use new flag for jscvt intrinsics. gcc/testsuite/ChangeLog: * gcc.target/aarch64/cpunative/native_cpu_21.c: Add jscvt to expected feature string. * gcc.target/aarch64/cpunative/native_cpu_22.c: Ditto. diff --git a/gcc/config/aarch64/aarch64-arches.def b/gcc/config/aarch64/aarch64-arches.def index fadf9c36b03865a3af9b25888a50f5bf3abe37b7..c93c5c39d69ee497f1da3dd398b0353a3f99be8c 100644 --- a/gcc/config/aarch64/aarch64-arches.def +++ b/gcc/config/aarch64/aarch64-arches.def @@ -33,7 +33,7 @@ AARCH64_ARCH("armv8-a", generic_armv8_a, V8A, 8, (SIMD)) AARCH64_ARCH("armv8.1-a", generic_armv8_a, V8_1A, 8, (V8A, LSE, CRC, RDMA)) AARCH64_ARCH("armv8.2-a", generic_armv8_a, V8_2A, 8, (V8_1A)) -AARCH64_ARCH("armv8.3-a", generic_armv8_a, V8_3A, 8, (V8_2A, PAUTH, RCPC, FCMA)) +AARCH64_ARCH("armv8.3-a", generic_armv8_a, V8_3A, 8, (V8_2A, PAUTH, RCPC, FCMA, JSCVT)) AARCH64_ARCH("armv8.4-a", generic_armv8_a, V8_4A, 8, (V8_3A, F16FML, DOTPROD, FLAGM)) AARCH64_ARCH("armv8.5-a", generic_armv8_a, V8_5A, 8, (V8_4A, SB, SSBS, PREDRES)) AARCH64_ARCH("armv8.6-a", generic_armv8_a, V8_6A, 8, (V8_5A, I8MM, BF16)) diff --git a/gcc/config/aarch64/aarch64-option-extensions.def b/gcc/config/aarch64/aarch64-option-extensions.def index 12640ed970d0475b9e28f1c4f1c6295e88e1ab97..c3663998c55b9ce4113dcce57bdea5980073d73c 100644 --- a/gcc/config/aarch64/aarch64-option-extensions.def +++ b/gcc/config/aarch64/aarch64-option-extensions.def @@ -151,6 +151,8 @@ AARCH64_OPT_EXTENSION("fp16fml", F16FML, (), (F16), (), "asimdfhm") AARCH64_FMV_FEATURE("fp16fml", FP16FML, (F16FML)) +AARCH64_OPT_FMV_EXTENSION("jscvt", JSCVT, (FP), (), (), "jscvt") + AARCH64_OPT_FMV_EXTENSION("fcma", FCMA, (SIMD), (), (), "fcma") AARCH64_OPT_FMV_EXTENSION("rcpc", RCPC, (), (), (), "lrcpc") diff --git a/gcc/config/aarch64/aarch64.h b/gcc/config/aarch64/aarch64.h index 0c3d7baf7c85e54f7dd63fedb2da80d654c9ea50..864f2d438479a74c9ada80577b37b2aa86085d02 100644 --- a/gcc/config/aarch64/aarch64.h +++ b/gcc/config/aarch64/aarch64.h @@ -361,7 +361,7 @@ constexpr auto AARCH64_FL_DEFAULT_ISA_MODE ATTRIBUTE_UNUSED #define TARGET_ARMV8_3 AARCH64_HAVE_ISA (V8_3A) /* Javascript conversion instruction from Armv8.3-a. */ -#define TARGET_JSCVT (TARGET_FLOAT && TARGET_ARMV8_3) +#define TARGET_JSCVT AARCH64_HAVE_ISA (JSCVT) /* Armv8.3-a Complex number extension to AdvSIMD extensions. */ #define TARGET_COMPLEX AARCH64_HAVE_ISA (FCMA) diff --git a/gcc/config/aarch64/arm_acle.h b/gcc/config/aarch64/arm_acle.h index ab4e7e60e046a9e9c81237de2ca5463c3d4f96ca..0f06bde6c50261208d03985b6614d1983b535efb 100644 --- a/gcc/config/aarch64/arm_acle.h +++ b/gcc/config/aarch64/arm_acle.h @@ -119,7 +119,7 @@ __revl (unsigned long __value) } #pragma GCC push_options -#pragma GCC target ("arch=armv8.3-a") +#pragma GCC target ("+nothing+jscvt") __extension__ extern __inline int32_t __attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) __jcvt (double __a) diff --git a/gcc/testsuite/gcc.target/aarch64/cpunative/native_cpu_21.c b/gcc/testsuite/gcc.target/aarch64/cpunative/native_cpu_21.c index 1d90e9ec9d971ae0f085fd832099058488c817b8..603ee48d584b8085755b577e09a6e7d6abbb5623 100644 --- a/gcc/testsuite/gcc.target/aarch64/cpunative/native_cpu_21.c +++ b/gcc/testsuite/gcc.target/aarch64/cpunative/native_cpu_21.c @@ -7,7 +7,7 @@ int main() return 0; } -/* { dg-final { scan-assembler {\.arch armv8-a\+flagm\+lse\+dotprod\+rdma\+crc\+fp16fml\+rcpc\+i8mm\+bf16\+sve2-aes\+sve2-bitperm\+sve2-sha3\+sve2-sm4\+sb\+ssbs\n} } } */ +/* { dg-final { scan-assembler {\.arch armv8-a\+flagm\+lse\+dotprod\+rdma\+crc\+fp16fml\+jscvt\+rcpc\+i8mm\+bf16\+sve2-aes\+sve2-bitperm\+sve2-sha3\+sve2-sm4\+sb\+ssbs\n} } } */ /* Check that an Armv8-A core doesn't fall apart on extensions without midr values. */ diff --git a/gcc/testsuite/gcc.target/aarch64/cpunative/native_cpu_22.c b/gcc/testsuite/gcc.target/aarch64/cpunative/native_cpu_22.c index 17050a0b72c98ecfd87ec5f7f522cce4db9efc16..e0ba97fb6e9a2969b8122ca0315ef73f16983045 100644 --- a/gcc/testsuite/gcc.target/aarch64/cpunative/native_cpu_22.c +++ b/gcc/testsuite/gcc.target/aarch64/cpunative/native_cpu_22.c @@ -7,7 +7,7 @@ int main() return 0; } -/* { dg-final { scan-assembler {\.arch armv8-a\+flagm\+lse\+dotprod\+rdma\+crc\+fp16fml\+rcpc\+i8mm\+bf16\+sve2-aes\+sve2-bitperm\+sve2-sha3\+sve2-sm4\+sb\+ssbs\+pauth\n} } } */ +/* { dg-final { scan-assembler {\.arch armv8-a\+flagm\+lse\+dotprod\+rdma\+crc\+fp16fml\+jscvt\+rcpc\+i8mm\+bf16\+sve2-aes\+sve2-bitperm\+sve2-sha3\+sve2-sm4\+sb\+ssbs\+pauth\n} } } */ /* Check that an Armv8-A core doesn't fall apart on extensions without midr values and that it enables optional features. */ From patchwork Fri Oct 4 17:53:22 2024 Content-Type: text/plain; charset="utf-8" MIME-Version: 1.0 Content-Transfer-Encoding: 7bit X-Patchwork-Submitter: Andrew Carlotti X-Patchwork-Id: 1992942 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=arm.com header.i=@arm.com header.a=rsa-sha256 header.s=selector1 header.b=h6sKLR81; dkim=pass (1024-bit key) header.d=arm.com header.i=@arm.com header.a=rsa-sha256 header.s=selector1 header.b=h6sKLR81; 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 4XKx4T5x9pz1xtH for ; Sat, 5 Oct 2024 03:54:01 +1000 (AEST) Received: from server2.sourceware.org (localhost [IPv6:::1]) by sourceware.org (Postfix) with ESMTP id E4A18385E003 for ; Fri, 4 Oct 2024 17:53:59 +0000 (GMT) X-Original-To: gcc-patches@gcc.gnu.org Delivered-To: gcc-patches@gcc.gnu.org Received: from EUR05-VI1-obe.outbound.protection.outlook.com (mail-vi1eur05on20621.outbound.protection.outlook.com [IPv6:2a01:111:f403:2613::621]) by sourceware.org (Postfix) with ESMTPS id A59B1385C6E3 for ; Fri, 4 Oct 2024 17:53:37 +0000 (GMT) DMARC-Filter: OpenDMARC Filter v1.4.2 sourceware.org A59B1385C6E3 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 A59B1385C6E3 Authentication-Results: server2.sourceware.org; arc=pass smtp.remote-ip=2a01:111:f403:2613::621 ARC-Seal: i=3; a=rsa-sha256; d=sourceware.org; s=key; t=1728064420; cv=pass; b=LgXgr+2v614hU9LAymVVaznnhu+AfVN9ArBqXUEsOXoPuNf3wNetPOrERrcpaUQkTi99KXnkCjd3MLiliYcRLsXuJZpuk3qPrhAhQYr9RVIayX0AeecE088BGb0TsXsI76eFL9tPAyBTmmcjUTOocEoQDLV7HOnBtB/uT0t2XPg= ARC-Message-Signature: i=3; a=rsa-sha256; d=sourceware.org; s=key; t=1728064420; c=relaxed/simple; bh=fJ7YQZUxA8dY2FUYvPSvY3oD0wWOpYFRfVOqFYknl14=; h=DKIM-Signature:DKIM-Signature:Date:From:To:Subject:Message-ID: MIME-Version; b=kXMSLbZ9z4DLumrA3yyrRLERmlhVsT+dLx96VPNC9avfFaixueri1EwhC2W93nbnbMpxN2gC9Uf7UcUuCQW5GNGgVSaKYUkGq1jX85zZg2IxnOt2bBbrbxwTbdGTQPKxS7VUYlzX9o0U/u0nfZ5Olhd31fuGfJcfGA7K5sX3BqA= ARC-Authentication-Results: i=3; server2.sourceware.org ARC-Seal: i=2; a=rsa-sha256; s=arcselector10001; d=microsoft.com; cv=pass; b=U922i2ij20wrqxUWi2GwaX2aQ/yw+2LYj42NfMZMf2Qyp2YyRB5Ujwx3ImDNamgAkBMr16ai6Rt37k5uM2rj+d4UuBFV4lcKOlweqiFLLNoaCPKpRBH0CIMNJYyQ02fx6FDb6ZpO8t7auabqyuPzymxKFRLJ/+RikErVxC169cjRF7I1L57uT4FNDTyzXZHpU7oQfuJ4DBeMYM/q2Ejp7r0Y+jtnaNLNv4E/KBzpmBuwKG6RDmWXFbCBDjLlyQkbuo4xCR6tYTesuZjY9CQDIXfDiykgLUKmLKExNXMzlNaINI6j+8uGqYJbPkq91Fiog8vGYgyvoC1OsVbXh9TL2Q== ARC-Message-Signature: i=2; a=rsa-sha256; c=relaxed/relaxed; d=microsoft.com; s=arcselector10001; 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=4lu2fo+4YVsF39RMw2GsnoUxx7EE3PlBEQ/RVG8xRZc=; b=dImItAP4Wk8ogfAkWHbj1/W5l1+XiIzU7rlqG/ZVa9YDSuDewAjey7pwVpZUbjOf6/wf0P70lay/mFzMk+BpBLZldmmr5vrIK0u8gly5wuX8ro5O6lwle7aAMszKyjA0GiJgtCAAxBhQX0LPJEyF3j4MAYNI+ubFpoeOPwLIAve4clXfvJp1y/oFZA611aO5rEnuEG++WHqMc83WJdl1wUaiETFS4+BdSxcx4Lm0hLWirxoJweTJuHdxm74W6SK7RHyRx+Me0gRZBA/9SDzYeAlOWza2zj8rO7nCbepRkL2+XiDcrOcTe19g+wNskQFcu7sLc9Bn/Y/RSP1t2x4ghQ== 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=arm.com; arc=pass (0 oda=1 ltdi=1 spf=[1,1,smtp.mailfrom=arm.com] dkim=[1,1,header.d=arm.com] dmarc=[1,1,header.from=arm.com]) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=arm.com; s=selector1; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-SenderADCheck; bh=4lu2fo+4YVsF39RMw2GsnoUxx7EE3PlBEQ/RVG8xRZc=; b=h6sKLR81o11tUDmSVKL+Ri168WwI27Kz8aj3ufhEVfSQoWp9SPhSxbOsHQnXQUMa8+eiwDbqVV5wrT2VsDm2sJe7n23wyidcKSMcel7Pf3NHa1Tu2uTOrO9e83SCSilp9HqCIualyLBhp1Uwojuhbj8Ojj4LDqqqm9wQ+GJiO9U= Received: from DUZPR01CA0253.eurprd01.prod.exchangelabs.com (2603:10a6:10:4b5::7) by AM8PR08MB6371.eurprd08.prod.outlook.com (2603:10a6:20b:363::22) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.8026.18; Fri, 4 Oct 2024 17:53:33 +0000 Received: from DB1PEPF00039234.eurprd03.prod.outlook.com (2603:10a6:10:4b5:cafe::3e) by DUZPR01CA0253.outlook.office365.com (2603:10a6:10:4b5::7) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.8026.18 via Frontend Transport; Fri, 4 Oct 2024 17:53:33 +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=arm.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 DB1PEPF00039234.mail.protection.outlook.com (10.167.8.107) with Microsoft SMTP Server (version=TLS1_3, cipher=TLS_AES_256_GCM_SHA384) id 15.20.8026.11 via Frontend Transport; Fri, 4 Oct 2024 17:53:33 +0000 Received: ("Tessian outbound 10d5cea79515:v473"); Fri, 04 Oct 2024 17:53:32 +0000 X-CheckRecipientChecked: true X-CR-MTA-CID: 1161084415e436dc X-TessianGatewayMetadata: AuqTccsGhPxggbTZwXLbb7unTe1iD69QqyhKkHXAZLUTL/ARZ/j6sv7g3dxJnNeKsvIwV+CBtCnD/NDqJJc9+45ovM6sRTdy3O6pQvixQX2w+5A4uWpB6S21i8oq77iGyd+IvxpEsm6F8Jgg7T4R1bfrUfUIPYJq8a26FfaKC6xKHIunhQRWVmOS4X/sO6Th X-CR-MTA-TID: 64aa7808 Received: from L60af32676802.2 by 64aa7808-outbound-1.mta.getcheckrecipient.com id 557C4593-425F-477A-A21B-A50875C841DE.1; Fri, 04 Oct 2024 17:53:26 +0000 Received: from EUR02-VI1-obe.outbound.protection.outlook.com by 64aa7808-outbound-1.mta.getcheckrecipient.com with ESMTPS id L60af32676802.2 (version=TLSv1.2 cipher=ECDHE-RSA-AES256-GCM-SHA384); Fri, 04 Oct 2024 17:53:26 +0000 ARC-Seal: i=1; a=rsa-sha256; s=arcselector10001; d=microsoft.com; cv=none; b=O7Ba7Io5dbEQV86J+vpIsIShuWW+gKHv17Jo1QX2+4sWe4jeHCUNUGhVu190zCu04r8GJzjiN2J4FY2s/bp/ULEsj6ua20nVF0q1T1kBGB7olkfxWrEvAwhJhwnpuNw0+ssVSTfr6cIJ/LS4PvfK1G4JV6hiaXbr5srlAnBAGLF14pBz0/Z/05V+Jl4Z8vjtxoeO+qzswmk0yFlT7K3pb14qqg6eaURbDkLLMEiWpocfz2ZdDvmrvUH4ttFFKgWf1UzvecOOHgZidwKJGvyI4KIqyIihF0IT2Ijt92rOePqfyYRoBqajmlJbThP4ZWx7UtBfMAWvxfpI2hiVl1RZSA== ARC-Message-Signature: i=1; a=rsa-sha256; c=relaxed/relaxed; d=microsoft.com; s=arcselector10001; 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=4lu2fo+4YVsF39RMw2GsnoUxx7EE3PlBEQ/RVG8xRZc=; b=qR8iaVqKkRrOCaVdmflXW+tWnsMJlYzeYHGY+hm40W7VQZMJrvHtYRtpe6gdzcZJdCBgIJL3Nn/g6ri+VymSq5ZBCcu+wE50lrjhPF7gtlMhO78+E8GBM0lyVT6ZDJ+joksjb1J5lVeBxZzgrXef+NuZ69ErfXy/6Wu0RnUkfFvQxySgWVeJ8jO63hE0T9R1vJHCe8JbmzkOMehUXowTIQBDfoLqGnhbRfn/PEe9aE1kQ3gdd1cFZG0BBcU6bg0e7P3HWx5Ith6ENf/72+wr7dxUPuESopi/1hNFTlF8ziS60a//F/LO03WBEOXqnFKh6PiOocSeesW5E/0chRx7hg== ARC-Authentication-Results: i=1; mx.microsoft.com 1; spf=pass smtp.mailfrom=arm.com; dmarc=pass action=none header.from=arm.com; dkim=pass header.d=arm.com; arc=none DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=arm.com; s=selector1; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-SenderADCheck; bh=4lu2fo+4YVsF39RMw2GsnoUxx7EE3PlBEQ/RVG8xRZc=; b=h6sKLR81o11tUDmSVKL+Ri168WwI27Kz8aj3ufhEVfSQoWp9SPhSxbOsHQnXQUMa8+eiwDbqVV5wrT2VsDm2sJe7n23wyidcKSMcel7Pf3NHa1Tu2uTOrO9e83SCSilp9HqCIualyLBhp1Uwojuhbj8Ojj4LDqqqm9wQ+GJiO9U= Authentication-Results-Original: dkim=none (message not signed) header.d=none;dmarc=none action=none header.from=arm.com; Received: from DU0PR08MB8255.eurprd08.prod.outlook.com (2603:10a6:10:411::9) by AS8PR08MB9527.eurprd08.prod.outlook.com (2603:10a6:20b:61d::7) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.8026.8; Fri, 4 Oct 2024 17:53:24 +0000 Received: from DU0PR08MB8255.eurprd08.prod.outlook.com ([fe80::cbc8:c020:6a1b:d27a]) by DU0PR08MB8255.eurprd08.prod.outlook.com ([fe80::cbc8:c020:6a1b:d27a%5]) with mapi id 15.20.8026.017; Fri, 4 Oct 2024 17:53:24 +0000 Date: Fri, 4 Oct 2024 18:53:22 +0100 From: Andrew Carlotti To: gcc-patches@gcc.gnu.org Cc: Richard Sandiford Subject: [PATCH 4/8] aarch64: Add new +frintts flag Message-ID: <903ffd34-70b3-2937-9659-d64903baaebd@e124511.cambridge.arm.com> References: Content-Disposition: inline In-Reply-To: X-ClientProxiedBy: LO4P123CA0521.GBRP123.PROD.OUTLOOK.COM (2603:10a6:600:272::22) To DU0PR08MB8255.eurprd08.prod.outlook.com (2603:10a6:10:411::9) MIME-Version: 1.0 X-MS-TrafficTypeDiagnostic: DU0PR08MB8255:EE_|AS8PR08MB9527:EE_|DB1PEPF00039234:EE_|AM8PR08MB6371:EE_ X-MS-Office365-Filtering-Correlation-Id: 55fe7a72-62e1-4d2b-2577-08dce49d76a2 x-checkrecipientrouted: true NoDisclaimer: true X-MS-Exchange-SenderADCheck: 1 X-MS-Exchange-AntiSpam-Relay: 0 X-Microsoft-Antispam-Untrusted: BCL:0;ARA:13230040|366016|376014|1800799024; X-Microsoft-Antispam-Message-Info-Original: 9fb1y1xld4ULgD60LQGmuASUJwTRt8UJ8ueXNiS38PR975qrno549dsuKLCyNnkF8QF/EYbLDC3vm/1ZUFCfZBytdcW7AxKHwUBTUG+EAS1I0JMpQcRNgOr9xU1Rn/Q5+7jNzptiE+3Wp6yHwQgV/jyExbLrYDkJQL/wSmSzsileuwRtdGyyxv6Cu9y8ECf1c5FNqE3IIQJ+FXTXVm16CtBHT2P745G1X5L98h2t/HnvPuNFzgM0UbeCipG1+x1Fl1Eoi84biyh1Na9+5LgP4DtgXwOccBg4AZbm+TmmKaiffsgfZY2wjAMw6Ep91LWKj/j7YPSzuLZa+C6yfnT8/YpoHJVpN0QC6Baz+odO6dtXnMGTGgUA6VYWyIcKb474HFa8RHwzhf2RuvF8a7/FkUAxBXCBhG5e0mTKNOWWtV7lytMB4Vu1PGht2zdSJ420/M9z8QmVPg5KpP/2rJRYMzZAdkOELiWBShVvVRhSqY1iw5F60d1DSYn9dWoJDwujS5vnF3jvs7p9WWec5Ocn8jXYNERX5HZXi0gcf4l3ESs217AmSW2dbNaGzX10/IpOXJ3Lr3oiGLZzuQSIjIs/0m6PCB9G4PHd5AkUJCwoxfZGoP6n5IZIi4SkaQ3rh6a778y8goJjyxn34RGYqbuXKyC9dXlWj8XqfhUULTmbomH3+/ZGKL39n3Pj6l7NJyp38ub2zcFuw6Rf3HTY68baWhlPxsbJgVrbRpOAtqUxPYYGcjqWoLn4eblHeHQHdfMy/SVATD4cAyb0NWhWdbiJjUsH8D02UD8VXynw8BTI2XUm9w21yaKLCDMfDOuNJALSr09zxRG6m/H+82F+bkHjmyO3OBrLgEuW9s1WpYUG6PHBY70GzjtnW5VjoDX4rk+duoN0xy6oVfLHennWwUvJsV0MaZ7B3vXGSJXRGNPY57vaX4SgUKzm0HUKeVao2ZLkkwFLSjwhv/97vRk0lFCHOFP/5uQ17sm3+c/J2ZvTrhCAPWhC2ZS5wDZTLjUlP3U1LgV0IZF6qEl8fIkXrHMkYj+omdxZHmUzPR6xgkQMghJBbhR8rW/BkFmeAEythUE+XBbTHgkvUEhPjHRq1ztcROAlAljEXqVSP4MduDL29ib+FLbvEw5uVYfccj01LddjdBDOwFfZGvEMq3jRDtQnUQEm+mTZV0pzv9QwkdqQeSGdFU58XOVdtx+O5RczIk+th/20XbmmqmfvrfRktvgw72l/jn248SmH2PAopk3xXu4= X-Forefront-Antispam-Report-Untrusted: CIP:255.255.255.255; CTRY:; LANG:en; SCL:1; SRV:; IPV:NLI; SFV:NSPM; H:DU0PR08MB8255.eurprd08.prod.outlook.com; PTR:; CAT:NONE; SFS:(13230040)(366016)(376014)(1800799024); DIR:OUT; SFP:1101; X-MS-Exchange-Transport-CrossTenantHeadersStamped: AS8PR08MB9527 Original-Authentication-Results: dkim=none (message not signed) header.d=none;dmarc=none action=none header.from=arm.com; X-EOPAttributedMessage: 0 X-MS-Exchange-SkipListedInternetSender: ip=[2603:10a6:10:411::9]; domain=DU0PR08MB8255.eurprd08.prod.outlook.com X-MS-Exchange-Transport-CrossTenantHeadersStripped: DB1PEPF00039234.eurprd03.prod.outlook.com X-MS-PublicTrafficType: Email X-MS-Office365-Filtering-Correlation-Id-Prvs: bcc4a0c9-8aba-4471-08de-08dce49d7151 X-Microsoft-Antispam: BCL:0; ARA:13230040|376014|35042699022|36860700013|1800799024|82310400026; X-Microsoft-Antispam-Message-Info: jqHsVhx/B23iGtczGEmKHiBP3iMoLwPodYi4ZMObduuDhaX6hjJ3GHlyw2CxMqisJHaf86tqaCYz2Emx7VYq8hhTAjWvXYmdK2HuCZKRZGKOIjHNaIydMc11uHRshyLwh8eqHEZaKUTP9HmB/3YU5REr3+TV8EfSo6pDOI8RZVG238fHBFq6bm/Bt9jjbBC5+77TWDjv896QmoNfms2hr0Mjb+mRb7HEdDER1AJzXE1T4SQ37oCjEqFhJr8GGkGnsEhB0Y+0KJEzWtxSteERe93XLisoC+ZJyeaFgaqtz3EahgB2b9+q6zfHK/SXjpAFXc25KzFA2Rea8u/KnAnv/H3tgkoz270ruKImZJ53imL8GzAepjZkFnmTPPWWbfZJNhVmygHgpl4GHMrPS8Y3J51Eh7INLG7qEPGyS821c0hmo3FFGAjpKxXQcIWy3i8eSd4BRfZ87kHxgFLA8HLewLWVzUvq3k3pxtYC4PSXyfHfCoxMYbL9IJB0465LA0EG+S3qqLcVgkA6023gTGS6e9gj8OKJ6hLxX4JyH3DgLDwUClAko+5dCNdYpD6WqIUvjnNHRNDcKTs0L9WJznetfJHIAienXFV+2C/d5G4q1IULh2N4sH/oRMFu8kAY07Pur/hOT4r5a/V8ba37CTKryp//RRh8cBzcViETriekAMXTsA7C0oenMsWx4kPmMqvZ2MT6sNaWqLmvqJ82hEH1lnKVsiZLM7Z1ui1EN/STXk7TH+Wz7a94W54KyrglGiPtRDQJn0L+hHLkKwgbr6exVm5p3JxtL980SPCPyNCA7v91eWrOkTaIWB0Yp4afIGvgpetEh1RzCeZlyFOt0RIJ3sMmCljsCPflrZDGXSFZINwFaSZmsxjVq9As8aslCWjs6UghwXpXaJmjosqEQxrs0eajjQZ1mmL4nJx9t4CNPRWidT/zsKqZ7/H2a1+v3VihS/GCWxFvEtFc5eQWOUzlnVAJj3dAQHFxQhgAHHyuo3Z74Uv3kqwt9mADc0xifhKKKCKhv4k6D7bDUaKZ8kDA3pKxG6v+gUjnTHkc3klcqySn/oGRjUdYQgbAHSUsjtjZDuhqu/SPaku8oy3iCLuGPpr5yTplo980YD2NRrudl3ndhTKh6Oz7jOY0+weh+ZLqDMoKrQTPu3Qx8k4vGvr2DK/FCNus++TquvCJl5hStPLMN6ZQiSTjXI6Z7+DZUYZ5Kodf6K+vyKQVblOhrQyxIjCKxX4uGhBHk5gYlgtsZ5Tl4Kni9DsJYpGYG6xQbdNIT4a0tb88JyEWo2z1m85On/uW7xWA/0+qH3DKEuJXj6zaIE3fgCJ3por9NfMAK3xF4EFwRZ5ta20S8DSMtSJZBg== 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:(13230040)(376014)(35042699022)(36860700013)(1800799024)(82310400026); DIR:OUT; SFP:1101; X-OriginatorOrg: arm.com X-MS-Exchange-CrossTenant-OriginalArrivalTime: 04 Oct 2024 17:53:33.1104 (UTC) X-MS-Exchange-CrossTenant-Network-Message-Id: 55fe7a72-62e1-4d2b-2577-08dce49d76a2 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: DB1PEPF00039234.eurprd03.prod.outlook.com X-MS-Exchange-CrossTenant-AuthAs: Anonymous X-MS-Exchange-CrossTenant-FromEntityHeader: HybridOnPrem X-MS-Exchange-Transport-CrossTenantHeadersStamped: AM8PR08MB6371 X-Spam-Status: No, score=-12.1 required=5.0 tests=BAYES_00, DKIM_SIGNED, DKIM_VALID, DKIM_VALID_AU, DKIM_VALID_EF, FORGED_SPF_HELO, GIT_PATCH_0, KAM_LOTSOFHASH, KAM_SHORT, SPF_HELO_PASS, SPF_NONE, TXREP, 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 gcc/ChangeLog: * config/aarch64/aarch64-arches.def (V8_5A): Add FRINTTS * config/aarch64/aarch64-option-extensions.def (FRINTTS): New flag. * config/aarch64/aarch64.h (TARGET_FRINT): Use new flag. * config/aarch64/arm_acle.h: Use new flag for frintts intrinsics. * config/aarch64/arm_neon.h: Ditto. gcc/testsuite/ChangeLog: * gcc.target/aarch64/cpunative/native_cpu_21.c: Add frintts to expected feature string. * gcc.target/aarch64/cpunative/native_cpu_22.c: Ditto. diff --git a/gcc/config/aarch64/aarch64-arches.def b/gcc/config/aarch64/aarch64-arches.def index c93c5c39d69ee497f1da3dd398b0353a3f99be8c..668e7833bd81a7d8795df022f205ca7ca0d0ddef 100644 --- a/gcc/config/aarch64/aarch64-arches.def +++ b/gcc/config/aarch64/aarch64-arches.def @@ -35,7 +35,7 @@ AARCH64_ARCH("armv8.1-a", generic_armv8_a, V8_1A, 8, (V8A, LSE, CRC, AARCH64_ARCH("armv8.2-a", generic_armv8_a, V8_2A, 8, (V8_1A)) AARCH64_ARCH("armv8.3-a", generic_armv8_a, V8_3A, 8, (V8_2A, PAUTH, RCPC, FCMA, JSCVT)) AARCH64_ARCH("armv8.4-a", generic_armv8_a, V8_4A, 8, (V8_3A, F16FML, DOTPROD, FLAGM)) -AARCH64_ARCH("armv8.5-a", generic_armv8_a, V8_5A, 8, (V8_4A, SB, SSBS, PREDRES)) +AARCH64_ARCH("armv8.5-a", generic_armv8_a, V8_5A, 8, (V8_4A, SB, SSBS, PREDRES, FRINTTS)) AARCH64_ARCH("armv8.6-a", generic_armv8_a, V8_6A, 8, (V8_5A, I8MM, BF16)) AARCH64_ARCH("armv8.7-a", generic_armv8_a, V8_7A, 8, (V8_6A)) AARCH64_ARCH("armv8.8-a", generic_armv8_a, V8_8A, 8, (V8_7A, MOPS)) diff --git a/gcc/config/aarch64/aarch64-option-extensions.def b/gcc/config/aarch64/aarch64-option-extensions.def index c3663998c55b9ce4113dcce57bdea5980073d73c..505f1fb721c64e4b55b52baf465024a57c68ab98 100644 --- a/gcc/config/aarch64/aarch64-option-extensions.def +++ b/gcc/config/aarch64/aarch64-option-extensions.def @@ -159,6 +159,8 @@ AARCH64_OPT_FMV_EXTENSION("rcpc", RCPC, (), (), (), "lrcpc") AARCH64_OPT_FMV_EXTENSION("rcpc3", RCPC3, (RCPC), (), (), "lrcpc3") +AARCH64_OPT_FMV_EXTENSION("frintts", FRINTTS, (FP), (), (), "frint") + AARCH64_OPT_FMV_EXTENSION("i8mm", I8MM, (SIMD), (), (), "i8mm") /* An explicit +bf16 implies +simd, but +bf16+nosimd still enables scalar BF16 diff --git a/gcc/config/aarch64/aarch64.h b/gcc/config/aarch64/aarch64.h index 864f2d438479a74c9ada80577b37b2aa86085d02..41430466b50bf223bf008c753d24f57570c1f2e5 100644 --- a/gcc/config/aarch64/aarch64.h +++ b/gcc/config/aarch64/aarch64.h @@ -367,7 +367,7 @@ constexpr auto AARCH64_FL_DEFAULT_ISA_MODE ATTRIBUTE_UNUSED #define TARGET_COMPLEX AARCH64_HAVE_ISA (FCMA) /* Floating-point rounding instructions from Armv8.5-a. */ -#define TARGET_FRINT (AARCH64_HAVE_ISA (V8_5A) && TARGET_FLOAT) +#define TARGET_FRINT AARCH64_HAVE_ISA (FRINTTS) /* TME instructions are enabled. */ #define TARGET_TME AARCH64_HAVE_ISA (TME) diff --git a/gcc/config/aarch64/arm_acle.h b/gcc/config/aarch64/arm_acle.h index 0f06bde6c50261208d03985b6614d1983b535efb..617f261e1ba24acc77527b42eacb5233410689b8 100644 --- a/gcc/config/aarch64/arm_acle.h +++ b/gcc/config/aarch64/arm_acle.h @@ -130,7 +130,7 @@ __jcvt (double __a) #pragma GCC pop_options #pragma GCC push_options -#pragma GCC target ("arch=armv8.5-a") +#pragma GCC target ("+nothing+frintts") __extension__ extern __inline float __attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) __rint32zf (float __a) diff --git a/gcc/config/aarch64/arm_neon.h b/gcc/config/aarch64/arm_neon.h index 0ab511a884126821ecae7d2fc7c1a3427bdfe5ac..2ffbffbac855ac2c47ad6416e7d2683c4ac2ab53 100644 --- a/gcc/config/aarch64/arm_neon.h +++ b/gcc/config/aarch64/arm_neon.h @@ -27678,7 +27678,7 @@ vfmlslq_laneq_high_f16 (float32x4_t __r, float16x8_t __a, float16x8_t __b, #pragma GCC pop_options #pragma GCC push_options -#pragma GCC target ("arch=armv8.5-a") +#pragma GCC target ("+nothing+simd+frintts") __extension__ extern __inline float32x2_t __attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) diff --git a/gcc/testsuite/gcc.target/aarch64/cpunative/native_cpu_21.c b/gcc/testsuite/gcc.target/aarch64/cpunative/native_cpu_21.c index 603ee48d584b8085755b577e09a6e7d6abbb5623..aa70d1d22b8299befcd81a696f051eb72997d548 100644 --- a/gcc/testsuite/gcc.target/aarch64/cpunative/native_cpu_21.c +++ b/gcc/testsuite/gcc.target/aarch64/cpunative/native_cpu_21.c @@ -7,7 +7,7 @@ int main() return 0; } -/* { dg-final { scan-assembler {\.arch armv8-a\+flagm\+lse\+dotprod\+rdma\+crc\+fp16fml\+jscvt\+rcpc\+i8mm\+bf16\+sve2-aes\+sve2-bitperm\+sve2-sha3\+sve2-sm4\+sb\+ssbs\n} } } */ +/* { dg-final { scan-assembler {\.arch armv8-a\+flagm\+lse\+dotprod\+rdma\+crc\+fp16fml\+jscvt\+rcpc\+frintts\+i8mm\+bf16\+sve2-aes\+sve2-bitperm\+sve2-sha3\+sve2-sm4\+sb\+ssbs\n} } } */ /* Check that an Armv8-A core doesn't fall apart on extensions without midr values. */ diff --git a/gcc/testsuite/gcc.target/aarch64/cpunative/native_cpu_22.c b/gcc/testsuite/gcc.target/aarch64/cpunative/native_cpu_22.c index e0ba97fb6e9a2969b8122ca0315ef73f16983045..ccd5d0d9bb7d7bf722bcffcc14c46d88d3223cf3 100644 --- a/gcc/testsuite/gcc.target/aarch64/cpunative/native_cpu_22.c +++ b/gcc/testsuite/gcc.target/aarch64/cpunative/native_cpu_22.c @@ -7,7 +7,7 @@ int main() return 0; } -/* { dg-final { scan-assembler {\.arch armv8-a\+flagm\+lse\+dotprod\+rdma\+crc\+fp16fml\+jscvt\+rcpc\+i8mm\+bf16\+sve2-aes\+sve2-bitperm\+sve2-sha3\+sve2-sm4\+sb\+ssbs\+pauth\n} } } */ +/* { dg-final { scan-assembler {\.arch armv8-a\+flagm\+lse\+dotprod\+rdma\+crc\+fp16fml\+jscvt\+rcpc\+frintts\+i8mm\+bf16\+sve2-aes\+sve2-bitperm\+sve2-sha3\+sve2-sm4\+sb\+ssbs\+pauth\n} } } */ /* Check that an Armv8-A core doesn't fall apart on extensions without midr values and that it enables optional features. */ From patchwork Fri Oct 4 17:53:40 2024 Content-Type: text/plain; charset="utf-8" MIME-Version: 1.0 Content-Transfer-Encoding: 7bit X-Patchwork-Submitter: Andrew Carlotti X-Patchwork-Id: 1992943 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=arm.com header.i=@arm.com header.a=rsa-sha256 header.s=selector1 header.b=PiyDV/JZ; dkim=pass (1024-bit key) header.d=arm.com header.i=@arm.com header.a=rsa-sha256 header.s=selector1 header.b=PiyDV/JZ; 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 4XKx5409Mnz1xtH for ; Sat, 5 Oct 2024 03:54:32 +1000 (AEST) Received: from server2.sourceware.org (localhost [IPv6:::1]) by sourceware.org (Postfix) with ESMTP id D1DFC3842584 for ; Fri, 4 Oct 2024 17:54:29 +0000 (GMT) X-Original-To: gcc-patches@gcc.gnu.org Delivered-To: gcc-patches@gcc.gnu.org Received: from EUR05-VI1-obe.outbound.protection.outlook.com (mail-vi1eur05on20620.outbound.protection.outlook.com [IPv6:2a01:111:f403:2613::620]) by sourceware.org (Postfix) with ESMTPS id AF29B385E45F for ; Fri, 4 Oct 2024 17:53:59 +0000 (GMT) DMARC-Filter: OpenDMARC Filter v1.4.2 sourceware.org AF29B385E45F 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 AF29B385E45F Authentication-Results: server2.sourceware.org; arc=pass smtp.remote-ip=2a01:111:f403:2613::620 ARC-Seal: i=3; a=rsa-sha256; d=sourceware.org; s=key; t=1728064441; cv=pass; b=VGKIqDnouIDtvNNSOzXp7r+BZr9td4E2zRdbcwkTklZ/wfV+86GIY/0dIUjj5gUb/vw+ISas2ixcYV05cKJByrP1T2hU34wBFFfW7GFk/DGT2xEhuCqKkQ3nbTKvGz+PWWqH//Ph6eg805DqTjoWtH3CTat86KUXMF2P4xqI7j4= ARC-Message-Signature: i=3; a=rsa-sha256; d=sourceware.org; s=key; t=1728064441; c=relaxed/simple; bh=GvOq6wqmU1LgvcezoQqNzwPR4CgRp+rrfmEMEWipNVM=; h=DKIM-Signature:DKIM-Signature:Date:From:To:Subject:Message-ID: MIME-Version; b=I6q9lbvjxzBdXek6D7oZPS648RI989z7AG4C1JE42ifVB5PbS1MrSubG9q7OrjUQSiGUMhrOa1SfJCh26S6xsuds3d4MURb924GLsph6MOBPu4VhIFdxYN0RUBpSShYrq7ZGXw6M6OE/Btq5lzY5DZP+EZ7o6j0myPveRs3Rlnk= ARC-Authentication-Results: i=3; server2.sourceware.org ARC-Seal: i=2; a=rsa-sha256; s=arcselector10001; d=microsoft.com; cv=pass; b=wK2BTvAMJTobr+SmTnFAdDF2aT6jNLkZsy7vMA1Tz56261D0f5Ft2zj8DStqjx5Dxzwkj7NakiMxJ7uxuB0Dj4s2xGa7/LLMPx0eSCSjlOB/ilGAgfehXy6kZ0PBNndvnYwWGRyGcV9G5AZFzjXVA6unAmLHtpullgdr436nb4s8J9G5oD3VmjkyEiPFCR/WyLUnlWvH0MBM5/Y5X/Ck/9q79g9K9FdB2aJasKjwOtze/R0Wq+OD9ragCslvI/AOK6/vkR2mnmnkctdks2YCsO/ftGSjZAtGPrCWp3g9bFX8DPrdNB+9/3enmV/ss8a5sNBes21K8ZjVt63fLX2iEw== ARC-Message-Signature: i=2; a=rsa-sha256; c=relaxed/relaxed; d=microsoft.com; s=arcselector10001; 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=ufB7aGGPZS1d/7XIVpeQi/vrlo1B5hYe1VAu6Mlu8ME=; b=goRn/glvbqhJtDCs8sjz4XaiaMq/RnhmtWXfQ2boUQshrZB4keM4zWa4CWD0alqdA4pPoploAl5Vu23oa4DMypPhbF3rQL6XsyezObiqZcr7pXr8gjH/NY+Vr5sd9u4At25MIwLoZlqg16uBdNGRoKIgeqZqP/j9tagaXHAnoAGqyCFGqcz8LJjQzuu6FSKRx9M4kWnVnxm9mVJ4cmgdCSlehgJt0Tdsh4irhKanK/VZ/4GGNwGA/JTVMaFjkoZdavyV0GIlfj7gJRzXdzdw63xsYfu0CN7QLndi+4+Q9lKhsQXYOD+Zcy8DH3Ch1dSQ6Cqc2fxaG6GA3EslfZDpsw== 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=arm.com; arc=pass (0 oda=1 ltdi=1 spf=[1,1,smtp.mailfrom=arm.com] dkim=[1,1,header.d=arm.com] dmarc=[1,1,header.from=arm.com]) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=arm.com; s=selector1; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-SenderADCheck; bh=ufB7aGGPZS1d/7XIVpeQi/vrlo1B5hYe1VAu6Mlu8ME=; b=PiyDV/JZGZMw2dlpttikJSuMniNaStpt791AsoasJus6GvhkCLn0UyqahULNkvGKBr/FoZsEWt9/aVIPCpMEHkme4O1ulNT7xbefvRurhsK5pQkyk0ptcVTO1nDvlHy1BPvkXyFkhh2dGDLiMUQHDEJ9v1ZowGTVdPfunqZ6mOw= Received: from AS8PR04CA0044.eurprd04.prod.outlook.com (2603:10a6:20b:312::19) by GVXPR08MB10986.eurprd08.prod.outlook.com (2603:10a6:150:1fc::12) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.8026.18; Fri, 4 Oct 2024 17:53:53 +0000 Received: from AMS1EPF00000048.eurprd04.prod.outlook.com (2603:10a6:20b:312:cafe::f1) by AS8PR04CA0044.outlook.office365.com (2603:10a6:20b:312::19) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.8026.18 via Frontend Transport; Fri, 4 Oct 2024 17:53:52 +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=arm.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 AMS1EPF00000048.mail.protection.outlook.com (10.167.16.132) with Microsoft SMTP Server (version=TLS1_3, cipher=TLS_AES_256_GCM_SHA384) id 15.20.8026.11 via Frontend Transport; Fri, 4 Oct 2024 17:53:52 +0000 Received: ("Tessian outbound 5b65fbeb7e07:v473"); Fri, 04 Oct 2024 17:53:52 +0000 X-CheckRecipientChecked: true X-CR-MTA-CID: 687cedef787e8575 X-TessianGatewayMetadata: nV6csrLYAa2oygUftrWQV69iSue5xmVScIFI1JMj8ZBBUB8u3rdVzVDoYod0SqALYibwRcUD5wiQsp/Et6ij32Y18kDwrk1ciTzopkVve30AajSl/0ZNXTt9cw3GcrMKqnwBzVC16A9tPE2AL/+7kTFXctcxE5rxMzd701Pu7Y20jKQFLhwo5FCv0X4+x0XK X-CR-MTA-TID: 64aa7808 Received: from L6672d25dca98.1 by 64aa7808-outbound-1.mta.getcheckrecipient.com id B0C3F592-4872-4301-9DBA-B67BA9CB2198.1; Fri, 04 Oct 2024 17:53:45 +0000 Received: from EUR02-DB5-obe.outbound.protection.outlook.com by 64aa7808-outbound-1.mta.getcheckrecipient.com with ESMTPS id L6672d25dca98.1 (version=TLSv1.2 cipher=ECDHE-RSA-AES256-GCM-SHA384); Fri, 04 Oct 2024 17:53:45 +0000 ARC-Seal: i=1; a=rsa-sha256; s=arcselector10001; d=microsoft.com; cv=none; b=r/rBPN6nUfhLnDGhJGUfWcl1B+AFbY2YCUz2wp0QyoUys3WL5/Bo4/mf1f+K6BdlQhT6TbsbcKc29KxnSDdtQTOSsKMm9kzv7i2qSB2nCqp76EjVQMj4YbgpOOQc/etQ9rQ35ejYTF5sbQxPKEnQ/+POYF0PtZY92yTazz4tLsJEURjK4A4Cop95Ywsis2ylsmL0PTnVRDSIc5kGhsopNAEubtFp+Jxbehar2+nNUqEnarQw7zDE5j+7NIR7tgL916pJ9jHJ22xTg+hqfML0PwKVjh5uI31O44WcOy5EbE3R7b8J5U7m44b/1iDgO6xstZ/ee//aRWUUCBnjlVjo4Q== ARC-Message-Signature: i=1; a=rsa-sha256; c=relaxed/relaxed; d=microsoft.com; s=arcselector10001; 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=ufB7aGGPZS1d/7XIVpeQi/vrlo1B5hYe1VAu6Mlu8ME=; b=tgbvE/XEbGW/W/Cmo+Wu2Jf+fTqaJ/nR4aojTm32BnHdIGbmDqZ6SmJdPr5YA265H7D/vHitpWJNBOGTUibzQTQEnk+SyPhUC1dnGVSb/NNrkXGHis52GcsWs3O6SQOJDnQmdcJVdYSgUNSVXA88Z3Qsktj/2RXpIWnfI9CctOZuW/6ksVy5huf0bgeK3ZQ8FG682Z2ENLcypMDK8N+pKRm8eCisDhXFI9K4LMSQuovXsOotrw5PYRS54EnTroIG0z4pCOVNbbvSJ1uKfiQ0xU9aBfqFW4pyH6YtRWD97KSN5yZPzY+P8ZtJ6EeP23Zdv+piYw+RiPsJbuHmXMxZ1g== ARC-Authentication-Results: i=1; mx.microsoft.com 1; spf=pass smtp.mailfrom=arm.com; dmarc=pass action=none header.from=arm.com; dkim=pass header.d=arm.com; arc=none DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=arm.com; s=selector1; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-SenderADCheck; bh=ufB7aGGPZS1d/7XIVpeQi/vrlo1B5hYe1VAu6Mlu8ME=; b=PiyDV/JZGZMw2dlpttikJSuMniNaStpt791AsoasJus6GvhkCLn0UyqahULNkvGKBr/FoZsEWt9/aVIPCpMEHkme4O1ulNT7xbefvRurhsK5pQkyk0ptcVTO1nDvlHy1BPvkXyFkhh2dGDLiMUQHDEJ9v1ZowGTVdPfunqZ6mOw= Authentication-Results-Original: dkim=none (message not signed) header.d=none;dmarc=none action=none header.from=arm.com; Received: from DU0PR08MB8255.eurprd08.prod.outlook.com (2603:10a6:10:411::9) by AS8PR08MB9527.eurprd08.prod.outlook.com (2603:10a6:20b:61d::7) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.8026.8; Fri, 4 Oct 2024 17:53:43 +0000 Received: from DU0PR08MB8255.eurprd08.prod.outlook.com ([fe80::cbc8:c020:6a1b:d27a]) by DU0PR08MB8255.eurprd08.prod.outlook.com ([fe80::cbc8:c020:6a1b:d27a%5]) with mapi id 15.20.8026.017; Fri, 4 Oct 2024 17:53:43 +0000 Date: Fri, 4 Oct 2024 18:53:40 +0100 From: Andrew Carlotti To: gcc-patches@gcc.gnu.org Cc: Richard Sandiford Subject: [PATCH 5/8] aarch64: Add new +flagm2 flag Message-ID: References: Content-Disposition: inline In-Reply-To: X-ClientProxiedBy: LO4P123CA0267.GBRP123.PROD.OUTLOOK.COM (2603:10a6:600:194::20) To DU0PR08MB8255.eurprd08.prod.outlook.com (2603:10a6:10:411::9) MIME-Version: 1.0 X-MS-TrafficTypeDiagnostic: DU0PR08MB8255:EE_|AS8PR08MB9527:EE_|AMS1EPF00000048:EE_|GVXPR08MB10986:EE_ X-MS-Office365-Filtering-Correlation-Id: c649fdfd-c29a-4f39-b370-08dce49d8262 x-checkrecipientrouted: true NoDisclaimer: true X-MS-Exchange-SenderADCheck: 1 X-MS-Exchange-AntiSpam-Relay: 0 X-Microsoft-Antispam-Untrusted: BCL:0;ARA:13230040|366016|376014|1800799024; X-Microsoft-Antispam-Message-Info-Original: dz9+T9awrZqcN8C6GCbKV7sPIEBUZhBzL2Vp2gVZResGyh5ZsScHt7Ux+qRyXyYb5JlS8omefwTAG226bRSlyLlNNUO0QIp3XujuZX2jTUOpvpBoDRgLHsghu7Y2FpsiunSuY52cMs5A9WiVSo9RZhvc/yQBsCZgU6uzj2QaBqPqsqA3tNLsrNNdI97nyFpPu+APq962/z82X0godddQjZkPVYnXNfEeLwgRun8cP/Y5NDOO7TZItreYu7S8dFeVNZBe3Wqxt7V3gBzWaUkpfJ7O1T83/uVcKtrf7cJ/bRl2FKbDk83PsP/1Tble7RyahhNd/b0QTyERHISfvor48eWDux8dFrpunK6K4kR6Lz1hkdFmsWONyIz4lqfXj+Bb//PP1o2uoshDLQN6nmktFni4j+hKd3YWntIpS801PBfg8thOJkuTzkuIG5qtVXWnvhZ3dqfVwXfgbpr+o/+IJLrKa1kFnPpx3iDiF2T8WXMVM2V5vXhGQkelNGtzHUf8xIGFGfybvblJR1gJoRybJwcBq2U0Hgo4iFZ/czdyWZmRGN8ycY8ttgpJcuo9QsTlSgk4BoHLy3uEjjszWNHEolbbzKxoxUOwv+YG3TKUgrNf4xp75QXkDneV/OFcnQSk0+cgM8Sngoczrcs/G1AynHtQZ5+B0OxakCntmy9yZowanWtocTuhW9HZ8r8EyQ1M8h3KeoxqmKQLwC3nLMtI01jNvtV7fPdVBrUcYekwGCl+sk5Hy3YLFD3VCW/kCGwEL5IzIKIKlyxjkO4p7WaswJjXdjqNR8fuV5ohgsVjwTf9wfS06pkVOtTgHcyf4CubXi+D9mtz0TFbtP0UcxNA352ZxAWIiW+rRBXNYDhaxQEYdG7sz79yDuikqr7uZNB5bppFVJtxlbozdqEp552ykwWGdhfrW5/Xbc8dgi2ylAtu6U7PtOXFHtxlwBHdCx1ml9wH++o1QCkXZg4JPldj/qn3iqlj2PEdcKqUpYptl3uI0KtV4R1GsyQcqqn95kIJdrlEJAgYude1JmDbg2Z7aqZeGdu/r0Y6Kno2VGpZmdvWfbhPFwaYTtOHA7XcT3cNq/Rc4W6Oyhd0mdyd5MfIzU1qdmsFxqxS+G2s4WLpG3ZzMj+keIvUcJWVFiP/1tICfj7KhusucEmdNyJntY5Z+ZzP4dTs18WM34ouPGVTpQpmwQDuBJB1lFoaa8zgANVywUxdaoT1RpZxLzwvbBwse8jqtSog6W9hsKMS8dPiMnY= X-Forefront-Antispam-Report-Untrusted: CIP:255.255.255.255; CTRY:; LANG:en; SCL:1; SRV:; IPV:NLI; SFV:NSPM; H:DU0PR08MB8255.eurprd08.prod.outlook.com; PTR:; CAT:NONE; SFS:(13230040)(366016)(376014)(1800799024); DIR:OUT; SFP:1101; X-MS-Exchange-Transport-CrossTenantHeadersStamped: AS8PR08MB9527 Original-Authentication-Results: dkim=none (message not signed) header.d=none;dmarc=none action=none header.from=arm.com; X-EOPAttributedMessage: 0 X-MS-Exchange-SkipListedInternetSender: ip=[2603:10a6:10:411::9]; domain=DU0PR08MB8255.eurprd08.prod.outlook.com X-MS-Exchange-Transport-CrossTenantHeadersStripped: AMS1EPF00000048.eurprd04.prod.outlook.com X-MS-PublicTrafficType: Email X-MS-Office365-Filtering-Correlation-Id-Prvs: d64107eb-7cbb-43b0-b043-08dce49d7c7b X-Microsoft-Antispam: BCL:0; ARA:13230040|36860700013|35042699022|1800799024|82310400026|376014; X-Microsoft-Antispam-Message-Info: WNcEaT5FZilPMQ42BWLPO+WSZ6ye3jFPgXnLo7jQa4mTaixJN8UYa+c6uesiOG80F+bamVpcIK8ewJocnzuOwqIFOqYT4kBy2h0kq5eSW3yVtQR6hnq5pKxiqUEVBPTaHECjO7rqVzCh3tzgs/sW1WCHWl4C5eNa28YnKZxwpHWxTN/bcH+zmwMOIWJT47G9BM7u9rnjA713tDE5881VbH4Jt3IfrTDxS8IfeXT+Ln/BiEI2gBBxHn/HiUFFftEnj3am5cGG7ra43mPXTsyIjm2/khD6uMXNB+NosnXla5JW6wwc8nz4Bz3Tuh89dQkAK/blBhljHyOjUMiCrDwXT3RORGz1l7DtSuPWs/ZSZjvjrixN4BVUvMR0qyzRTSIHQa9+/KdvQxWmSkHLmDhHxJQNAy+d0w6nkEnU3Q47e+1WwxdbtKLzm7Ms9M4smcczyogoCCxPOz++K8K2ZLJEAapYiFMoRwbR38rUPhnt9ZGBoWBRq4fFpfW5fPZpviqBLYOqU+ay2tc3qMOoAQVO2mIX/La1natrFz30yxlBEGX99HFtYFPYJN2B4vxjqW44KNPGpK1rJEwkl4uQ3TcvSbSEdCr5DF/y7RmpExVHSa4jLiaeGSEIh6xU3+I8s3c0Bw17TkTwBQhhYJ+bdPOiVkV8GETI0i7XK3lsz6lRiyAkkL2FbH7wkatvhGI0/iS6C6XGYsNa7rYGDPjf8crMnBnAXgBxeuqsEOkRxXxP6t3ZZXjGV7SloUNDsGBzwfvLVkrMJSDguxNGR9PCJP/GSD+2tJTWBaKwel8yZNuchnluV53NxFuQXJjQ3ygv92iRKdLzW9bI+kh0E+DCczssFa2Ph0KNk/wNwpolx5d4ZEczKC1tOyvXyehze1gf86ZCZe5dOK2maBwrlTvkHE+4EBag3+e7kExZxVXZZlb/XXFIVs4DAXDjzR/hfa1lDhxfp26eTrVlRwMKFXAuNkQ/j8TWHvcmdkO8Gyi7t2d2UVBlL+kEK0FNMn/UwghCKLmVyfIRogXfAJ1g6J08MAHT24q9ww5Vt7PkO87KvcwjaySLDyguQSvIBOiLCCRngx/Ulf/JQ14rsh7IFpFemKztMHoKl3TXFmAsLmvyAufHHZhYuUP6bh9kPF2WG8kklERQH3dD8r5aWj0QNh7COKb9q+6sncG4T0MVbC+0D+nGYVabN0Qp3RaLlLNZ14IQJCm1M3/YDe50hiSPm884DtxJUSfhqrfWVHxmkj5NDaG2XFL3hlJYgyAB1aYyGJqngatqQQX/JP82f/KRp3QaLIdeKGVrC+x+rcGR9JhG8Z/QN8AAxlV95dlsngBG0YVGZxEN 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:(13230040)(36860700013)(35042699022)(1800799024)(82310400026)(376014); DIR:OUT; SFP:1101; X-OriginatorOrg: arm.com X-MS-Exchange-CrossTenant-OriginalArrivalTime: 04 Oct 2024 17:53:52.7804 (UTC) X-MS-Exchange-CrossTenant-Network-Message-Id: c649fdfd-c29a-4f39-b370-08dce49d8262 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: AMS1EPF00000048.eurprd04.prod.outlook.com X-MS-Exchange-CrossTenant-AuthAs: Anonymous X-MS-Exchange-CrossTenant-FromEntityHeader: HybridOnPrem X-MS-Exchange-Transport-CrossTenantHeadersStamped: GVXPR08MB10986 X-Spam-Status: No, score=-12.1 required=5.0 tests=BAYES_00, DKIM_SIGNED, DKIM_VALID, DKIM_VALID_AU, DKIM_VALID_EF, FORGED_SPF_HELO, GIT_PATCH_0, KAM_LOTSOFHASH, KAM_SHORT, SPF_HELO_PASS, SPF_NONE, TXREP, 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 GCC does not currently emit the axflag or xaflag instructions, so this primarily affects the flags passed through to the assembler. gcc/ChangeLog: * config/aarch64/aarch64-arches.def (V8_5A): Add FLAGM2. * config/aarch64/aarch64-option-extensions.def (FLAGM2): New flag. gcc/testsuite/ChangeLog: * gcc.target/aarch64/cpunative/native_cpu_21.c: Add flagm2 to expected feature string instead of flagm. * gcc.target/aarch64/cpunative/native_cpu_22.c: Ditto. diff --git a/gcc/config/aarch64/aarch64-arches.def b/gcc/config/aarch64/aarch64-arches.def index 668e7833bd81a7d8795df022f205ca7ca0d0ddef..84782d55089650b5854c60497bc68f9564d6f90b 100644 --- a/gcc/config/aarch64/aarch64-arches.def +++ b/gcc/config/aarch64/aarch64-arches.def @@ -35,7 +35,7 @@ AARCH64_ARCH("armv8.1-a", generic_armv8_a, V8_1A, 8, (V8A, LSE, CRC, AARCH64_ARCH("armv8.2-a", generic_armv8_a, V8_2A, 8, (V8_1A)) AARCH64_ARCH("armv8.3-a", generic_armv8_a, V8_3A, 8, (V8_2A, PAUTH, RCPC, FCMA, JSCVT)) AARCH64_ARCH("armv8.4-a", generic_armv8_a, V8_4A, 8, (V8_3A, F16FML, DOTPROD, FLAGM)) -AARCH64_ARCH("armv8.5-a", generic_armv8_a, V8_5A, 8, (V8_4A, SB, SSBS, PREDRES, FRINTTS)) +AARCH64_ARCH("armv8.5-a", generic_armv8_a, V8_5A, 8, (V8_4A, SB, SSBS, PREDRES, FRINTTS, FLAGM2)) AARCH64_ARCH("armv8.6-a", generic_armv8_a, V8_6A, 8, (V8_5A, I8MM, BF16)) AARCH64_ARCH("armv8.7-a", generic_armv8_a, V8_7A, 8, (V8_6A)) AARCH64_ARCH("armv8.8-a", generic_armv8_a, V8_8A, 8, (V8_7A, MOPS)) diff --git a/gcc/config/aarch64/aarch64-option-extensions.def b/gcc/config/aarch64/aarch64-option-extensions.def index 505f1fb721c64e4b55b52baf465024a57c68ab98..b73324abbeb6145b5a2c26fdb22f41de9b6045d9 100644 --- a/gcc/config/aarch64/aarch64-option-extensions.def +++ b/gcc/config/aarch64/aarch64-option-extensions.def @@ -103,6 +103,8 @@ AARCH64_OPT_FMV_EXTENSION("rng", RNG, (), (), (), "rng") AARCH64_OPT_FMV_EXTENSION("flagm", FLAGM, (), (), (), "flagm") +AARCH64_OPT_FMV_EXTENSION("flagm2", FLAGM2, (FLAGM), (), (), "flagm2") + AARCH64_OPT_FMV_EXTENSION("lse", LSE, (), (), (), "atomics") AARCH64_OPT_FMV_EXTENSION("fp", FP, (), (), (), "fp") diff --git a/gcc/testsuite/gcc.target/aarch64/cpunative/native_cpu_21.c b/gcc/testsuite/gcc.target/aarch64/cpunative/native_cpu_21.c index aa70d1d22b8299befcd81a696f051eb72997d548..c1d5896e1eb0b3b48ac0c1eeb95a74c4b6ec9e85 100644 --- a/gcc/testsuite/gcc.target/aarch64/cpunative/native_cpu_21.c +++ b/gcc/testsuite/gcc.target/aarch64/cpunative/native_cpu_21.c @@ -7,7 +7,7 @@ int main() return 0; } -/* { dg-final { scan-assembler {\.arch armv8-a\+flagm\+lse\+dotprod\+rdma\+crc\+fp16fml\+jscvt\+rcpc\+frintts\+i8mm\+bf16\+sve2-aes\+sve2-bitperm\+sve2-sha3\+sve2-sm4\+sb\+ssbs\n} } } */ +/* { dg-final { scan-assembler {\.arch armv8-a\+flagm2\+lse\+dotprod\+rdma\+crc\+fp16fml\+jscvt\+rcpc\+frintts\+i8mm\+bf16\+sve2-aes\+sve2-bitperm\+sve2-sha3\+sve2-sm4\+sb\+ssbs\n} } } */ /* Check that an Armv8-A core doesn't fall apart on extensions without midr values. */ diff --git a/gcc/testsuite/gcc.target/aarch64/cpunative/native_cpu_22.c b/gcc/testsuite/gcc.target/aarch64/cpunative/native_cpu_22.c index ccd5d0d9bb7d7bf722bcffcc14c46d88d3223cf3..4533a2bf5912dc609327b63164ba4577e98f9eec 100644 --- a/gcc/testsuite/gcc.target/aarch64/cpunative/native_cpu_22.c +++ b/gcc/testsuite/gcc.target/aarch64/cpunative/native_cpu_22.c @@ -7,7 +7,7 @@ int main() return 0; } -/* { dg-final { scan-assembler {\.arch armv8-a\+flagm\+lse\+dotprod\+rdma\+crc\+fp16fml\+jscvt\+rcpc\+frintts\+i8mm\+bf16\+sve2-aes\+sve2-bitperm\+sve2-sha3\+sve2-sm4\+sb\+ssbs\+pauth\n} } } */ +/* { dg-final { scan-assembler {\.arch armv8-a\+flagm2\+lse\+dotprod\+rdma\+crc\+fp16fml\+jscvt\+rcpc\+frintts\+i8mm\+bf16\+sve2-aes\+sve2-bitperm\+sve2-sha3\+sve2-sm4\+sb\+ssbs\+pauth\n} } } */ /* Check that an Armv8-A core doesn't fall apart on extensions without midr values and that it enables optional features. */ From patchwork Fri Oct 4 17:54:00 2024 Content-Type: text/plain; charset="utf-8" MIME-Version: 1.0 Content-Transfer-Encoding: 7bit X-Patchwork-Submitter: Andrew Carlotti X-Patchwork-Id: 1992946 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=arm.com header.i=@arm.com header.a=rsa-sha256 header.s=selector1 header.b=aI8nU54K; dkim=pass (1024-bit key) header.d=arm.com header.i=@arm.com header.a=rsa-sha256 header.s=selector1 header.b=aI8nU54K; 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 4XKx5t2ttcz1xsn for ; Sat, 5 Oct 2024 03:55:14 +1000 (AEST) Received: from server2.sourceware.org (localhost [IPv6:::1]) by sourceware.org (Postfix) with ESMTP id 981F2386F474 for ; Fri, 4 Oct 2024 17:55:12 +0000 (GMT) X-Original-To: gcc-patches@gcc.gnu.org Delivered-To: gcc-patches@gcc.gnu.org Received: from EUR05-VI1-obe.outbound.protection.outlook.com (mail-vi1eur05on20601.outbound.protection.outlook.com [IPv6:2a01:111:f403:2613::601]) by sourceware.org (Postfix) with ESMTPS id 9C0263842588 for ; Fri, 4 Oct 2024 17:54:17 +0000 (GMT) DMARC-Filter: OpenDMARC Filter v1.4.2 sourceware.org 9C0263842588 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 9C0263842588 Authentication-Results: server2.sourceware.org; arc=pass smtp.remote-ip=2a01:111:f403:2613::601 ARC-Seal: i=3; a=rsa-sha256; d=sourceware.org; s=key; t=1728064461; cv=pass; b=UNAPtiUdlD7YHClHTUzux/Ho3QOoKjUqTzCjpeQN6Z6MWlegJhH1RgPJ2at9cUiaWjkXp5M1uYeHS3CPA6vuxsLTHaF2PO8rDA+bh9y2BdaDB/wHXAkeWhpgrrs6/7EDEjWYIG0Vec787RhwhT+shz3px7DHHId5BezU/wQRGFE= ARC-Message-Signature: i=3; a=rsa-sha256; d=sourceware.org; s=key; t=1728064461; c=relaxed/simple; bh=A4Y/0zJg6MFh6m24FFrr6zKu9+Enwo3jAflz57AEfYc=; h=DKIM-Signature:DKIM-Signature:Date:From:To:Subject:Message-ID: MIME-Version; b=PvcgCCVJJc+m3PhYmNl9YbcxcrAsvrG28lDkb0TjrxwVeUULMlXOXvOxc6R3hD7jm5liJKv5AD9PCBtGjlGGL160lUHImCBjctQt0VKZeVLiom6nZG/8jPG3MF1jRCVanLMiPR6ti+cq9Cxhm5VbEJfnQqJqwKYRkU5o+uYPzLA= ARC-Authentication-Results: i=3; server2.sourceware.org ARC-Seal: i=2; a=rsa-sha256; s=arcselector10001; d=microsoft.com; cv=pass; b=u94n/qWyvLniPassN19kJAwxkG1rxMjIaENCgkexpjZCSSuVhclDX1yZ0PeFn5vB8hDjYJj831XJ7AeePBq7bbpGIaFn/83H3YiU6Fbs9Kpq8n50axoAg6Y6BHzotEAzQvdhGtevW1C0I8SZoeLSeYOo1EKsgvxxpaEYVk9NkCoMnWPJRPjqXeSo4U5HZM4yJRVyPc/NSqAf5IWQ1zERehIsTNH8b4diH4sPHz1BkEc3vW8JOlwgTtSGygcRxebXZIJLoR7/3sSEs9DACtSWNtfsRj5pAfU+ijy+kR6muntxkNjqzbgfOEdD2Fjyx4Nq6zJoFblaLnXknr0EomfutA== ARC-Message-Signature: i=2; a=rsa-sha256; c=relaxed/relaxed; d=microsoft.com; s=arcselector10001; 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=jli4vI0JPNowR4YgR10azX61utMHciahFYK+Voh4d+s=; b=pB3wYWSsgM3zSAeNvJBTnlYhFNo95WDtBjDYkMHIEo/2Uc4G6xtLB6mpVGJ+PI1UNTGkcJa56FEtmWE4hrLgSk+CylYc47Aw0w5yGi+egf5k6Ap6QG9SltGOc9EfqKvWvXjiUDU7VWtbVz9JJCraoRMRMlw5rcqGOin9EEHNcrLkb04HvtVTIgbfjQRua2Ty7uhRS/PulA4GupWlj3QxR8sxBmzp5fdCHQ6KP0/hopcqYUoFcYQclSVh6f+l3ClQ3kTURUVR3UwU8VhLLoY8K44hagzxfA5C/S6ndYBdXJOu7wemoe+tczsl8aC+fAascTD1SjbaAYz4djyM0cPKig== 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=arm.com; arc=pass (0 oda=1 ltdi=1 spf=[1,1,smtp.mailfrom=arm.com] dkim=[1,1,header.d=arm.com] dmarc=[1,1,header.from=arm.com]) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=arm.com; s=selector1; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-SenderADCheck; bh=jli4vI0JPNowR4YgR10azX61utMHciahFYK+Voh4d+s=; b=aI8nU54K7kDUTKXLNCIYv7zXUhrXSzbNt1dIS8qgHInd2z7NjKF5+lspwNi2nHRhdM3f4U2oPSzfkjWYtYw+Un0JZgX6GCrqIAtYoO2nmDBVCNPZFzgV+GL7+y1ixPgJwuT3Jaw9C8mnT0YGRoRzhupGWXF8nuoJm5AFHNpmVow= Received: from AM6P192CA0084.EURP192.PROD.OUTLOOK.COM (2603:10a6:209:8d::25) by DB3PR08MB8985.eurprd08.prod.outlook.com (2603:10a6:10:43f::6) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.8026.18; Fri, 4 Oct 2024 17:54:12 +0000 Received: from AMS0EPF00000199.eurprd05.prod.outlook.com (2603:10a6:209:8d:cafe::5) by AM6P192CA0084.outlook.office365.com (2603:10a6:209:8d::25) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.8026.18 via Frontend Transport; Fri, 4 Oct 2024 17:54:12 +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=arm.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 AMS0EPF00000199.mail.protection.outlook.com (10.167.16.245) with Microsoft SMTP Server (version=TLS1_3, cipher=TLS_AES_256_GCM_SHA384) id 15.20.7918.13 via Frontend Transport; Fri, 4 Oct 2024 17:54:11 +0000 Received: ("Tessian outbound 994fc319cf83:v473"); Fri, 04 Oct 2024 17:54:11 +0000 X-CheckRecipientChecked: true X-CR-MTA-CID: 5d9a03bcedb57b99 X-TessianGatewayMetadata: j1ojCIXTuPNpvq6XKT+zQKUagPg9DOE/0g4i8yOuav1UpbqCjIdNvE25WmKHkJmirXnXN/KI7Aj8de+cD8KPruhdQmukPhlMAxfGECrA+iQg4XUoJn/VoulvAJ6Z+0D91oCN86K/YgZZ5FVSAE7h2jTOoybwG1VR/S8FwfteAuPgTAn+b/oNBtZ7/bG8c3qy X-CR-MTA-TID: 64aa7808 Received: from L553f2b095053.2 by 64aa7808-outbound-1.mta.getcheckrecipient.com id D972D2AD-C171-4AC6-B13B-8785DDD6DA34.1; Fri, 04 Oct 2024 17:54:04 +0000 Received: from EUR02-VI1-obe.outbound.protection.outlook.com by 64aa7808-outbound-1.mta.getcheckrecipient.com with ESMTPS id L553f2b095053.2 (version=TLSv1.2 cipher=ECDHE-RSA-AES256-GCM-SHA384); Fri, 04 Oct 2024 17:54:04 +0000 ARC-Seal: i=1; a=rsa-sha256; s=arcselector10001; d=microsoft.com; cv=none; b=wyke6pgQC9VDT8jhIJjEpscNvrkkSrNqmioZSNAlk/4VY12adEM6Qqx6AW/2n+unkrhnAB0IpDb8uzmjKFVula4ZU/f7A3XL7hY/dVfs2N8rDpjIRlAyMmWX160KLMrugGGZscc+Oq0m7kHeWL5cePv3N/mRaXw35iG/RwILINBY6Z6NL6hc67MqNEqhfokciLmDQqWN0F8ChJioNbjiNaW01oHlxbOetpd9LcownMaKseQBRkSlXqhD6hMxXWvDgJdCeUYkd78g0JTY/ntFVGpA+EQfcdbuZhmh1/eb+0YmnKklRiK17Wu3BE7rB3Q+f/7ybm3YrdhmJpewSo2e8g== ARC-Message-Signature: i=1; a=rsa-sha256; c=relaxed/relaxed; d=microsoft.com; s=arcselector10001; 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=jli4vI0JPNowR4YgR10azX61utMHciahFYK+Voh4d+s=; b=EaOa+wVJH0POtuXhCcrWRp5W3LZELNHKGhtETxEYBDKJ1O9tppg42nGMvdgBnkEY4WxQlL2VKfcwbCSg/9VwPOXzH3HPxXgz4/GHWYemA+OqPwa+mx6F5ij6gNcMMGnGRnpW5mHA2Acg7SxFq5AUv4EwS98AiXwQUgGtqW3ix67K8pdEuDO1js/f3I3SZElwRtU5XGB20HZ4IAukWBmmLObuFRzYbtOu6bys1sxkEL/68sqcIGo3WViRIEjYwqTCCy/Unljogqlk7eAe9e2npPqmrfz40tFHMJCcJzGolMJhCbIFpA20jPB3qvnLyYKjWlgDkz9DQFWYQ82a6e3mPQ== ARC-Authentication-Results: i=1; mx.microsoft.com 1; spf=pass smtp.mailfrom=arm.com; dmarc=pass action=none header.from=arm.com; dkim=pass header.d=arm.com; arc=none DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=arm.com; s=selector1; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-SenderADCheck; bh=jli4vI0JPNowR4YgR10azX61utMHciahFYK+Voh4d+s=; b=aI8nU54K7kDUTKXLNCIYv7zXUhrXSzbNt1dIS8qgHInd2z7NjKF5+lspwNi2nHRhdM3f4U2oPSzfkjWYtYw+Un0JZgX6GCrqIAtYoO2nmDBVCNPZFzgV+GL7+y1ixPgJwuT3Jaw9C8mnT0YGRoRzhupGWXF8nuoJm5AFHNpmVow= Authentication-Results-Original: dkim=none (message not signed) header.d=none;dmarc=none action=none header.from=arm.com; Received: from DU0PR08MB8255.eurprd08.prod.outlook.com (2603:10a6:10:411::9) by AS8PR08MB9527.eurprd08.prod.outlook.com (2603:10a6:20b:61d::7) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.8026.8; Fri, 4 Oct 2024 17:54:02 +0000 Received: from DU0PR08MB8255.eurprd08.prod.outlook.com ([fe80::cbc8:c020:6a1b:d27a]) by DU0PR08MB8255.eurprd08.prod.outlook.com ([fe80::cbc8:c020:6a1b:d27a%5]) with mapi id 15.20.8026.017; Fri, 4 Oct 2024 17:54:02 +0000 Date: Fri, 4 Oct 2024 18:54:00 +0100 From: Andrew Carlotti To: gcc-patches@gcc.gnu.org Cc: Richard Sandiford Subject: [PATCH 6/8] aarch64: Add new +rcpc2 flag Message-ID: <75c96ec3-ea4d-3fa2-2abd-d99cda5e26a9@e124511.cambridge.arm.com> References: Content-Disposition: inline In-Reply-To: X-ClientProxiedBy: LO4P123CA0500.GBRP123.PROD.OUTLOOK.COM (2603:10a6:600:1ab::19) To DU0PR08MB8255.eurprd08.prod.outlook.com (2603:10a6:10:411::9) MIME-Version: 1.0 X-MS-TrafficTypeDiagnostic: DU0PR08MB8255:EE_|AS8PR08MB9527:EE_|AMS0EPF00000199:EE_|DB3PR08MB8985:EE_ X-MS-Office365-Filtering-Correlation-Id: b896d091-6af9-40be-b926-08dce49d8d7c x-checkrecipientrouted: true NoDisclaimer: true X-MS-Exchange-SenderADCheck: 1 X-MS-Exchange-AntiSpam-Relay: 0 X-Microsoft-Antispam-Untrusted: BCL:0;ARA:13230040|366016|376014|1800799024; X-Microsoft-Antispam-Message-Info-Original: yg2RoproMMlTyvPYLyIS21a/LO2RRBPnla5qFKJLotC66lhmUnENz0O1xOB7rf85SNL9WVD+ACh19ZdfDo6yC4Ssk/uBui+yah2wFJbnfJlT9448zROZ231Mbu1qG0r4iZifm4aVN+dGP/ZpuLPqJj9SwOcupjXVo0FEZv/IGO/oFA7K1qQvn6r3vi/Sc9+zjNtUxJHbaMi3+dsN/8PvJ0H1IeIsgqmfelJpREELPni3fT9Co+NtvodWADuolYnfmHHPQZrOffqVedMXfG56kqukEKTzp/LMG1HWThhWoU2HQKd403mTyjxjHelVftDO3hMDjvSYxh5GovITGu3cru6Wzt5m18xrqde1MhZOB4NQHV07KgnC1ywcD689sbNqE2Ujos/AipyLd3/oaOpqlxFpzcv0JUEI8GdKEfrhXHk6smpaaNHiDbUms/gIDyIQfXYUP+O6DPivctDwbrzsjrO3heqGYi7b8/FpYUGofNOwBHYeihJkRYzwnB5eXKXnm/ohaBbjji+SV0i2fGYsfs4nI9Cg6Cj+Zi8vUQwxSueUCwsRJAKYwczK3iEQtV+EbvKIaXo3/LQejXxwV6k9O5esfDSfnlQrv0/yi3I54PB7UcNnRKN4KpwXFD81yZunMS8GX759lCiPTeSCFjgo9A1NlEL4KVo1J0H61HQFGNOfx/HZyWgSURhMo8uYRYgILiKkCr7BencH/fJB/sKX+vQFE+XjvaVt5jXWAqPSfkSPMVY0FODBcZYJnloffofg0mMYQ5aS/Gj5EQenJPb2XplCrinrJUuwgXD52dB36l0t9uy6r7tiLb4vHy+TDVQEbql+sK8yXmVE/gdqrHasTLC4Sx2WpXnTo3gDaFA0X6zuwC2XXBNHiLzgDAdhyjyiDEOy0CCY8yhOJpirzYwXW3/niXlUwnJUNEk9XpwYyQ4SrzsZrvX1VyeJdcRoThmkKq8ZjaAaCsZ1MRMBsADpohaW0rajc7S4ZHkBwJ0qu761cyAmO+kFo/L4OCS3sJ/O+W5d9BdcH0qJV8dq8xE9pgcH/EmdqhfYNiq4bjj4wbSAk3F+dMjJuGfL4hhGVKxLvW8ULeEXneAMekzImvOcD5r5P50crwoAD6wjs6klGk2RVcBK+2cwRFnsqtJz6IimE6Go8aJZQBeVLtZX9gR//lEP+1EBQ50HK3DdBTQ8rdSyUPjpVXDmSeoKtga3lam26vXVB5bvmK91vQPfB0xi7rPr0MTG7S1gcmPQSP3dAcs= X-Forefront-Antispam-Report-Untrusted: CIP:255.255.255.255; CTRY:; LANG:en; SCL:1; SRV:; IPV:NLI; SFV:NSPM; H:DU0PR08MB8255.eurprd08.prod.outlook.com; PTR:; CAT:NONE; SFS:(13230040)(366016)(376014)(1800799024); DIR:OUT; SFP:1101; X-MS-Exchange-Transport-CrossTenantHeadersStamped: AS8PR08MB9527 Original-Authentication-Results: dkim=none (message not signed) header.d=none;dmarc=none action=none header.from=arm.com; X-EOPAttributedMessage: 0 X-MS-Exchange-SkipListedInternetSender: ip=[2603:10a6:10:411::9]; domain=DU0PR08MB8255.eurprd08.prod.outlook.com X-MS-Exchange-Transport-CrossTenantHeadersStripped: AMS0EPF00000199.eurprd05.prod.outlook.com X-MS-PublicTrafficType: Email X-MS-Office365-Filtering-Correlation-Id-Prvs: 62490de3-483d-456a-6035-08dce49d87f6 X-Microsoft-Antispam: BCL:0; ARA:13230040|35042699022|36860700013|1800799024|376014|82310400026; X-Microsoft-Antispam-Message-Info: DcRhAGkeslGLsLpRMwq6Axn8Te1WdKc+bE8pPlrpRkdZ/EHrTP+m7cjJhqzgKAtKVTRxo7XgnmhUjOqB3vYFmvCPMxLJhz3P9OuV4+0sksoqnydspe4thoIxor4Dydag+niTpOhU4fMbM+REoEHx46fMyE9AHVrWiR3eRsxBUio4YEzjQgEdswS9uZ+BxS3XaQqbdNITjHfu67pwEgXeox4/94bQ9Cy17Y3RIMCgW2TDQ04JXbVt5pTZoRYHSS2zK2zWvsdo5fKZ9s3A4tJ+U8aJ/4WNoKzMadbqKppmyiJi8+M9D0FTl/bR8Qs7FHl+Cb+DUiV7hXEqNb5D55LmQ10bnkPmDPl9hKwsdFIekOi71o9fTK64Skku8KTaFs9VcAug/0rMAXYwhTITLiIjzSG15esIKQpUXctkMHGe6eRiFu1XLW8I0qgW+S7tZ8ChVtn3lxoJrBLnJViQeeF7um5Sm1wSzAgSxBMxYWS8GXZqqIn1G/QTpP4DyYxblS+O3kg/RItv5m2/RPSHtyO3T493cbDkf+h2ZyqaWVUe++GcCErBnqn22i9i/G2Oj9r0/7uFL7l0qNzuCYq0RsEqi4FQMgSJDAxsumoLI9HM6dgVu7kdbwOMfnNRVPjRdT6hl8d4pcX/gfy1EBQ5NX0yv0NPe6+doAGhy0EiBuGwTYcZPXfWKZ7DuaueqBp9IWjpTN5l71nLdP+WbM+ETEmO5cLQxLfqB7DqOiD8ChuaUV94TcuwSWjbJlgpUHjiKpOTuFSAIqT3F/O3KNGByrLmMRHIun+G0WIv0ppUuj1XTVY3TuzNOBDQHF9NF/AgtY6lFsMKAVm+XrponCKBpknQVZEj6Xd84uhKFM9371QvKJcjccgUUWe7gNz29nX5gKaZBDNkkRfu/CpSZiVN1MpWn1F/c8RniJub0B6/merV/HLU2QfFGlfhuXIOJeU+nd7v3VaSU6jQswKcSC+7U//QNs8j7sZbAS5anYTKstj5DoI8kYjn9gaknjB6sM6VQ8503ranxEccuxSSHB6JL6O6cyiiuup5eRQSrmFeJLi7rNG/DK4M2SUEm6hXpJoQ9yQJB0F75RiqLruOI/54GOJl88wEcOcBF6uXn+mflrrqcb6ZqhV4MNkqkTrVPq3oJRjtELa6r6QoOe1AFlWydiReQaelBItsLv8e/V/C5SNyECQiujJbnpGRCKOWTMNcwPN6/KM4nDM2PKk556mYAIeOBAErgyrLw0GvcrhuwgwbtgIvOJRkaHqUWQ6WEB6gt2z4rwf4U4ivFm3mMiptY+80hKOH80GklPUV2TcGZwDHK46yw8tWn2bhio5osJQs5YckgrPY/AFJ1HppnhI+agzJmw== 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:(13230040)(35042699022)(36860700013)(1800799024)(376014)(82310400026); DIR:OUT; SFP:1101; X-OriginatorOrg: arm.com X-MS-Exchange-CrossTenant-OriginalArrivalTime: 04 Oct 2024 17:54:11.3746 (UTC) X-MS-Exchange-CrossTenant-Network-Message-Id: b896d091-6af9-40be-b926-08dce49d8d7c 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: AMS0EPF00000199.eurprd05.prod.outlook.com X-MS-Exchange-CrossTenant-AuthAs: Anonymous X-MS-Exchange-CrossTenant-FromEntityHeader: HybridOnPrem X-MS-Exchange-Transport-CrossTenantHeadersStamped: DB3PR08MB8985 X-Spam-Status: No, score=-12.1 required=5.0 tests=BAYES_00, DKIM_SIGNED, DKIM_VALID, DKIM_VALID_AU, DKIM_VALID_EF, FORGED_SPF_HELO, GIT_PATCH_0, KAM_LOTSOFHASH, KAM_SHORT, SPF_HELO_PASS, SPF_NONE, TXREP, 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 gcc/ChangeLog: * config/aarch64/aarch64-arches.def (V8_4A): Add RCPC2. * config/aarch64/aarch64-option-extensions.def (RCPC2): New flag. (RCPC3): Add RCPC2 dependency. * config/aarch64/aarch64.h (TARGET_RCPC2): Use new flag. gcc/testsuite/ChangeLog: * gcc.target/aarch64/cpunative/native_cpu_21.c: Add rcpc2 to expected feature string instead of rcpc. * gcc.target/aarch64/cpunative/native_cpu_22.c: Ditto. diff --git a/gcc/config/aarch64/aarch64-arches.def b/gcc/config/aarch64/aarch64-arches.def index 84782d55089650b5854c60497bc68f9564d6f90b..f182d3dc6c77bf63ab272ab1b5824c1523390e09 100644 --- a/gcc/config/aarch64/aarch64-arches.def +++ b/gcc/config/aarch64/aarch64-arches.def @@ -34,7 +34,7 @@ AARCH64_ARCH("armv8-a", generic_armv8_a, V8A, 8, (SIMD)) AARCH64_ARCH("armv8.1-a", generic_armv8_a, V8_1A, 8, (V8A, LSE, CRC, RDMA)) AARCH64_ARCH("armv8.2-a", generic_armv8_a, V8_2A, 8, (V8_1A)) AARCH64_ARCH("armv8.3-a", generic_armv8_a, V8_3A, 8, (V8_2A, PAUTH, RCPC, FCMA, JSCVT)) -AARCH64_ARCH("armv8.4-a", generic_armv8_a, V8_4A, 8, (V8_3A, F16FML, DOTPROD, FLAGM)) +AARCH64_ARCH("armv8.4-a", generic_armv8_a, V8_4A, 8, (V8_3A, F16FML, DOTPROD, FLAGM, RCPC2)) AARCH64_ARCH("armv8.5-a", generic_armv8_a, V8_5A, 8, (V8_4A, SB, SSBS, PREDRES, FRINTTS, FLAGM2)) AARCH64_ARCH("armv8.6-a", generic_armv8_a, V8_6A, 8, (V8_5A, I8MM, BF16)) AARCH64_ARCH("armv8.7-a", generic_armv8_a, V8_7A, 8, (V8_6A)) diff --git a/gcc/config/aarch64/aarch64-option-extensions.def b/gcc/config/aarch64/aarch64-option-extensions.def index b73324abbeb6145b5a2c26fdb22f41de9b6045d9..b929773eba176a391d6e9242067e4f63e4434637 100644 --- a/gcc/config/aarch64/aarch64-option-extensions.def +++ b/gcc/config/aarch64/aarch64-option-extensions.def @@ -159,7 +159,9 @@ AARCH64_OPT_FMV_EXTENSION("fcma", FCMA, (SIMD), (), (), "fcma") AARCH64_OPT_FMV_EXTENSION("rcpc", RCPC, (), (), (), "lrcpc") -AARCH64_OPT_FMV_EXTENSION("rcpc3", RCPC3, (RCPC), (), (), "lrcpc3") +AARCH64_OPT_FMV_EXTENSION("rcpc2", RCPC2, (RCPC), (), (), "ilrcpc") + +AARCH64_OPT_FMV_EXTENSION("rcpc3", RCPC3, (RCPC2), (), (), "lrcpc3") AARCH64_OPT_FMV_EXTENSION("frintts", FRINTTS, (FP), (), (), "frint") diff --git a/gcc/config/aarch64/aarch64.h b/gcc/config/aarch64/aarch64.h index 41430466b50bf223bf008c753d24f57570c1f2e5..3ed1930d3e4ac9f250219a43aa91cb8ed123f53c 100644 --- a/gcc/config/aarch64/aarch64.h +++ b/gcc/config/aarch64/aarch64.h @@ -427,7 +427,7 @@ constexpr auto AARCH64_FL_DEFAULT_ISA_MODE ATTRIBUTE_UNUSED /* The RCPC2 extensions from Armv8.4-a that allow immediate offsets to LDAPR and sign-extending versions.*/ -#define TARGET_RCPC2 ((AARCH64_HAVE_ISA (V8_4A) && TARGET_RCPC) || TARGET_RCPC3) +#define TARGET_RCPC2 AARCH64_HAVE_ISA (RCPC2) /* RCPC3 (Release Consistency) extensions, optional from Armv8.2-a. */ #define TARGET_RCPC3 AARCH64_HAVE_ISA (RCPC3) diff --git a/gcc/testsuite/gcc.target/aarch64/cpunative/native_cpu_21.c b/gcc/testsuite/gcc.target/aarch64/cpunative/native_cpu_21.c index c1d5896e1eb0b3b48ac0c1eeb95a74c4b6ec9e85..904cdf452263961442f3ecc31cd1b6563130f9c7 100644 --- a/gcc/testsuite/gcc.target/aarch64/cpunative/native_cpu_21.c +++ b/gcc/testsuite/gcc.target/aarch64/cpunative/native_cpu_21.c @@ -7,7 +7,7 @@ int main() return 0; } -/* { dg-final { scan-assembler {\.arch armv8-a\+flagm2\+lse\+dotprod\+rdma\+crc\+fp16fml\+jscvt\+rcpc\+frintts\+i8mm\+bf16\+sve2-aes\+sve2-bitperm\+sve2-sha3\+sve2-sm4\+sb\+ssbs\n} } } */ +/* { dg-final { scan-assembler {\.arch armv8-a\+flagm2\+lse\+dotprod\+rdma\+crc\+fp16fml\+jscvt\+rcpc2\+frintts\+i8mm\+bf16\+sve2-aes\+sve2-bitperm\+sve2-sha3\+sve2-sm4\+sb\+ssbs\n} } } */ /* Check that an Armv8-A core doesn't fall apart on extensions without midr values. */ diff --git a/gcc/testsuite/gcc.target/aarch64/cpunative/native_cpu_22.c b/gcc/testsuite/gcc.target/aarch64/cpunative/native_cpu_22.c index 4533a2bf5912dc609327b63164ba4577e98f9eec..feb959b11b0e383a5e1f3214d55f80f56d2605d4 100644 --- a/gcc/testsuite/gcc.target/aarch64/cpunative/native_cpu_22.c +++ b/gcc/testsuite/gcc.target/aarch64/cpunative/native_cpu_22.c @@ -7,7 +7,7 @@ int main() return 0; } -/* { dg-final { scan-assembler {\.arch armv8-a\+flagm2\+lse\+dotprod\+rdma\+crc\+fp16fml\+jscvt\+rcpc\+frintts\+i8mm\+bf16\+sve2-aes\+sve2-bitperm\+sve2-sha3\+sve2-sm4\+sb\+ssbs\+pauth\n} } } */ +/* { dg-final { scan-assembler {\.arch armv8-a\+flagm2\+lse\+dotprod\+rdma\+crc\+fp16fml\+jscvt\+rcpc2\+frintts\+i8mm\+bf16\+sve2-aes\+sve2-bitperm\+sve2-sha3\+sve2-sm4\+sb\+ssbs\+pauth\n} } } */ /* Check that an Armv8-A core doesn't fall apart on extensions without midr values and that it enables optional features. */ From patchwork Fri Oct 4 17:54:16 2024 Content-Type: text/plain; charset="utf-8" MIME-Version: 1.0 Content-Transfer-Encoding: 7bit X-Patchwork-Submitter: Andrew Carlotti X-Patchwork-Id: 1992945 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=arm.com header.i=@arm.com header.a=rsa-sha256 header.s=selector1 header.b=noSulDKK; dkim=pass (1024-bit key) header.d=arm.com header.i=@arm.com header.a=rsa-sha256 header.s=selector1 header.b=noSulDKK; 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 4XKx5d1LSGz1xtH for ; Sat, 5 Oct 2024 03:55:01 +1000 (AEST) Received: from server2.sourceware.org (localhost [IPv6:::1]) by sourceware.org (Postfix) with ESMTP id 31AD2385E003 for ; Fri, 4 Oct 2024 17:54:58 +0000 (GMT) X-Original-To: gcc-patches@gcc.gnu.org Delivered-To: gcc-patches@gcc.gnu.org Received: from EUR05-VI1-obe.outbound.protection.outlook.com (mail-vi1eur05on20625.outbound.protection.outlook.com [IPv6:2a01:111:f403:2613::625]) by sourceware.org (Postfix) with ESMTPS id 5C5FC385E827 for ; Fri, 4 Oct 2024 17:54:33 +0000 (GMT) DMARC-Filter: OpenDMARC Filter v1.4.2 sourceware.org 5C5FC385E827 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 5C5FC385E827 Authentication-Results: server2.sourceware.org; arc=pass smtp.remote-ip=2a01:111:f403:2613::625 ARC-Seal: i=3; a=rsa-sha256; d=sourceware.org; s=key; t=1728064476; cv=pass; b=qbTrW5EZXOTpSinTLqTWZL26RlMYB8PF0c81WdV78gBWQkVthR+PGUXI6UYc/RsVoxWiMD/eZDyr/gid3Yr1OjRnvq98WQHPQPo7O8t7b94BBo8cIOG+d3FTsDG7YtchGpBvl0+3BKAp4HzK+IVyLqhOAAURNjAHm1OW4cjWt6Y= ARC-Message-Signature: i=3; a=rsa-sha256; d=sourceware.org; s=key; t=1728064476; c=relaxed/simple; bh=Sxz3ZifBNPLYCmqDeKH/T6Jwb+TEueFRzdcFK/F/fMc=; h=DKIM-Signature:DKIM-Signature:Date:From:To:Subject:Message-ID: MIME-Version; b=Gk+MHi4V5b1yfr2rdTgkLiwhKRV4OYroUCrTEsv9WDYJjShNOarY/nJgP2D56ErFacuknIjKk9ytPWV16+j+XjA9OdkdECrHVHZ5z552OM4j/sPytvNd0Qecj+7+r1O1IixIJqwilPueQJOStulbeFDvRAzsDxVOHkRULoH8olY= ARC-Authentication-Results: i=3; server2.sourceware.org ARC-Seal: i=2; a=rsa-sha256; s=arcselector10001; d=microsoft.com; cv=pass; b=Oj9j27ezrY2iuHaudqaQMk1zmhkfAkfdxN5JnLGH9vifB7F3rKgwCkytB9samo9+u5x+0fmp1aZEjOL3LFa6oStwYm8SrShmSgGJiJ0iOZNs4SDKJ4hNcaLYOoYL/n8+KIEercBwggchslQejvFj9OgkICO2Arwj7qEbZ+WheUrXDECrYRSFPP1IP+/U2Gl6pYub281LZdRRBS6SiL1dpuQ4Cel1fcIzw06eiCvbhjMjxA1ygwr1qLKXqcofWH7l4IhTY3HxQLr+SRLAVAJ2lem3ankSxZ0OzZtMwvYlICs9cEwnvIMlVEBykG3PSVGApXNEcmYDZ0ZkPzVQZLO/PA== ARC-Message-Signature: i=2; a=rsa-sha256; c=relaxed/relaxed; d=microsoft.com; s=arcselector10001; 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=loUvVV6DvoO4k9NHVaYjsebH0om4q449E/slIPBsdJQ=; b=WgldrAcWJbq4kBvVTpZNTOsCMHJtAxR6pQ1Afpz39Sb1LiC03fEaj5cKKwiZHJ12ZNCYXFfki41P7Fd6r/ZieVEcOK5Oyah9duMl9BWu5Lyz8MsFryrl1HFm1ynEYQtfaGeXJzTkcGhO0dNc2ygdrGvwqC3erTjzsVJ9VmuU+6/ExLlP03j5dRj9Np1f0uASuRwQNWSW8hpA6TBHSZHCawhcbGFtE3wRhKGHHe4tUhyTFohlaWrRPoIp+Auv4ObCbrTni8Eo0FzQOzZBtNCI7sBwE2NRbMNPPZwlvkrnPUHyit9cTgVjvbDdamlNoZ4zJi8JWFSQrpV9TkYonJX+xg== 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=arm.com; arc=pass (0 oda=1 ltdi=1 spf=[1,1,smtp.mailfrom=arm.com] dkim=[1,1,header.d=arm.com] dmarc=[1,1,header.from=arm.com]) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=arm.com; s=selector1; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-SenderADCheck; bh=loUvVV6DvoO4k9NHVaYjsebH0om4q449E/slIPBsdJQ=; b=noSulDKKv5Kv4SnzCaAa50fW3XUSBGFTJ7fr7IW2BrYLbs/23jIY7eXZ1jy4jJI3deDG06RlH8D4NsaR45rgLKhWHncDOwcK4dYmBd5sRAWCz56k78WzRIA/bQ3kZCaI8FbXxYoO+PXoU+K78wflrg0tidO8CuHUuSztoAQRpjg= Received: from AM5PR04CA0020.eurprd04.prod.outlook.com (2603:10a6:206:1::33) by VI0PR08MB11198.eurprd08.prod.outlook.com (2603:10a6:800:252::11) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.8026.16; Fri, 4 Oct 2024 17:54:27 +0000 Received: from AM1PEPF000252DF.eurprd07.prod.outlook.com (2603:10a6:206:1:cafe::dc) by AM5PR04CA0020.outlook.office365.com (2603:10a6:206:1::33) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.8026.18 via Frontend Transport; Fri, 4 Oct 2024 17:54:27 +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=arm.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 AM1PEPF000252DF.mail.protection.outlook.com (10.167.16.57) with Microsoft SMTP Server (version=TLS1_3, cipher=TLS_AES_256_GCM_SHA384) id 15.20.8026.11 via Frontend Transport; Fri, 4 Oct 2024 17:54:26 +0000 Received: ("Tessian outbound 2f6d3313e4d6:v473"); Fri, 04 Oct 2024 17:54:26 +0000 X-CheckRecipientChecked: true X-CR-MTA-CID: 2135209eb20ab8d3 X-TessianGatewayMetadata: dojjOZoPBBVRTOZatZL8ICGVAKhL7Wv3q8KhUVnVue1onp/nDglA8oDJyXg/jE5DixnhpOF00V3vLt6J4LeMpk/0E1cpJ0Gf6BGe/Yt/M4qG9Q2DiSxCmKlAHbJ5JMxzYYBDBr9avbTveBKnAqFuPeMHAxR6fgutTd9AMRWKk/pJOrAlKNBgWvcmNhijEiWa X-CR-MTA-TID: 64aa7808 Received: from L6f6cba83118a.2 by 64aa7808-outbound-1.mta.getcheckrecipient.com id EFA9FE0A-834A-41F7-9FB5-C0BEC77C09C0.1; Fri, 04 Oct 2024 17:54:20 +0000 Received: from EUR02-DB5-obe.outbound.protection.outlook.com by 64aa7808-outbound-1.mta.getcheckrecipient.com with ESMTPS id L6f6cba83118a.2 (version=TLSv1.2 cipher=ECDHE-RSA-AES256-GCM-SHA384); Fri, 04 Oct 2024 17:54:20 +0000 ARC-Seal: i=1; a=rsa-sha256; s=arcselector10001; d=microsoft.com; cv=none; b=OxURkXGbe0RGhpeG8MdmJcaBrZuwmGKvmbliah2W38DM5S529ybrlnMb1iiJBDhjllBHgGrXvvZKtAhtuwWv2x9DSnqMBivN4PCuiP+KrHkYP/jeHBljSs7UQoSfhr2lbAyH5DNn7gYK23fILEjWpQa3tqG9GMUhDsMiMWHwBKp+RP63l2Jg91FcEWHrw2OBW131FG+01gkGlKkoZ/DvwGuLUHnqdCDVhScpu4KYvEC0Q2FCirDnC1inHHg5RBqoIrnGP7Z+NTp+etXDDLRQXb9JvU6FBQa8rnJaHXoWsvi0j0gnKvp0lOO/WTpMuzvnBwnbuSTgarAM5NnoxUsCtw== ARC-Message-Signature: i=1; a=rsa-sha256; c=relaxed/relaxed; d=microsoft.com; s=arcselector10001; 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=loUvVV6DvoO4k9NHVaYjsebH0om4q449E/slIPBsdJQ=; b=UsPOPb30aJLkBgl10o24AE/MdfW5KFse5n1r0kIoovqBr2KaPTeoBCx521ScqEzZT5uigLxhLguQYkLyiQbelF20knSjcUtERSObdltogrV5O9EGBJ2cU2cR9MYHbWGVW8pUuMlM17B+DWp3L8LkVVxs7mNAR9kyrWvVg2X8KboxTBco04hLDrKfXl4q0EoUE0hsZKhSoPzsBCqX+6NfkE5NmNDOWj1FGDAmdLkO5Nm6HdBTbLyGJis2Gh8gVdRNI+wnyzLsEyVzlwe9/QhVpLsboDbOqKkm3NhNUQMxgSuS2i50r/p+/cMqytZ0cLh38StFifFyrd0ZpJwqVMh/lg== ARC-Authentication-Results: i=1; mx.microsoft.com 1; spf=pass smtp.mailfrom=arm.com; dmarc=pass action=none header.from=arm.com; dkim=pass header.d=arm.com; arc=none DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=arm.com; s=selector1; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-SenderADCheck; bh=loUvVV6DvoO4k9NHVaYjsebH0om4q449E/slIPBsdJQ=; b=noSulDKKv5Kv4SnzCaAa50fW3XUSBGFTJ7fr7IW2BrYLbs/23jIY7eXZ1jy4jJI3deDG06RlH8D4NsaR45rgLKhWHncDOwcK4dYmBd5sRAWCz56k78WzRIA/bQ3kZCaI8FbXxYoO+PXoU+K78wflrg0tidO8CuHUuSztoAQRpjg= Authentication-Results-Original: dkim=none (message not signed) header.d=none;dmarc=none action=none header.from=arm.com; Received: from DU0PR08MB8255.eurprd08.prod.outlook.com (2603:10a6:10:411::9) by AS8PR08MB9527.eurprd08.prod.outlook.com (2603:10a6:20b:61d::7) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.8026.8; Fri, 4 Oct 2024 17:54:19 +0000 Received: from DU0PR08MB8255.eurprd08.prod.outlook.com ([fe80::cbc8:c020:6a1b:d27a]) by DU0PR08MB8255.eurprd08.prod.outlook.com ([fe80::cbc8:c020:6a1b:d27a%5]) with mapi id 15.20.8026.017; Fri, 4 Oct 2024 17:54:18 +0000 Date: Fri, 4 Oct 2024 18:54:16 +0100 From: Andrew Carlotti To: gcc-patches@gcc.gnu.org Cc: Richard Sandiford Subject: [PATCH 7/8] aarch64: Add new +wfxt flag Message-ID: References: Content-Disposition: inline In-Reply-To: X-ClientProxiedBy: LO4P265CA0100.GBRP265.PROD.OUTLOOK.COM (2603:10a6:600:2bc::12) To DU0PR08MB8255.eurprd08.prod.outlook.com (2603:10a6:10:411::9) MIME-Version: 1.0 X-MS-TrafficTypeDiagnostic: DU0PR08MB8255:EE_|AS8PR08MB9527:EE_|AM1PEPF000252DF:EE_|VI0PR08MB11198:EE_ X-MS-Office365-Filtering-Correlation-Id: dc937c81-fcae-4bce-b837-08dce49d96c1 x-checkrecipientrouted: true NoDisclaimer: true X-MS-Exchange-SenderADCheck: 1 X-MS-Exchange-AntiSpam-Relay: 0 X-Microsoft-Antispam-Untrusted: BCL:0;ARA:13230040|366016|376014|1800799024; X-Microsoft-Antispam-Message-Info-Original: dVwsmwNqAtA9pPpgx1RLnK8Y3lsyb8YhOuin9JIPsJq7wv+fUtiSaaR7ZyFdONVNKvWEkhF+ue1rHzeDMZRYIcHkULERpov1CeeNiVYCfZBTyDWTYILD56fDgX30C8caKuK0o+Z7E/pbRjbuIkX96slLoazQvBc2NWXeyXbr781f3ESNpLUgnerOhiiFXK36scyS6bz4zeF5EvwsExm09O3oJcoAzOyDYkxGbIafQrc81uyNjl5WzxiBZotuFdrlbmVQvAoHnDSSRpjXyCSfocSrCbsz/FbMRi1vzIapuIn3FHi1XsECLd6+ZL+I4gPFftHVU3vbgqve59/ePr6OSbQhDyMJTTvQiBl7AczAYiJyTI3A4uVtK6Z0lr6DquxBeK2mJKVDtUJfUXTP4eD/2DCfGaVxnME4ZJEVKpxDrjIVEjQ8NQrmttzlyCsBozJQcaRsJOzYSIej8yLEpnNBfqhezmKl7bcmZtssUDgWXUTuXMN+80lAx+Snc3kPqvOsmu4OeHyLsSztYMIiHE6rPDfv6EQS8w61a0lKP1V1x5rtL5TPtKqj+NUEJxSVlfrqYxj4TLFgr4PVF+HSu6VQOGE1CCHbjV6S7WE44yFkrZUdn6T1HSMG2qhriHNjKharnrRwPF2M2m85GTP6asCw4NNu6wAHByG6D0XvBxdKbxBvMMGzfEg1zraPLR2rYaLlotDfcEfEKVj7cCoXX3MmH5HFGlUn28fj3ZBFXoIhj6bbqbaX0653z/qONonUZvCtGSLK0THL+8YCoW867lgbL/6ipOuVMcRHsG1FJUNQ4WQgKMlU2nK4HMADpIxwJnJS0smPUQ4OlGP2wLDjX5hVcIAgfTZyGEStos57jQsDetFUM+mfe6ptHT0Mmit0p/YNO9ytsaY+/bSsSesp1hZWsk4c4YDfnjriMHGEwGP6Z14mUVNeAF366VTsc1Ma9xEnv8vtD16PYYT94v5mImWueQ6/s0vLyV52UcbhjUzMpsxSXKnIfEW64LN5oMtnRjgFTH05EafJU1oCG191ADO9ek/zIhaXJvCeeC+QVSW59kVzcma+opsDEjytWJpjL5gVIUVQy8sn+3t4cyZNL3FSYTlohcYJnKy6vn2KJbuBaDENdSrDrpN5+1k8GKyVbOoczb3vNQ2Ne5xXvgNyMrCKGrn4XXMPL+BnAUMdCVlFB5K283OMvHbSNoEmOdl33lDWbf0y2eDuCVbZTvipZdBYuH85mzCO1T7mhWi7AdltQs04en1yZZcU+rzpl0sp87pTeyNNStugMofYCuoZdyoJYQ== X-Forefront-Antispam-Report-Untrusted: CIP:255.255.255.255; CTRY:; LANG:en; SCL:1; SRV:; IPV:NLI; SFV:NSPM; H:DU0PR08MB8255.eurprd08.prod.outlook.com; PTR:; CAT:NONE; SFS:(13230040)(366016)(376014)(1800799024); DIR:OUT; SFP:1101; X-MS-Exchange-Transport-CrossTenantHeadersStamped: AS8PR08MB9527 Original-Authentication-Results: dkim=none (message not signed) header.d=none;dmarc=none action=none header.from=arm.com; X-EOPAttributedMessage: 0 X-MS-Exchange-SkipListedInternetSender: ip=[2603:10a6:10:411::9]; domain=DU0PR08MB8255.eurprd08.prod.outlook.com X-MS-Exchange-Transport-CrossTenantHeadersStripped: AM1PEPF000252DF.eurprd07.prod.outlook.com X-MS-PublicTrafficType: Email X-MS-Office365-Filtering-Correlation-Id-Prvs: da4b6d41-747f-41d6-e290-08dce49d91e8 X-Microsoft-Antispam: BCL:0; ARA:13230040|82310400026|35042699022|376014|1800799024|36860700013; X-Microsoft-Antispam-Message-Info: QngI+X0gqC9RLJBMGtKvWN+c/maNt9qYHY7uV+vw3sUzDdT15oz8PScRPpTeGrPxS3aezk6RKLobRzZV1VjhVxbpggfMDewOL/L651B88SFZSAwanEZLmHkrz90etDJmlJlhgybRicTFzdATy8koc8noDhFyHnN1X6gf7BAAbk4cmVMVESwfo9JKLXTNjtTB62P8dMzA9GnT4Af9pLt/owAryijxdUCyH6J97jbTpKiP6y+DVrd90FVqh0ZooyRU5UqpJHEUHDRkl+4YdDyok8oQmg74++8symMK9oR9wMk80wHEk327an9B7+Gts7PJ0hqhOCKujeYWeU4H/r0K7lP8oNlR1VsdAgkvjJGoqFvbDvFicMnXAYXYgTX2Hq61mW9+LxTfbvXLCLvCJRAOp9EThZMbcyVippEMOBf9x8zmqDkAY5KS/vt3Z1rzY026Xn3B8GeyfbBO2SBqLawH5Jl/ha1fyWH9nh+G9FDO1IkwdySeZG4y0bMWBewxN7+RgJZuCmcfp4zNMUBjzkIGprDuZuSyGjR89eKcMa8P3sysLj+335H4A7An1OSJiBwPRZiXnOj4H+DQWXC0++AgX1A7sazXc+0t60QlJAyJOjqAk0JfgDAkUlOoN6fjyHuaDsj4UFqIWyA7F0qy26wLQXgRHX8ObGYvEnpE92mdkSE3kKCJGTOjjz+i0RkTyUItltzLBHLclTlYXSyEeuLJxfggDNgB9pQwP2MKY27nfjNmHCF2M4gIjILqsE5JHQIjplItpTIAYjr+2LZqhAmPmRmtt6Rcg0Kn8bmLD+KlyWoxoTx4sPm4C6tbHI3OH3tPxfX7BWCf0gKLxGAF+7boxm8aoFdoN9RfiBCQKeXmNo6QVhqSRE0N6nrM1uEYG6iTiqHCc5rLODCoVcVlnp6RTJXjtqizlyIvYUqpU/hEA4U1Oje72mGLyEn0sQwHrfF0BZtKpXXnNVz4UTwZQaHXn9z/6sjBvAbu7IWfZMc8qEBzubtmKLE7axjnlmH/Ue/aNVz9hrlz5e9xfc5jcXzoWdAiYTSq9wXXLndODgNyLhU01YkYypozdp+MqL6rUQgsd4oC6rQdbxAYV4GRFY3aCaSC1Hk5Wu5SC/jO327beF5bnBHee1d71/uJArpHxElqEQDY4L8X1SVr3Kc9sfJRg4+0Fqkj5DEusy0kwdQNIVPZrm0wFPEW1ktKZLSSCN0d/epSEXf0DXRPZZ2GbZY10jpsNhnnBsqJ2gVZzzjFwdcbS/dgtcvJ7KJJazxCbx0vyTXV9ae15o/L07VB+ptFHBrESb9ly3VhQEtyzb1Xhb6oI5z9O0555BTUhoJDqejTznUNMRAXsSbJIE2O2MgLp4kJbYyrgbKsVwaCvEhgxh8= 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:(13230040)(82310400026)(35042699022)(376014)(1800799024)(36860700013); DIR:OUT; SFP:1101; X-OriginatorOrg: arm.com X-MS-Exchange-CrossTenant-OriginalArrivalTime: 04 Oct 2024 17:54:26.9575 (UTC) X-MS-Exchange-CrossTenant-Network-Message-Id: dc937c81-fcae-4bce-b837-08dce49d96c1 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: AM1PEPF000252DF.eurprd07.prod.outlook.com X-MS-Exchange-CrossTenant-AuthAs: Anonymous X-MS-Exchange-CrossTenant-FromEntityHeader: HybridOnPrem X-MS-Exchange-Transport-CrossTenantHeadersStamped: VI0PR08MB11198 X-Spam-Status: No, score=-12.2 required=5.0 tests=BAYES_00, DKIM_SIGNED, DKIM_VALID, DKIM_VALID_AU, DKIM_VALID_EF, FORGED_SPF_HELO, GIT_PATCH_0, SPF_HELO_PASS, SPF_NONE, TXREP, 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 GCC does not currently emit the wfet or wfit instructions, so this primarily affects the flags passed through to the assembler. gcc/ChangeLog: * config/aarch64/aarch64-arches.def (V8_7A): Add WFXT. * config/aarch64/aarch64-option-extensions.def (WFXT): New flag. diff --git a/gcc/config/aarch64/aarch64-arches.def b/gcc/config/aarch64/aarch64-arches.def index f182d3dc6c77bf63ab272ab1b5824c1523390e09..fa06377dda089c8a89628bc4cc66d54510346053 100644 --- a/gcc/config/aarch64/aarch64-arches.def +++ b/gcc/config/aarch64/aarch64-arches.def @@ -37,7 +37,7 @@ AARCH64_ARCH("armv8.3-a", generic_armv8_a, V8_3A, 8, (V8_2A, PAUTH, R AARCH64_ARCH("armv8.4-a", generic_armv8_a, V8_4A, 8, (V8_3A, F16FML, DOTPROD, FLAGM, RCPC2)) AARCH64_ARCH("armv8.5-a", generic_armv8_a, V8_5A, 8, (V8_4A, SB, SSBS, PREDRES, FRINTTS, FLAGM2)) AARCH64_ARCH("armv8.6-a", generic_armv8_a, V8_6A, 8, (V8_5A, I8MM, BF16)) -AARCH64_ARCH("armv8.7-a", generic_armv8_a, V8_7A, 8, (V8_6A)) +AARCH64_ARCH("armv8.7-a", generic_armv8_a, V8_7A, 8, (V8_6A, WFXT)) AARCH64_ARCH("armv8.8-a", generic_armv8_a, V8_8A, 8, (V8_7A, MOPS)) AARCH64_ARCH("armv8.9-a", generic_armv8_a, V8_9A, 8, (V8_8A, CSSC)) AARCH64_ARCH("armv8-r", generic_armv8_a, V8R , 8, (V8_4A)) diff --git a/gcc/config/aarch64/aarch64-option-extensions.def b/gcc/config/aarch64/aarch64-option-extensions.def index b929773eba176a391d6e9242067e4f63e4434637..9781d48f63778d186b66427bae7deb2c01e14107 100644 --- a/gcc/config/aarch64/aarch64-option-extensions.def +++ b/gcc/config/aarch64/aarch64-option-extensions.def @@ -220,6 +220,8 @@ AARCH64_OPT_EXTENSION("pauth", PAUTH, (), (), (), "paca pacg") AARCH64_OPT_EXTENSION("ls64", LS64, (), (), (), "") +AARCH64_OPT_FMV_EXTENSION("wfxt", WFXT, (), (), (), "wfxt") + AARCH64_OPT_EXTENSION("sme-f64f64", SME_F64F64, (SME), (), (), "") AARCH64_FMV_FEATURE("sme-f64f64", SME_F64, (SME_F64F64)) From patchwork Fri Oct 4 17:54:39 2024 Content-Type: text/plain; charset="utf-8" MIME-Version: 1.0 Content-Transfer-Encoding: 7bit X-Patchwork-Submitter: Andrew Carlotti X-Patchwork-Id: 1992947 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=arm.com header.i=@arm.com header.a=rsa-sha256 header.s=selector1 header.b=Y0Z7+gf8; dkim=pass (1024-bit key) header.d=arm.com header.i=@arm.com header.a=rsa-sha256 header.s=selector1 header.b=Y0Z7+gf8; 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 4XKx79707Nz1xsn for ; Sat, 5 Oct 2024 03:56:21 +1000 (AEST) Received: from server2.sourceware.org (localhost [IPv6:::1]) by sourceware.org (Postfix) with ESMTP id CCF04385DDFF for ; Fri, 4 Oct 2024 17:56:19 +0000 (GMT) X-Original-To: gcc-patches@gcc.gnu.org Delivered-To: gcc-patches@gcc.gnu.org Received: from EUR05-VI1-obe.outbound.protection.outlook.com (mail-vi1eur05on20625.outbound.protection.outlook.com [IPv6:2a01:111:f403:2613::625]) by sourceware.org (Postfix) with ESMTPS id 0E1A0385EC18 for ; Fri, 4 Oct 2024 17:54:54 +0000 (GMT) DMARC-Filter: OpenDMARC Filter v1.4.2 sourceware.org 0E1A0385EC18 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 0E1A0385EC18 Authentication-Results: server2.sourceware.org; arc=pass smtp.remote-ip=2a01:111:f403:2613::625 ARC-Seal: i=3; a=rsa-sha256; d=sourceware.org; s=key; t=1728064496; cv=pass; b=pXLlNW+NmTdt4Rqg7/BqJ49wiCfF8zX5OQoO2DT39GhLmFpWuhObeKwaGBgVyxXAPhW6/2l7UDB05uhxSX4ouNv6TIDlwW8PbxA8vFSOFnfAultFNYm4Ea+LsOjJRknJm4+wtLaFtfsl2iGUXAi1C8L+GD4SwWGPfwNdFrj41eM= ARC-Message-Signature: i=3; a=rsa-sha256; d=sourceware.org; s=key; t=1728064496; c=relaxed/simple; bh=TXmcEfk1VqTXVmHUgXxzkl9KBWHXV4OOnxuXeEABFws=; h=DKIM-Signature:DKIM-Signature:Date:From:To:Subject:Message-ID: MIME-Version; b=ov/KTvvq6n0IpIYTNKZ2OuHD6gS0JajUK7EUw8gehNwCxegDNnkMoLw/G1bDMD4/2qi1yV+giGDPV8eCmqmiPWKQn8sajSHK5LPYu7gPdF6sBkt2bTfUMZQxuw5doQua4lSbpOZj4IvQ21A4jSYLgvAZtvKfxrL3N41NeMbOGR4= ARC-Authentication-Results: i=3; server2.sourceware.org ARC-Seal: i=2; a=rsa-sha256; s=arcselector10001; d=microsoft.com; cv=pass; b=M+76CGCQJ8ABduvP/zaPpi9aYV0kx/YgGO8JJ81ZkCVIRAyIDiL3epbwM0nTpChW/fpvV5H+lC20ZMuSPRJVVDxDzq+DSOAKCWnn0vKgaE0O0pT8sJcCXSb0Ke7KT7inFdNelMhKXEPoZ2PtODUp7InQQ8+CGSsb7Pl+Q87Lxdsk858Ebkit5hfjpfcfOBuARu1gQ2mj+UsWP/eAgwkL0EbXGLyNwudpqFlJ6h1EMukSZCAiapEDlzndclcktSELPRS/gP7H4bOWmZWuJ5Fcss2Ftq4+s0gGh39pHPksQeqdRU7hEQRtx7JQNNEqwNBlASK1a8xbVLnx8qS+XDb8JA== ARC-Message-Signature: i=2; a=rsa-sha256; c=relaxed/relaxed; d=microsoft.com; s=arcselector10001; 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=YgTt8/wGfcp15VLSUFh7N3mpI8pwQQP83mi9rcScGNQ=; b=DfoPl3OMrFAGmpkOQY0IO2xy1iawLHs76dM/RI/pN/v+wiZo3uftWmU+zz6bekBzLek3m1hAYRvC0w30UDl3rNrmcrOza+EJlCuo9gI0zAIEwEHWhCBLYONwcsxjbFpDXNmnxUyL7v1zGyHuXcLOFaWfKRtH/+kbSqYLH/EhvoYw53EZEmUuU5bi9Gf1mzA9/lzL2SinilfFV96QUWNzPFNURiMnfJ4ZCtqJ1NSuPVzbaPZ07Aa0euJ/GIawCUoKVWj57ru0NAS6SLM3OW4IISXlumyQtjOJFhx+I2b/CDUOPoxWsWVrGXIuHKk/vwqQcSsimLARGmYdiMyckKTNIw== 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=arm.com; arc=pass (0 oda=1 ltdi=1 spf=[1,1,smtp.mailfrom=arm.com] dkim=[1,1,header.d=arm.com] dmarc=[1,1,header.from=arm.com]) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=arm.com; s=selector1; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-SenderADCheck; bh=YgTt8/wGfcp15VLSUFh7N3mpI8pwQQP83mi9rcScGNQ=; b=Y0Z7+gf8RxtuCMUl9BESwWizO4Z1dFP0BBd3H1LooACnx050OPFASQSucmssMHuZicuIjrwyRVQ6t4S450lXbYjqNXGFCalg7XiwdExHQSAiACpee+F0JuNIuCoJ0fFXTIbAiptgaoxZgUYq777SdUlGU/Gba57jhEuYpzfJ3P8= Received: from DUZPR01CA0102.eurprd01.prod.exchangelabs.com (2603:10a6:10:4bb::9) by AM8PR08MB6515.eurprd08.prod.outlook.com (2603:10a6:20b:369::18) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.8026.18; Fri, 4 Oct 2024 17:54:51 +0000 Received: from DU2PEPF00028D05.eurprd03.prod.outlook.com (2603:10a6:10:4bb:cafe::a2) by DUZPR01CA0102.outlook.office365.com (2603:10a6:10:4bb::9) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.8026.17 via Frontend Transport; Fri, 4 Oct 2024 17:54:51 +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=arm.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 DU2PEPF00028D05.mail.protection.outlook.com (10.167.242.165) with Microsoft SMTP Server (version=TLS1_3, cipher=TLS_AES_256_GCM_SHA384) id 15.20.8026.11 via Frontend Transport; Fri, 4 Oct 2024 17:54:49 +0000 Received: ("Tessian outbound 5b65fbeb7e07:v473"); Fri, 04 Oct 2024 17:54:48 +0000 X-CheckRecipientChecked: true X-CR-MTA-CID: 83ab28cbcd97a005 X-TessianGatewayMetadata: T8fd+RZ1y7T/BAGNdvjqjIK37rFegGNMdAYIyc/d3ODikUMpmfTL1sc9g3Oey7MjnSxX830EaPIrWJRAH9odwKY4NTBSLDLoa/kIA+3DZD4UMpMVmyXqjyJj4KZQXt5bhN/0pXjAUvbpjxIQrgjitdp5Bx35mcjYpmYPdLLgoXdrHgQuvnphWy9mOh1VBKGO X-CR-MTA-TID: 64aa7808 Received: from L801c3eb204d3.2 by 64aa7808-outbound-1.mta.getcheckrecipient.com id 18D57136-0AA9-4112-8515-75512E7ADB6E.1; Fri, 04 Oct 2024 17:54:43 +0000 Received: from EUR02-AM0-obe.outbound.protection.outlook.com by 64aa7808-outbound-1.mta.getcheckrecipient.com with ESMTPS id L801c3eb204d3.2 (version=TLSv1.2 cipher=ECDHE-RSA-AES256-GCM-SHA384); Fri, 04 Oct 2024 17:54:43 +0000 ARC-Seal: i=1; a=rsa-sha256; s=arcselector10001; d=microsoft.com; cv=none; b=vFjHk01+G8WoCkw3jOxjEDEFduAIwf2OgCWHV1kt+KWZtZSEnhsyj9YxU8rD5Dsj9I+3MfLd6j30PMbqh/JDn2n2ujjOM8yHP2aX4/B349zBQr8kVRS8QNbXVaEh69UQH9t+s8yfDlCmB9HHrT0eDSToqNRxA6YKgMmUG21ZCH3qW+jIlquvddAcHBmOfwXKC8YpyG2atoBuwc13TSBAtlF8XKANoK4OXkspix0zIUdDBdE9FNobkVO5itXU+Ln8BmYeDesdrn8+ERESABfqUUSkQ/LoKSfwBawYvvw/UJp3X3SBB6OOg/BthGU5nTB0AtVnMIBSl4pW8IsSq3+4EA== ARC-Message-Signature: i=1; a=rsa-sha256; c=relaxed/relaxed; d=microsoft.com; s=arcselector10001; 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=YgTt8/wGfcp15VLSUFh7N3mpI8pwQQP83mi9rcScGNQ=; b=youn8B4SS8R2jw33qiFX7uAXumjY7J8mvId99zmPYzIhxNGlkw4nILmePm93A27/5XTi6PZrHEm9hVqRqlw0ERJtZqAAwGBMP1Dc8WJOCAH1akuIT1p6dYMTiI1na3q9ax/2xK9dbYaRJE59rdT5v0mK53lAwAxyicKa6ypR3k2v989aQ/XBuJT1beIcOhCgxZgz4bQi7W/RtbdehgCBDp6xBxBZetRmmBbJYkK1lZTta4gdivqujAGi41RoyQM+F9bFdTmJ0zkU0wZAfdviKWEU981pfF1/3oaNAyphmofXa9251TCwIyOlxZdwJGKQYGkAnGf5Qt85Z1HkTjIGfg== ARC-Authentication-Results: i=1; mx.microsoft.com 1; spf=pass smtp.mailfrom=arm.com; dmarc=pass action=none header.from=arm.com; dkim=pass header.d=arm.com; arc=none DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=arm.com; s=selector1; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-SenderADCheck; bh=YgTt8/wGfcp15VLSUFh7N3mpI8pwQQP83mi9rcScGNQ=; b=Y0Z7+gf8RxtuCMUl9BESwWizO4Z1dFP0BBd3H1LooACnx050OPFASQSucmssMHuZicuIjrwyRVQ6t4S450lXbYjqNXGFCalg7XiwdExHQSAiACpee+F0JuNIuCoJ0fFXTIbAiptgaoxZgUYq777SdUlGU/Gba57jhEuYpzfJ3P8= Authentication-Results-Original: dkim=none (message not signed) header.d=none;dmarc=none action=none header.from=arm.com; Received: from DU0PR08MB8255.eurprd08.prod.outlook.com (2603:10a6:10:411::9) by AS8PR08MB9527.eurprd08.prod.outlook.com (2603:10a6:20b:61d::7) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.8026.8; Fri, 4 Oct 2024 17:54:41 +0000 Received: from DU0PR08MB8255.eurprd08.prod.outlook.com ([fe80::cbc8:c020:6a1b:d27a]) by DU0PR08MB8255.eurprd08.prod.outlook.com ([fe80::cbc8:c020:6a1b:d27a%5]) with mapi id 15.20.8026.017; Fri, 4 Oct 2024 17:54:41 +0000 Date: Fri, 4 Oct 2024 18:54:39 +0100 From: Andrew Carlotti To: gcc-patches@gcc.gnu.org Cc: Richard Sandiford Subject: [PATCH 8/8] aarch64: Add new +xs flag Message-ID: <3794c82e-2269-d12d-3557-94aac3421377@e124511.cambridge.arm.com> References: Content-Disposition: inline In-Reply-To: X-ClientProxiedBy: LO2P265CA0398.GBRP265.PROD.OUTLOOK.COM (2603:10a6:600:f::26) To DU0PR08MB8255.eurprd08.prod.outlook.com (2603:10a6:10:411::9) MIME-Version: 1.0 X-MS-TrafficTypeDiagnostic: DU0PR08MB8255:EE_|AS8PR08MB9527:EE_|DU2PEPF00028D05:EE_|AM8PR08MB6515:EE_ X-MS-Office365-Filtering-Correlation-Id: df419d4c-3ceb-4151-da55-08dce49da3ec x-checkrecipientrouted: true NoDisclaimer: true X-MS-Exchange-SenderADCheck: 1 X-MS-Exchange-AntiSpam-Relay: 0 X-Microsoft-Antispam-Untrusted: BCL:0;ARA:13230040|366016|376014|1800799024; X-Microsoft-Antispam-Message-Info-Original: W6PQ0if2kLtqRRtWR9mTUz1BVxhxuNyOS3qAJWF3qa1K4f6pGPJ/qm3MV9yP9jyMnB5GXRJqPSbkuQau2/I/+1WaKmkMJZaCf5HPyZFOF3kapBtnIdgFANu1IvxYvp34K8PyWy3kPl90l9V/VMLMqHPX/xgW5w/xujn2E9k8U5hQSsl8un/L4e+0NJ6Rtk6jG3hdMq3vXr9IFFpHOH880IhAocPtjLG6HYqa5VttTLCRemQKwokngviXZVWsiqiUIpdjphY39BZM31zN6qVDhJiC0Zb6tjPouHlXXvdR4sOZT1k8pcPdtZWPOYCT7faM1eKTM7SZCVyR6nMaPcV/zpYVQCL/sk0aA/Xc/Rex3KXbskaBbgvYJNAY6rjK/yLCPwqBfwI8fYzjmsslPQiO2OCR5Qfs1xpSMVCSExitToBStV2VrXHOUv/hUDQcGpp+hkYOb1yBzeTap6fuPy+Qph0nvkNNhjjYn6vI5YZToJwybR4RgMpwEdhY582b9jBp06dj3zsCsyepMeLE8tSqdRo5AvAg0VDw/XUUhNz/DWH4I0z3SOMojVGr40SluUHFMHW8xtMnaxC1Yp+AKBCDhBAHZ9M4vhbYrdYnhHOV/Mq5PlYEeV3f+2O8+ViVuy7DjZS9iWdABj8r7VW5w9ahlPHgylqiLvRTlMV9lODddHINABba9CCxhqMIyQFr6G+Mu4tz34b9xmkQaZ7syWlr6OmJSr4IhYe2GeOsAcYusYL+8YwckWNCRiTOtBKeCt0NLpFANrtdeGK/r3J3DLF740Pw0ooAOqUvNiY4kIezxoz6Gmpj6vX5V1mWYZq2h1to/H3SPqTcSAPyBPn0xDZFP+ipAf0Ulp36I5EbaCsDDqu5I0npJQDtDBCcrA5QeoLQe04FoMuxV2wWzKGrz3mXCOrTKBYMnCpKWkqIPT6gIgzCuSJ+qbW2SDpzy3Hj9AJoXvz2YTY3D0Ty2PfS1hvesnruCn1D0ANgMYf79GG2me7KVhKfh+Cvll46sTQt1RHa6QAS1xjZ1RvZ6kq2rkhtu+qgoeFVoyU5hUhxTWb3qDPyaeWS3QePSfr7pe1isi2I5C3LssF7GmbgYKXCoU5ckQvhqgIcOfZa1ws35i+u78AhWHsaCDOyLuuFY8kUW7we7h1WIxnDOTMNR9CbNsJ1UdfDNyT1BLGUfFcVlPgm6l5Q8KGaMwps5ESGUBofoCNLZiiszT8W/j6LmHqTUF9QszVLZKXDZFsY8QYNWgLq6klZcYdpJhLHvrcoW1EenbXjGzj2o3aGIL9ri35N1SvMyw== X-Forefront-Antispam-Report-Untrusted: CIP:255.255.255.255; CTRY:; LANG:en; SCL:1; SRV:; IPV:NLI; SFV:NSPM; H:DU0PR08MB8255.eurprd08.prod.outlook.com; PTR:; CAT:NONE; SFS:(13230040)(366016)(376014)(1800799024); DIR:OUT; SFP:1101; X-MS-Exchange-Transport-CrossTenantHeadersStamped: AS8PR08MB9527 Original-Authentication-Results: dkim=none (message not signed) header.d=none;dmarc=none action=none header.from=arm.com; X-EOPAttributedMessage: 0 X-MS-Exchange-SkipListedInternetSender: ip=[2603:10a6:10:411::9]; domain=DU0PR08MB8255.eurprd08.prod.outlook.com X-MS-Exchange-Transport-CrossTenantHeadersStripped: DU2PEPF00028D05.eurprd03.prod.outlook.com X-MS-PublicTrafficType: Email X-MS-Office365-Filtering-Correlation-Id-Prvs: 01596ef1-0bee-4d7d-afed-08dce49d9f65 X-Microsoft-Antispam: BCL:0; ARA:13230040|376014|36860700013|35042699022|82310400026|1800799024; X-Microsoft-Antispam-Message-Info: bdOCK2WFYwVzM5gAbO+mQRIBXkGQoc95bEIRh5JEHwcXnRgNflKE9jSH7wBbqkXuMggvynFTtXcZ0ntPyBZIFymh3YP1R5VmlYV4uSnsaq42aFH8xk/qaij6LWpaf0eFbtksLRaS+cPvSyDb54thKb/Aof6ZRS0VRTl1gwUalcDg8oYJ36clTf1V6X5rOGGaNCe2YovcpTIT4HfX3JKOKUyYCPO95V7DfIHAigRCLvs/z46TwfjfncA3O9oILyD43wtcUoP8mSGZ9il1A8Q95rTuCpTrASmyG3XLHGdto+8SV4KQWrTfrAc9zsp3fSxx8RJlVItm5L3axvzzYrIaxt75hFZBcLhBkKflHtGFvdk54C2PQbFU9BHixYvO/5gQxMUzAfHNG4tADHz5l9m8bbIq58GqAcVOplJXB8KaEqEvL20y/n0aDiQmiYP/AUllbMw23DoWbyjKeDrlAipdTNUeUKzlE1w/dpF6orPGYUhR3b1YWDjVsmRFhgEqhsE8qtJQV8/AoPUuIkVmzeyqA0cdg+LaeVwql+/wwbvhbVMj+u/tQDqydKE8GCRHF4s6z/K8pmxjzPiM8RQ0ro9TZH1BRIb9a4F418mM1hiMWJaCqfns200J4nVYg1aJfA3zePzy4FR6hXHdoS3vPWK+q8rONSJYzZK5nRCQH5ZbRuoExj8ObbKkhDVWLgu8/8fXorKfRaxYfgKAQMndCImx6LVIn8Dw0MsmGZuur3sTsSWFdgex5NauRd5KAhNIj8c/zpn5o+skGejWnqfuDbJWyS2mDrWb8bE+nUv0VGInwXSMK5jbweDNBzVKEDbNI7JSwh3IYfVUs8xYQGSm2o2LFrce0GcRsrJ4IL9lg1BrBrwoSekNg8WPi60iat72eQqSplmL4WeXhL3xOkaSg7nEoz8mdhjIEG4noNiBtnBp/qJOc5VmGKyBcQyFC4sSaXx3HNDulHf+KpMp4iLydDTcf9SbBzhhxhF3uFWl5Boio1sjT7YjAJhuTSQVbKCrp5OTqYZS5p7nHSHt/KLkJl4AqVFQRc9slKFX9SAkrY2+PFU6KEELEpfQc4lVi0HTxQqOtG1HvftlGNYXWf1zBMA+z0lyoLyMzOv6UltcgHvVxY93NCgqFmqEwV+54JMoEsT6rfJUszUTch2ik7n8S+M/ASaKwunSB7gUA0QaAIMQdRuvxpM50iSaacyWZ69BPh6rNvqpFytymwTBn7O4FpvHxhum0maruIzKqfsHxGB8z/ulJxLpkR7+XLmOGqhWoAmdp2LlE9UDsZjr+yJA9ecyM5MzTmnMcJQ7oQLhxt1A2nLVBYJpEZ4cc5PxA5vnsMtnhpZqUXU45vTJ65ZWr4FKF6BLOcTNu6ifaHwwxMhrOt84HWNDYC7VCn2SC3US4aCc 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:(13230040)(376014)(36860700013)(35042699022)(82310400026)(1800799024); DIR:OUT; SFP:1101; X-OriginatorOrg: arm.com X-MS-Exchange-CrossTenant-OriginalArrivalTime: 04 Oct 2024 17:54:49.0974 (UTC) X-MS-Exchange-CrossTenant-Network-Message-Id: df419d4c-3ceb-4151-da55-08dce49da3ec 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: DU2PEPF00028D05.eurprd03.prod.outlook.com X-MS-Exchange-CrossTenant-AuthAs: Anonymous X-MS-Exchange-CrossTenant-FromEntityHeader: HybridOnPrem X-MS-Exchange-Transport-CrossTenantHeadersStamped: AM8PR08MB6515 X-Spam-Status: No, score=-12.2 required=5.0 tests=BAYES_00, DKIM_SIGNED, DKIM_VALID, DKIM_VALID_AU, DKIM_VALID_EF, FORGED_SPF_HELO, GIT_PATCH_0, SPF_HELO_PASS, SPF_NONE, TXREP, 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 GCC does not emit tlbi instructions, so this only affects the flags passed through to the assembler. gcc/ChangeLog: * config/aarch64/aarch64-arches.def (V8_7A): Add XS. * config/aarch64/aarch64-option-extensions.def (XS): New flag. diff --git a/gcc/config/aarch64/aarch64-arches.def b/gcc/config/aarch64/aarch64-arches.def index fa06377dda089c8a89628bc4cc66d54510346053..66fe5cef0896847715d3b0a404ebabedfc82f34d 100644 --- a/gcc/config/aarch64/aarch64-arches.def +++ b/gcc/config/aarch64/aarch64-arches.def @@ -37,7 +37,7 @@ AARCH64_ARCH("armv8.3-a", generic_armv8_a, V8_3A, 8, (V8_2A, PAUTH, R AARCH64_ARCH("armv8.4-a", generic_armv8_a, V8_4A, 8, (V8_3A, F16FML, DOTPROD, FLAGM, RCPC2)) AARCH64_ARCH("armv8.5-a", generic_armv8_a, V8_5A, 8, (V8_4A, SB, SSBS, PREDRES, FRINTTS, FLAGM2)) AARCH64_ARCH("armv8.6-a", generic_armv8_a, V8_6A, 8, (V8_5A, I8MM, BF16)) -AARCH64_ARCH("armv8.7-a", generic_armv8_a, V8_7A, 8, (V8_6A, WFXT)) +AARCH64_ARCH("armv8.7-a", generic_armv8_a, V8_7A, 8, (V8_6A, WFXT, XS)) AARCH64_ARCH("armv8.8-a", generic_armv8_a, V8_8A, 8, (V8_7A, MOPS)) AARCH64_ARCH("armv8.9-a", generic_armv8_a, V8_9A, 8, (V8_8A, CSSC)) AARCH64_ARCH("armv8-r", generic_armv8_a, V8R , 8, (V8_4A)) diff --git a/gcc/config/aarch64/aarch64-option-extensions.def b/gcc/config/aarch64/aarch64-option-extensions.def index 9781d48f63778d186b66427bae7deb2c01e14107..93adb556276c2379f50805d40d891229c87e1783 100644 --- a/gcc/config/aarch64/aarch64-option-extensions.def +++ b/gcc/config/aarch64/aarch64-option-extensions.def @@ -222,6 +222,8 @@ AARCH64_OPT_EXTENSION("ls64", LS64, (), (), (), "") AARCH64_OPT_FMV_EXTENSION("wfxt", WFXT, (), (), (), "wfxt") +AARCH64_OPT_EXTENSION("xs", XS, (), (), (), "") + AARCH64_OPT_EXTENSION("sme-f64f64", SME_F64F64, (SME), (), (), "") AARCH64_FMV_FEATURE("sme-f64f64", SME_F64, (SME_F64F64))