From patchwork Tue Oct 1 13:58:37 2024 Content-Type: text/plain; charset="utf-8" MIME-Version: 1.0 Content-Transfer-Encoding: 7bit X-Patchwork-Submitter: Andrew Carlotti X-Patchwork-Id: 1991485 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=SNCE1vQY; dkim=pass (1024-bit key) header.d=arm.com header.i=@arm.com header.a=rsa-sha256 header.s=selector1 header.b=SNCE1vQY; 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 4XJ0142xLsz1xtg for ; Tue, 1 Oct 2024 23:59:20 +1000 (AEST) Received: from server2.sourceware.org (localhost [IPv6:::1]) by sourceware.org (Postfix) with ESMTP id 3BAAD38708DD for ; Tue, 1 Oct 2024 13:59:18 +0000 (GMT) X-Original-To: gcc-patches@gcc.gnu.org Delivered-To: gcc-patches@gcc.gnu.org Received: from EUR02-VI1-obe.outbound.protection.outlook.com (mail-vi1eur02on20605.outbound.protection.outlook.com [IPv6:2a01:111:f403:2607::605]) by sourceware.org (Postfix) with ESMTPS id 7C72A38708B4 for ; Tue, 1 Oct 2024 13:58:52 +0000 (GMT) DMARC-Filter: OpenDMARC Filter v1.4.2 sourceware.org 7C72A38708B4 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 7C72A38708B4 Authentication-Results: server2.sourceware.org; arc=pass smtp.remote-ip=2a01:111:f403:2607::605 ARC-Seal: i=3; a=rsa-sha256; d=sourceware.org; s=key; t=1727791135; cv=pass; b=TPk2zxVGv9jEc+lexCpxNUW1gtUfT1JznZD9dE5XHiV4DJpsL8a/VBHWfcqVa9apSwPVJwaEp3ao8MhtSEklZvNDCV+SiqbG5pxQHSddO+XKYxPvKdMfp2a5MiBHSl3C+OL28yJNgXclk2EU2FUwfEbmMhN6QuUf9ZbKhuMVKUY= ARC-Message-Signature: i=3; a=rsa-sha256; d=sourceware.org; s=key; t=1727791135; c=relaxed/simple; bh=Qb0Lk4civLulWYd0lzj8DMZcRkHPAhAmj6c63tS+0Mg=; h=DKIM-Signature:DKIM-Signature:Date:From:To:Subject:Message-ID: MIME-Version; b=UhTK9v0kNrsQ/BcAQFx6otrNwg9y90i110R4hyR+uRpGW9g5tpn0KJeUwjS4uWBlDBrIYIHAz9NzqjKfYzOeyZQ4itXyHVTOm565m9wr5OPXDK6LFND7gRajllmAAOg4XUy3txwB3RkRxqUNrJFeT8+MoMgz84Ef4tDlbrwAlpQ= ARC-Authentication-Results: i=3; server2.sourceware.org ARC-Seal: i=2; a=rsa-sha256; s=arcselector10001; d=microsoft.com; cv=pass; b=cHulXrKfyWEYJziD4pjqEJIsjWNDS/sbQOPjsVaX4TxyKvVDaXhQj7VoeOkhEkwPJn/cCO8P44p+lS6U9n0yHPokFa59/CVuaioGqWOcHuWtXvNO4z5zqajvsjTJbMzD/+gtuxEN1U7vvKr5igW5hIzzDSGWO7FRQ7dWFIjHDcUi/cwQL4U1wqEePE6NyMelpytVtNULGO2LNHlikX4HcaoDZqvADhDbqm/7fxqL0uUH6YLumsTcQSLrXZHgujEQltuz4dh+9NBdvDaPVMO3uUCe+vmX1AnVCXFWT/K2qcbqqVxm/HDnHNDl+Pd+I4dI1UMUKwq6OceEZz59aKEPOg== 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=EC1vk3UQufgb+P8R3sBB4IEI+FQKpXiDcNgN5fMTnBw=; b=tJDxJO4x43kXgRkOPsr8pVGgMRqyOuxrnhu7a8P00yj8IwrPIskRWlugg8q6CKwJ3dj4C2/+qRu+JxSvK8i3Cnokjoc6pmP0MLboJ/JZM1vRPChMhSvJ/DTzEA1kreXj9Gu8XMB10dkUCrdlu7D9cTFOxA5JL6PnC5GoAqQzai3MgS4kNUzGXxPrAnKoc86K8AS4ThhX7XqW/MZDK+FiGTJMcJouQGfTcNthz25S3YKniy7DH7TiFMT+44feQpwOR24J2Q628en/Lv0ji5S7iSaTI3nwU3Wd+DH6p7gn8bnir6qMtew+QJTQ83FLqoilJzcn2Uts7HYHhpNaRY15hQ== 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=EC1vk3UQufgb+P8R3sBB4IEI+FQKpXiDcNgN5fMTnBw=; b=SNCE1vQYOGUOabrJcfFLsK2po74Xv0Ga+8Bss/LwE8MDAyV6eFQNljrrbR1uaFaCW6jmCh9ggkfUBx613ZNa08rlXOD2bQ72g8DbOLzucyj+pD4u80MwRLW7n87dNCTy7/+0PzDdufhmBMvV31tQv3pgW7t19v7UELE3cKYuVYI= Received: from DU2PR04CA0026.eurprd04.prod.outlook.com (2603:10a6:10:3b::31) by AS8PR08MB9765.eurprd08.prod.outlook.com (2603:10a6:20b:616::17) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.8026.15; Tue, 1 Oct 2024 13:58:49 +0000 Received: from DB1PEPF000509E4.eurprd03.prod.outlook.com (2603:10a6:10:3b:cafe::aa) by DU2PR04CA0026.outlook.office365.com (2603:10a6:10:3b::31) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.8005.27 via Frontend Transport; Tue, 1 Oct 2024 13:58:49 +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 DB1PEPF000509E4.mail.protection.outlook.com (10.167.242.54) with Microsoft SMTP Server (version=TLS1_3, cipher=TLS_AES_256_GCM_SHA384) id 15.20.8005.15 via Frontend Transport; Tue, 1 Oct 2024 13:58:48 +0000 Received: ("Tessian outbound 994fc319cf83:v473"); Tue, 01 Oct 2024 13:58:48 +0000 X-CheckRecipientChecked: true X-CR-MTA-CID: 1958e6a0fe519aa2 X-TessianGatewayMetadata: 8dyZwbZrCPV08j6wuppb3wXWNUTEJR4wUs6ermNZ8s3xMNd03INZB8AcI4DmRaUWt3ZqZ7jwk161bN1wgoHMDBXMpC3oE+kuNHsMqhl0KXos0j03IWw/8p+wc3dHa+rlAdnqZweSK0H6UAxxToCa+zuPOSvlK18kgJU+BDYBBHe21153wEgtoOtCmIhhvxrd X-CR-MTA-TID: 64aa7808 Received: from L208bfc5aa1bc.1 by 64aa7808-outbound-1.mta.getcheckrecipient.com id 8370B285-BB6D-4342-A578-00C5E8FB7CC4.1; Tue, 01 Oct 2024 13:58:41 +0000 Received: from EUR02-AM0-obe.outbound.protection.outlook.com by 64aa7808-outbound-1.mta.getcheckrecipient.com with ESMTPS id L208bfc5aa1bc.1 (version=TLSv1.2 cipher=ECDHE-RSA-AES256-GCM-SHA384); Tue, 01 Oct 2024 13:58:41 +0000 ARC-Seal: i=1; a=rsa-sha256; s=arcselector10001; d=microsoft.com; cv=none; b=tycm83ul2cYlf8Q1lqeZCEICfCcJ+DhXnySBcGG3YbkiqxIByn6n7QdLvejmEJbv9mJgwyJir5RlKN0OqucN2rteVGAeNNSnulP7Iv78wGvjHiwR495bE0NxkTH/EmTmnJ6HQRK28nSjn+7tcFodPTHhIWpnM0t1fp4w6oOAQNX3tssgi4LZrjwS5e7i0eFiXUt5xj5MvJ3QDnXck7XrEi+IoCftRY9B9Hzwn7kf7m9ZyzNStoSe9Iwrz4AyqwLCA16qRsMwJbAGK6mtTUdlZoNWWhHTKB0eu3YPZ2X5Kcyk70vvgXuXWUMlKtQrJaWBKs7nBMvmICG6l7UvKZ12Bg== 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=EC1vk3UQufgb+P8R3sBB4IEI+FQKpXiDcNgN5fMTnBw=; b=RC7Z9XjZtdKGN95claGL++CfrMCQKlLpujZY/IQNn2wb1Wn6OaYy4FiMi93zEroh3bo0tAc4uDD0dstCVKszJ9fR9P21YX7oOGNvo2yJ3BjEokvJC9/k9R/yobzTjc9dfam5PAJ2L3Myn2smdKCfuKojhKCEqzWaO6QgbgIQQpwRWWSaPAfYwSsUPy8JxkV1QOGtxrEfl3417qmQdtt+IYeWJP3dfl0WaIpeRr9dVMUJjKJ5ChTuExnDjx8NGFsQoMAi3LZ/s5wepTnit39RAkJ132rVtVUAgfijTmHFeWnY6rlsy+l+sOtDUF+5UaUPIdxmvjCc1oMkPGs5rE1MTA== 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=EC1vk3UQufgb+P8R3sBB4IEI+FQKpXiDcNgN5fMTnBw=; b=SNCE1vQYOGUOabrJcfFLsK2po74Xv0Ga+8Bss/LwE8MDAyV6eFQNljrrbR1uaFaCW6jmCh9ggkfUBx613ZNa08rlXOD2bQ72g8DbOLzucyj+pD4u80MwRLW7n87dNCTy7/+0PzDdufhmBMvV31tQv3pgW7t19v7UELE3cKYuVYI= 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 DB8PR08MB5498.eurprd08.prod.outlook.com (2603:10a6:10:11c::24) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.8026.14; Tue, 1 Oct 2024 13:58:39 +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.014; Tue, 1 Oct 2024 13:58:39 +0000 Date: Tue, 1 Oct 2024 14:58:37 +0100 From: Andrew Carlotti To: gcc-patches@gcc.gnu.org Cc: Richard Sandiford Subject: [PATCH] aarch64: Add support for mfloat8x{8|16}_t types Message-ID: Content-Disposition: inline X-ClientProxiedBy: LO4P265CA0236.GBRP265.PROD.OUTLOOK.COM (2603:10a6:600:315::15) To DU0PR08MB8255.eurprd08.prod.outlook.com (2603:10a6:10:411::9) MIME-Version: 1.0 X-MS-TrafficTypeDiagnostic: DU0PR08MB8255:EE_|DB8PR08MB5498:EE_|DB1PEPF000509E4:EE_|AS8PR08MB9765:EE_ X-MS-Office365-Filtering-Correlation-Id: 37732c3d-4059-444c-3603-08dce2212c62 x-checkrecipientrouted: true NoDisclaimer: true X-MS-Exchange-SenderADCheck: 1 X-MS-Exchange-AntiSpam-Relay: 0 X-Microsoft-Antispam-Untrusted: BCL:0;ARA:13230040|1800799024|376014|366016; X-Microsoft-Antispam-Message-Info-Original: UnhBaxsasXNNwGVssDd+OeDWjnj2zhIilfsChKGfBJWUoWhC2EdW/+iPbS1twjHi+GRlJY5oXz4PW+KnOWi8GRaN7wSrjZG2Yuzfec52sy5rhAA5QzgylaGFuZKMJ99hg9NfN77GBd92xvaizGNfySnqxOrbH6B/t1EWKPYeIi1C2Z9eCU4xCPaV01ByyzkeC8rnxOAVnM025ZBsS8rG1P62+hubxh7ICdPTuL3dZ0GLUHkEb4r06HCAMy42nzTIUgiEaeGUJ+gxNmcQ1RnITQMY+fsd/Vt1oyaNlXefUrW1YeQbcxwDdb00nVsvdSEVnt1pufhVXboxIF838VHcI/h4nwJjLSbtzbGg0X0rKEPaTuGDwq/nk3IdiGUwm9Bd8LtBHy7ZRkV0QBKXoh9DBV//+HsBjj6h72GLgBc3SOtOGkFw6ln9ieDoaKQhhG+wUBM3k8HCrTVdOaw3k35BIW7IeaisFd+WnZSgBLdiiD6X8w8pFIkpZMXnYdE960shxTwvvH0/A1gLUWrRLz3kTB4twtBb2pm0D7M7YwYtQAf+JXMdzI10ihnVNcfUDW3FkMtRYmTBICKYWyuDOUJpphSajO7Bvgh531lBZcdaZxAqeK2BkGC2Gu9zs7A94OlTWNmGcBTkr6ZPhfyVQoqDOfDNkveu3f4cZTUB6fSqSHI9bD83IqikwpHqkAE7RUlIJyaxWSJAW1D5s8kaQFNjVHtSyeHJ11XzT20VpL4+p6i/ci3s1xsfg5cVUG/T/K/TSKzApShSMdfZw0b1h0yRhuSU06t7zhhqg7UmlejI2Nz1tA40B63//8DzL2treB+/zVyl1q250opWp86xVyl4XHv1LjOeoFpWAgXx1lOrd6k387xNFyaj4h/1BO8zoRzJw91awn55rtmnq7HeUW5zJOqAPW1+GofHJByxyG4tOSe+bCgXZ7OKoB7EffTYkA5PxOubFmWSajONvuHIyimgl6zOriz08YrejW1HhkCBZr8sxjHOqJklsHtX8aaHeWGo30HrLHhM2aMzN85oSuwXiYIV9qwXhdDHzv+E0cFE7I4wceK0/2zRwhBUt8DC7yjukT/L+L08B66zpDiR3wOr6Xhxshdp6ZzZ+cniGBl1QTXa1X6E3dRAHjYPlJxIM1JPzGsy710LJn9mq+dnQzv0OEQSmd4MMXapLJKG4jVF03SvVMPiETbMhLvatIfg0sKwdVyOlMRZDlAx2NhfMOKG/fCadDKK3qIFHwm1a6ac8TyZeGvwoKXvkJpnYcVI2jVvzZAcuog0t78RnsYveW/8eVKeQj3kYjhPcaJ2hK9XBZ7XY5RObAsunolojgQm7ga4auOlyTW7K0D6stuLiof6ow== 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)(1800799024)(376014)(366016); DIR:OUT; SFP:1101; X-MS-Exchange-Transport-CrossTenantHeadersStamped: DB8PR08MB5498 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: DB1PEPF000509E4.eurprd03.prod.outlook.com X-MS-PublicTrafficType: Email X-MS-Office365-Filtering-Correlation-Id-Prvs: 5f0c1eb8-ea46-445e-11b3-08dce221271c X-Microsoft-Antispam: BCL:0; ARA:13230040|376014|36860700013|35042699022|1800799024|82310400026; X-Microsoft-Antispam-Message-Info: L9YQTJ/aFGAunk2O5M7Q78X21ZHoqNac1EYy0iLzK9OlFQJGVVWUsfMOgNg45Zrtsq0gKz7REhSHz88ILXbcc3GA8C4D2Ec7BaBJ2OaParl0Xv8SrPihLKiTJ/1kR5g8OcFWSdlC3pJMFpJ9XeGf2zqp/arUXpViBPMI4G71u1MEFxIOnIWs1+RNi9o2SFzL3TNHLvpR9gxnWYTwVQg/ZTiQcu8MiY9SrJno4CIkr9ayq7pkEhrqCoGPdPTCxh8ksh01SghUBSH31IVKwuDwYqelIrZDEOieZ6bce6g1l82FsckpVdGMpnmAWlsBl6+TsgIpgBqVBaOSKYW7C/Lu32Du0Gio9BQ+FuhcCqZgVXKbiUgzoBKPl+XAKRMrQda9ykINIK2P+c7Khj6JIrJuyntPYEYYJymD/icDgvoyz9U5cJ2sqpfmZUmupEj/TxLU89XonUhdtptUwO7eGgyeTRJldZ9Q9CMc7BUMF24zGClWzLKTy8WVNvaNaYSrP//SUnpna+JJqY2utRmOIIxkfg8ECgteVhGNG14k9/dtYCnQXF20O53PhqFZg4KgoCj/ZARL7wie7/EllXcZEXn13LUr6dV36PUB6E4HU4Qz68F4fYlXpRxPU8Bn38tZoSbm3If8l958PqbM7pBO4CHLXebYfQAq5Wne/uazFAlJkQNaGt3cREXaXoJYEqa2/DH8J3Z9VsfzPU/BROPdwJN1h+hyt7YjszadJU+pSaxpJ1v9OeGmZVWQNPZ3OrL8dwe5l9S4SZ0OF1WolnKbgpmBUZ1CJSOQk4gIjS3+SSE557I/girhc6ZdQXNl5z3zSNxZ7EuuVRSvDiZSUS78gYi4zFRy1rEAfGoNjdKEr9CCYCOuUA6LHhbgappPWVUDpi2fN0ssiWzkFr1n2v8RLVHaAaFvUtbITNxDt64OVd3QCoMoEtyJXyPUqfs4Lie6Lxsd3NhRQUO9zt89eYdbBZsfWrdqUSOg22+9uzLvLVekxxv8tw1m/fANL5QeMXUK13VBmFDqFrFdxySV/cZXFrNksBQUwUDoqUiNdvqFv7FehrDeunfeyIlCI7l7YhGye3svwTMFdAthaeh1EgLpsj9aUXMaQXDFqHRnEU9rKYr8799Ax8J+cNXoYZ5BBr7NU52bvkGyQAhbT9/Zw8fBQwgoxNfvlV2HWe8G5DFyO8QYaVCjfaL6yIOEczCioEkWj3Q3vKEu2NMub9gpDS8jzn8M5Y3uzNqjt1E/9RZPsudb3Tpqom0BVNVyU46bmiF1R17goTlGyLkZTBPm0aZD4emt8WuLd2zuPoNro3MPeE3jHWtnpo1UttBO0Rg+e9FdkmF4+PUseFKobF9eVgf6l+sZv750tm42fr6cRLZSGWH6gOESaJdKaC7wwammUY+MYXxn 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)(1800799024)(82310400026); DIR:OUT; SFP:1101; X-OriginatorOrg: arm.com X-MS-Exchange-CrossTenant-OriginalArrivalTime: 01 Oct 2024 13:58:48.5887 (UTC) X-MS-Exchange-CrossTenant-Network-Message-Id: 37732c3d-4059-444c-3603-08dce2212c62 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: DB1PEPF000509E4.eurprd03.prod.outlook.com X-MS-Exchange-CrossTenant-AuthAs: Anonymous X-MS-Exchange-CrossTenant-FromEntityHeader: HybridOnPrem X-MS-Exchange-Transport-CrossTenantHeadersStamped: AS8PR08MB9765 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, 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 I've tested this with a hacked in FP8 intrinsic. Is this patch ok for master, or should it wait until we've implemented the intrinsics? gcc/ChangeLog: * config/aarch64/aarch64-builtins.cc (MODE_d_mf8): New. (MODE_q_mf8): New. (QUAL_mf8): New. (aarch64_lookup_simd_type_in_table): Match modal_float bit. (aarch64_init_simd_builtin_types): Initialise FP8 simd types. * config/aarch64/aarch64-builtins.h (enum aarch64_type_qualifiers): Add qualifier_modal_float bit. * config/aarch64/aarch64-simd-builtin-types.def: Add Mfloat8x{8|16}_t types. * config/aarch64/arm_neon.h: Add mfloat8x{8|16}_t typedefs. diff --git a/gcc/config/aarch64/aarch64-builtins.h b/gcc/config/aarch64/aarch64-builtins.h index e326fe666769cedd6c06d0752ed30b9359745ac9..00db7a74885db4d97ed365e8e3e2d7cf7d8410a4 100644 --- a/gcc/config/aarch64/aarch64-builtins.h +++ b/gcc/config/aarch64/aarch64-builtins.h @@ -54,6 +54,8 @@ enum aarch64_type_qualifiers /* Lane indices selected in quadtuplets. - must be in range, and flipped for bigendian. */ qualifier_lane_quadtup_index = 0x1000, + /* Modal FP types. */ + qualifier_modal_float = 0x2000, }; #define ENTRY(E, M, Q, G) E, diff --git a/gcc/config/aarch64/aarch64-builtins.cc b/gcc/config/aarch64/aarch64-builtins.cc index 7d17df05a0f7e8c42596af7f1de4652b59563fe0..f6921ac1d5619e85d4239cd93d1bc84c1d55d4df 100644 --- a/gcc/config/aarch64/aarch64-builtins.cc +++ b/gcc/config/aarch64/aarch64-builtins.cc @@ -133,6 +133,7 @@ #define MODE_d_f16 E_V4HFmode #define MODE_d_f32 E_V2SFmode #define MODE_d_f64 E_V1DFmode +#define MODE_d_mf8 E_V8QImode #define MODE_d_s8 E_V8QImode #define MODE_d_s16 E_V4HImode #define MODE_d_s32 E_V2SImode @@ -148,6 +149,7 @@ #define MODE_q_f16 E_V8HFmode #define MODE_q_f32 E_V4SFmode #define MODE_q_f64 E_V2DFmode +#define MODE_q_mf8 E_V16QImode #define MODE_q_s8 E_V16QImode #define MODE_q_s16 E_V8HImode #define MODE_q_s32 E_V4SImode @@ -177,6 +179,7 @@ #define QUAL_p16 qualifier_poly #define QUAL_p64 qualifier_poly #define QUAL_p128 qualifier_poly +#define QUAL_mf8 qualifier_modal_float #define LENGTH_d "" #define LENGTH_q "q" @@ -1087,7 +1090,8 @@ aarch64_lookup_simd_type_in_table (machine_mode mode, { int i; int nelts = ARRAY_SIZE (aarch64_simd_types); - int q = qualifiers & (qualifier_poly | qualifier_unsigned); + int q = qualifiers + & (qualifier_poly | qualifier_unsigned | qualifier_modal_float); for (i = 0; i < nelts; i++) { @@ -1190,6 +1194,10 @@ aarch64_init_simd_builtin_types (void) aarch64_simd_types[Bfloat16x4_t].eltype = bfloat16_type_node; aarch64_simd_types[Bfloat16x8_t].eltype = bfloat16_type_node; + /* Init FP8 element types. */ + aarch64_simd_types[Mfloat8x8_t].eltype = aarch64_mfp8_type_node; + aarch64_simd_types[Mfloat8x16_t].eltype = aarch64_mfp8_type_node; + for (i = 0; i < nelts; i++) { tree eltype = aarch64_simd_types[i].eltype; diff --git a/gcc/config/aarch64/aarch64-simd-builtin-types.def b/gcc/config/aarch64/aarch64-simd-builtin-types.def index 6111cd0d4fe1136feabb36a4077cf86d13b835e2..83b2da2e7dc0962c1e5957e25c8f6232c2148fe5 100644 --- a/gcc/config/aarch64/aarch64-simd-builtin-types.def +++ b/gcc/config/aarch64/aarch64-simd-builtin-types.def @@ -52,3 +52,5 @@ ENTRY (Float64x2_t, V2DF, none, 13) ENTRY (Bfloat16x4_t, V4BF, none, 14) ENTRY (Bfloat16x8_t, V8BF, none, 14) + ENTRY (Mfloat8x8_t, V8QI, modal_float, 13) + ENTRY (Mfloat8x16_t, V16QI, modal_float, 14) diff --git a/gcc/config/aarch64/arm_neon.h b/gcc/config/aarch64/arm_neon.h index 0092314cf7586bf77c8272cff8156608f56eaedc..63f860886c3152e3de7f29833119f9f65b6774a2 100644 --- a/gcc/config/aarch64/arm_neon.h +++ b/gcc/config/aarch64/arm_neon.h @@ -73,6 +73,8 @@ typedef __Poly64_t poly64_t; typedef __Poly128_t poly128_t; typedef __mfp8 mfloat8_t; +typedef __Mfloat8x8_t mfloat8x8_t; +typedef __Mfloat8x16_t mfloat8x16_t; typedef __fp16 float16_t; typedef float float32_t;