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