From patchwork Sat Dec 9 23:30:30 2023 Content-Type: text/plain; charset="utf-8" MIME-Version: 1.0 Content-Transfer-Encoding: 7bit X-Patchwork-Submitter: Victor Do Nascimento X-Patchwork-Id: 1874100 Return-Path: X-Original-To: incoming@patchwork.ozlabs.org Delivered-To: patchwork-incoming@legolas.ozlabs.org Authentication-Results: legolas.ozlabs.org; dkim=pass (1024-bit key; unprotected) header.d=armh.onmicrosoft.com header.i=@armh.onmicrosoft.com header.a=rsa-sha256 header.s=selector2-armh-onmicrosoft-com header.b=QhKEC7QJ; dkim=pass (1024-bit key) header.d=armh.onmicrosoft.com header.i=@armh.onmicrosoft.com header.a=rsa-sha256 header.s=selector2-armh-onmicrosoft-com header.b=QhKEC7QJ; 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 4Snklx6RnLz1ySY for ; Sun, 10 Dec 2023 10:31:07 +1100 (AEDT) Received: from server2.sourceware.org (localhost [IPv6:::1]) by sourceware.org (Postfix) with ESMTP id B1599385842A for ; Sat, 9 Dec 2023 23:31:04 +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-db8eur05on2052.outbound.protection.outlook.com [40.107.20.52]) by sourceware.org (Postfix) with ESMTPS id 239833858C42 for ; Sat, 9 Dec 2023 23:30:50 +0000 (GMT) DMARC-Filter: OpenDMARC Filter v1.4.2 sourceware.org 239833858C42 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 239833858C42 Authentication-Results: server2.sourceware.org; arc=pass smtp.remote-ip=40.107.20.52 ARC-Seal: i=3; a=rsa-sha256; d=sourceware.org; s=key; t=1702164652; cv=pass; b=RexykO9NNAc2+BKqcQZdU3zVmYa926z8bto6fol967ENq3jHkPNO7SKcyjsQS4d6wOuw1oHNcIhPlSJMRgELKcNIHdcp/NEL5cJi0asWm6mO01Fc2txfWlbsvXKhBNqtHr6fMxv/GCYgkn/xSY0c4ccNQQY5h0hOZJX3mbanJLM= ARC-Message-Signature: i=3; a=rsa-sha256; d=sourceware.org; s=key; t=1702164652; c=relaxed/simple; bh=9ihoAiiQErJBHxitc2SEd4rGQLmC0FZdbG2P4vfDalQ=; h=DKIM-Signature:DKIM-Signature:From:To:Subject:Date:Message-ID: MIME-Version; b=lFtn39RlYGa8wwtZJu1yl86Hk9DTOpNmvFLPLozERV+xciZvsx+VuoH2qmZxO75knL59svfU78KJZW6KsnIFL88vkIXj9mKugy7bRVokgAgn3WzDhZQfeRoWxxivcO7c0eY7/gAigj9h0o8Ccm/JuX9FoGvJQujPSMOOVkvM+/4= ARC-Authentication-Results: i=3; server2.sourceware.org ARC-Seal: i=2; a=rsa-sha256; s=arcselector9901; d=microsoft.com; cv=pass; b=iyUtvoPfE8xn9H08kymX7tVPsn/oxbPP+83GVVR25AA25zgTNrn0OexwnvdwWnXEIgCPQqDsPCNsOPZsMhrTgqmcipe+7kJIJNZYkFuHrLKDhcIjUZ+Hxth9w5aDOeXZg3xnEaVojqHS/aIHD68+NFllDdIptrBXwPCndqu2fzjT3dVKGNkdTQO9IZFv/G/r9dMRIezlQNjxBuDfMQxEnSKUdwqKDoZfdKZ56LvnjZm23SgOBitp5/zHA1uCgsUj90J4IZBkCkQ+dPzzZ869iQQXSy4mI1Va7LxmIZDNe/SUwpJd8VcaTqYIR0yiFx0/luM7mPphMuA8WW2xtZ91pA== ARC-Message-Signature: i=2; a=rsa-sha256; c=relaxed/relaxed; d=microsoft.com; s=arcselector9901; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-AntiSpam-MessageData-ChunkCount:X-MS-Exchange-AntiSpam-MessageData-0:X-MS-Exchange-AntiSpam-MessageData-1; bh=t/UX9OIc/S2XU+p/bEuJmkhney2FKZqbYSVJ013wiss=; b=FCCyCyFkhN2wRfz6v9ZjeexrS0VDDNLjOjL7bQKNXQNz21uik4k8LybH8g/EtBhjUzCqN7dUsJSuM9PbIvgpDxg4AC8JtJ3l/DzydmlXivc3+Er0P1lzx+5OWJM49DxXiojmbT8ahgMK1GQVORv4u5oZlWAW1/Wrudr68P/0LcHie34FVuZxwdFoukAlTc2F8SFzIVNXJfKSKoRSSxIafGNpRepHMb/hK+s7uEMHLK1FwDGFZs6rqHsanmBZ3VKPtbpYz8M3scJ7GSJLUstAqR4UDCC22YwwC3O+MdNFpN/qpew/ZoKPNac2ijIbg3W8Hy+NMViCgqMylli0IDKZcA== ARC-Authentication-Results: i=2; mx.microsoft.com 1; spf=pass (sender ip is 63.35.35.123) smtp.rcpttodomain=gcc.gnu.org smtp.mailfrom=arm.com; dmarc=pass (p=none sp=none pct=100) action=none header.from=arm.com; dkim=pass (signature was verified) header.d=armh.onmicrosoft.com; arc=pass (0 oda=1 ltdi=1 spf=[1,1,smtp.mailfrom=arm.com] dmarc=[1,1,header.from=arm.com]) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=armh.onmicrosoft.com; s=selector2-armh-onmicrosoft-com; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-SenderADCheck; bh=t/UX9OIc/S2XU+p/bEuJmkhney2FKZqbYSVJ013wiss=; b=QhKEC7QJaU03PTiArfcA1/zi426iqk+jVjXYWaiTinJp75O7VpQ62C/2oYSTsQE1IIkX5rOHGz8KrvWaCyPPxHptH+74PgdjhCADrgiZtvgK4Z+bmNElRd4ncEYlKbA+ndqGiofqW9h55vbxjVZZ0WM95zokOmdv2Ir61E2Lrbw= Received: from DB9PR01CA0028.eurprd01.prod.exchangelabs.com (2603:10a6:10:1d8::33) by PR3PR08MB5562.eurprd08.prod.outlook.com (2603:10a6:102:85::7) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.7068.30; Sat, 9 Dec 2023 23:30:47 +0000 Received: from DB5PEPF00014B9D.eurprd02.prod.outlook.com (2603:10a6:10:1d8:cafe::a6) by DB9PR01CA0028.outlook.office365.com (2603:10a6:10:1d8::33) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.7068.29 via Frontend Transport; Sat, 9 Dec 2023 23:30:47 +0000 X-MS-Exchange-Authentication-Results: spf=pass (sender IP is 63.35.35.123) smtp.mailfrom=arm.com; dkim=pass (signature was verified) header.d=armh.onmicrosoft.com;dmarc=pass action=none header.from=arm.com; Received-SPF: Pass (protection.outlook.com: domain of arm.com designates 63.35.35.123 as permitted sender) receiver=protection.outlook.com; client-ip=63.35.35.123; helo=64aa7808-outbound-1.mta.getcheckrecipient.com; pr=C Received: from 64aa7808-outbound-1.mta.getcheckrecipient.com (63.35.35.123) by DB5PEPF00014B9D.mail.protection.outlook.com (10.167.8.164) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.7091.18 via Frontend Transport; Sat, 9 Dec 2023 23:30:47 +0000 Received: ("Tessian outbound e243565b0037:v228"); Sat, 09 Dec 2023 23:30:47 +0000 X-CheckRecipientChecked: true X-CR-MTA-CID: 61d82f67fa197624 X-CR-MTA-TID: 64aa7808 Received: from 6c8b34232fa0.1 by 64aa7808-outbound-1.mta.getcheckrecipient.com id 306DFCA9-B628-48E6-892E-CCACCB17642C.1; Sat, 09 Dec 2023 23:30:40 +0000 Received: from EUR01-VE1-obe.outbound.protection.outlook.com by 64aa7808-outbound-1.mta.getcheckrecipient.com with ESMTPS id 6c8b34232fa0.1 (version=TLSv1.2 cipher=ECDHE-RSA-AES256-GCM-SHA384); Sat, 09 Dec 2023 23:30:40 +0000 ARC-Seal: i=1; a=rsa-sha256; s=arcselector9901; d=microsoft.com; cv=none; b=VA5SNPGD/7T9bJ3TBt9KDrASsuEAfp6Hadnmz9FpXGKViyCCKk9dw9tm9DqQEmTnEaE0xPAcvnq8Zet1msSFBu4te1zgmQy6+G2DYikd4OcHU9b2gd2YSmdZ3aYxlFhl6cuQWN/2clAiDQ6Z5YX+NtMODs/lJ5um6J2y8dXFesbaW33nqU0kisKEtHBdW7nMZCCd6rssi/AkMLXeGDPeR4hA8YbCZGP00cErfogqmWyZuAW8TQ+T34W8gNUk3IouilNoGjg7FFW2Qw5kFD0dvSFRUw4hB/16vRStfGBPBJ6d0Tb1JMPzXTeB5t+pnVX5IhyGotfiqXHOO/PlpdLwPw== ARC-Message-Signature: i=1; a=rsa-sha256; c=relaxed/relaxed; d=microsoft.com; s=arcselector9901; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-AntiSpam-MessageData-ChunkCount:X-MS-Exchange-AntiSpam-MessageData-0:X-MS-Exchange-AntiSpam-MessageData-1; bh=t/UX9OIc/S2XU+p/bEuJmkhney2FKZqbYSVJ013wiss=; b=S3TjlZVo8nPgY9AsDddZ7iESU8oKD99dedWVnsUGgRGjW2BG7sZVVRSwJ0WRE48fSg1rLS36K9tCJRv6o/TkEKsk+jjpQ3HsnDn3FFFF2gs8ZMksfSjr5q0aEaLmB1SjkLdCpd/oweyQWIRW9ndRIA70UHvnhn2MwvhS0dvi8MBbWfla/Rn3aMJQbcC1oGntwwOl5l9v3tj9LpbzoGZKjBvV5nEZEjaujsR82QmolO+Wlj5rCleulvhIv92wCiFv2/VOBhClgQlsIUjTvHaMKAh3Vh/sOxdVMAlVLGsVklnN8IPOt2+IS/NmTLD/yaA8ScUvzD9ngQ1d1rLl30ff+A== ARC-Authentication-Results: i=1; mx.microsoft.com 1; spf=pass (sender ip is 40.67.248.234) smtp.rcpttodomain=gcc.gnu.org smtp.mailfrom=arm.com; dmarc=pass (p=none sp=none pct=100) action=none header.from=arm.com; dkim=none (message not signed); arc=none (0) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=armh.onmicrosoft.com; s=selector2-armh-onmicrosoft-com; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-SenderADCheck; bh=t/UX9OIc/S2XU+p/bEuJmkhney2FKZqbYSVJ013wiss=; b=QhKEC7QJaU03PTiArfcA1/zi426iqk+jVjXYWaiTinJp75O7VpQ62C/2oYSTsQE1IIkX5rOHGz8KrvWaCyPPxHptH+74PgdjhCADrgiZtvgK4Z+bmNElRd4ncEYlKbA+ndqGiofqW9h55vbxjVZZ0WM95zokOmdv2Ir61E2Lrbw= Received: from DUZP191CA0031.EURP191.PROD.OUTLOOK.COM (2603:10a6:10:4f8::23) by AS8PR08MB6231.eurprd08.prod.outlook.com (2603:10a6:20b:298::13) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.7068.30; Sat, 9 Dec 2023 23:30:38 +0000 Received: from DU6PEPF0000B620.eurprd02.prod.outlook.com (2603:10a6:10:4f8:cafe::26) by DUZP191CA0031.outlook.office365.com (2603:10a6:10:4f8::23) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.7046.34 via Frontend Transport; Sat, 9 Dec 2023 23:30:38 +0000 X-MS-Exchange-Authentication-Results: spf=pass (sender IP is 40.67.248.234) smtp.mailfrom=arm.com; dkim=none (message not signed) header.d=none;dmarc=pass action=none header.from=arm.com; Received-SPF: Pass (protection.outlook.com: domain of arm.com designates 40.67.248.234 as permitted sender) receiver=protection.outlook.com; client-ip=40.67.248.234; helo=nebula.arm.com; pr=C Received: from nebula.arm.com (40.67.248.234) by DU6PEPF0000B620.mail.protection.outlook.com (10.167.8.136) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_128_GCM_SHA256) id 15.20.7091.18 via Frontend Transport; Sat, 9 Dec 2023 23:30:38 +0000 Received: from AZ-NEU-EX04.Arm.com (10.251.24.32) by AZ-NEU-EX04.Arm.com (10.251.24.32) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_128_GCM_SHA256) id 15.1.2507.32; Sat, 9 Dec 2023 23:30:37 +0000 Received: from e125768.cambridge.arm.com (10.2.78.50) by mail.arm.com (10.251.24.32) with Microsoft SMTP Server id 15.1.2507.32 via Frontend Transport; Sat, 9 Dec 2023 23:30:37 +0000 From: Victor Do Nascimento To: CC: , , , Victor Do Nascimento Subject: [PATCH] aarch64: arm_neon.h - Fix -Wincompatible-pointer-types errors Date: Sat, 9 Dec 2023 23:30:30 +0000 Message-ID: <20231209233036.1712956-1-victor.donascimento@arm.com> X-Mailer: git-send-email 2.42.0 MIME-Version: 1.0 X-EOPAttributedMessage: 1 X-MS-TrafficTypeDiagnostic: DU6PEPF0000B620:EE_|AS8PR08MB6231:EE_|DB5PEPF00014B9D:EE_|PR3PR08MB5562:EE_ X-MS-Office365-Filtering-Correlation-Id: 042155c8-2689-47bc-7a13-08dbf90edf27 x-checkrecipientrouted: true NoDisclaimer: true X-MS-Exchange-SenderADCheck: 1 X-MS-Exchange-AntiSpam-Relay: 0 X-Microsoft-Antispam-Untrusted: BCL:0; X-Microsoft-Antispam-Message-Info-Original: jIP/XBu1Tp0eJWDH4ajiPjXKR2zh5dVJTIlfTICzv9LzODMUjpW/9l59uZlO+AFhSZxc383dGI9E5troHKir9ejeuBfrF1FCWQUvna38en13PVLtTbbNXHlR8ndTyICVPQTRETsKYxrVxL19ExqfgmujyMsQKGTbL06+zCPzSVYMl4TQMbLvFQzuGSsaLk2LTJ8L5rMEr5fx850VLwKKgjJQO8Xfxb0rSnsWuCE6u87vpCs/d1HswOKwM0IY+m3fMAzU4yYHGCBIrD9uLLHG0gmI+TPJmy/M1Mt64aqu/C/xFP5D3Z+HIsRmX6m6zZCza6XGaDIMtowjfJy26bZmIfVjmn0gihQHz0Bhhcfa+Ci7mNFEvBGegWu8KJMHGLiZpVs07XAgtw+9HulVvseWFgYUbgaJ0MB6rSIEQ64w5kKv2ts/1i6HQBm8HG93VlpljqlUFj121eCr+VrVL5MmBRB3wCFNbHQY3DMxm0x4aT9RyarDmXRTLjWR32k8pZGpqbk6c9MOx36+gHvXYDTjUjYhjlYUld3BI0p1afdHQDT+tF/7UYXIlD/dq7PYMrt1L3WSB7Iv44IlwbcS5KAh8O88iIv4NYkv7Wc+/Fj41fcNfav22AR5vYRWrx2jKQOFsoTcpkYFyXHXd0icC8O/HP/Oz3Yv6h+GsmoL9Dvh3PkNVUnIjZfMSZqaCUhkFcuwlugaOiDRwt8fCTY2FsHACzIZ3ETkOQlIWeFaObIFKJ+S70BHtcF5NLwPDHcXng72d7R9wYbyOJbVvFekJ6EV8w== X-Forefront-Antispam-Report-Untrusted: CIP:40.67.248.234; CTRY:IE; LANG:en; SCL:1; SRV:; IPV:NLI; SFV:NSPM; H:nebula.arm.com; PTR:InfoDomainNonexistent; CAT:NONE; SFS:(13230031)(4636009)(136003)(39860400002)(376002)(396003)(346002)(230922051799003)(451199024)(1800799012)(186009)(82310400011)(64100799003)(46966006)(36840700001)(40470700004)(41300700001)(5660300002)(2906002)(2616005)(1076003)(6666004)(7696005)(36756003)(478600001)(36860700001)(47076005)(81166007)(82740400003)(356005)(426003)(83380400001)(336012)(40480700001)(26005)(8936002)(40460700003)(8676002)(4326008)(86362001)(6916009)(54906003)(316002)(70206006)(70586007)(36900700001); DIR:OUT; SFP:1101; X-MS-Exchange-Transport-CrossTenantHeadersStamped: AS8PR08MB6231 X-MS-Exchange-Transport-CrossTenantHeadersStripped: DB5PEPF00014B9D.eurprd02.prod.outlook.com X-MS-PublicTrafficType: Email X-MS-Office365-Filtering-Correlation-Id-Prvs: 74947964-8383-49cd-efaf-08dbf90ed9bc X-Microsoft-Antispam: BCL:0; X-Microsoft-Antispam-Message-Info: QxaNfVLAWUtngCxUw21cIGRhgm4oAEzA9U8odu38S22HiQvOcfClwqyjQHB+t+U3j3HY25JRvUjo3UwKr7YQczzjiymsnjOTIzig6DsE7B5suivb/1tcu9crkG7W4PwiIm74MdaTsy62Z2lZs0oC5+/o/uBg9HK/BMmgZxed4uGdwmJ9v+XoJ9GOEpgWL6EPlzMrz4mP9LS5I5v7vH1pbtEFNezToe44SIe02XS+/bLkIJR3lGWZ9riAtiPADS/KLP+2q40QJAi40OzfDI3RyzTlYZs8jJBplSaLM7bxLEoudD2dLn4g41aWvdTYymlvFNY/Wj+9AOEY/a5wKCbs03/q2eNRVxtsGL0ldkNCtEGFWGksmwPuIgnrzHJFKvyEF7OsmF4Ch2NIWcKShP2YNzogackLvtcb6oUSSDg7rImZMpuwYhfanM4CyIHSZksD9i4c5vTorso1Dr4FReLNOM2Ypb65WMY32EEFp/wem7Gd2Z3pL3lXZkMVR/h0UX2azbnDIICnHLqaab9+a4ogBZAoTcyOzdHFndllgSdTg5vms/75qkHoeYptX78ELOuwBekYmcburu7pUSJGtB8K/0ESwAZaxNx5eC+TlHTKGm86lgSGg+wgKnfKX6q2jcV0nlaCny+FrDMAD5gN5Rb56yoVAytJJ0sQ8i2dm38ehukqUMGtDK4OXoNmrd07u/sfWzONFkX24Dkv2i0RUn13YA== X-Forefront-Antispam-Report: CIP:63.35.35.123; CTRY:IE; LANG:en; SCL:1; SRV:; IPV:CAL; SFV:NSPM; H:64aa7808-outbound-1.mta.getcheckrecipient.com; PTR:ec2-63-35-35-123.eu-west-1.compute.amazonaws.com; CAT:NONE; SFS:(13230031)(4636009)(39860400002)(376002)(136003)(346002)(396003)(230922051799003)(451199024)(186009)(64100799003)(1800799012)(82310400011)(36840700001)(46966006)(41300700001)(36860700001)(47076005)(2616005)(1076003)(426003)(336012)(26005)(83380400001)(82740400003)(36756003)(86362001)(81166007)(5660300002)(316002)(8936002)(4326008)(8676002)(2906002)(7696005)(6666004)(6916009)(70206006)(54906003)(70586007)(478600001)(40480700001); DIR:OUT; SFP:1101; X-OriginatorOrg: arm.com X-MS-Exchange-CrossTenant-OriginalArrivalTime: 09 Dec 2023 23:30:47.1821 (UTC) X-MS-Exchange-CrossTenant-Network-Message-Id: 042155c8-2689-47bc-7a13-08dbf90edf27 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: DB5PEPF00014B9D.eurprd02.prod.outlook.com X-MS-Exchange-CrossTenant-AuthAs: Anonymous X-MS-Exchange-CrossTenant-FromEntityHeader: HybridOnPrem X-MS-Exchange-Transport-CrossTenantHeadersStamped: PR3PR08MB5562 X-Spam-Status: No, score=-12.4 required=5.0 tests=BAYES_00, DKIM_SIGNED, DKIM_VALID, FORGED_SPF_HELO, GIT_PATCH_0, KAM_DMARC_NONE, RCVD_IN_DNSWL_NONE, RCVD_IN_MSPIKE_H2, SPF_HELO_PASS, SPF_NONE, TXREP, T_SCC_BODY_TEXT_LINE, UNPARSEABLE_RELAY autolearn=ham autolearn_force=no version=3.4.6 X-Spam-Checker-Version: SpamAssassin 3.4.6 (2021-04-09) on server2.sourceware.org X-BeenThere: gcc-patches@gcc.gnu.org X-Mailman-Version: 2.1.30 Precedence: list List-Id: Gcc-patches mailing list List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , Errors-To: gcc-patches-bounces+incoming=patchwork.ozlabs.org@gcc.gnu.org In the Linux kernel, u64/s64 are [un]signed long long, not [un]signed long. This means that when the `arm_neon.h' header is used by the kernel, any use of the `uint64_t' / `in64_t' types needs to be correctly cast to the correct `__builtin_aarch64_simd_di' / `__builtin_aarch64_simd_df' types when calling the relevant ACLE builtins. This patch adds the necessary fixes to ensure that `vstl1_*' and `vldap1_*' intrinsics are correctly defined for use by the kernel. gcc/ChangeLog: * config/aarch64/arm_neon.h (vldap1_lane_u64): Add `const' to `__builtin_aarch64_simd_di *' cast. (vldap1q_lane_u64): Likewise. (vldap1_lane_s64): Cast __src to `const __builtin_aarch64_simd_di *'. (vldap1q_lane_s64): Likewise. (vldap1_lane_f64): Cast __src to `const __builtin_aarch64_simd_df *'. (vldap1q_lane_f64): Cast __src to `const __builtin_aarch64_simd_df *'. (vldap1_lane_p64): Add `const' to `__builtin_aarch64_simd_di *' cast. (vldap1q_lane_p64): Add `const' to `__builtin_aarch64_simd_di *' cast. (vstl1_lane_u64): remove stray `const'. (vstl1_lane_s64): Cast __src to `__builtin_aarch64_simd_di *'. (vstl1q_lane_s64): Likewise. (vstl1_lane_f64): Cast __src to `const __builtin_aarch64_simd_df *'. (vstl1q_lane_f64): Likewise. --- gcc/config/aarch64/arm_neon.h | 34 +++++++++++++++++++++------------- 1 file changed, 21 insertions(+), 13 deletions(-) diff --git a/gcc/config/aarch64/arm_neon.h b/gcc/config/aarch64/arm_neon.h index ef0d75e07ce..f394de595f7 100644 --- a/gcc/config/aarch64/arm_neon.h +++ b/gcc/config/aarch64/arm_neon.h @@ -13456,7 +13456,7 @@ __attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) vldap1_lane_u64 (const uint64_t *__src, uint64x1_t __vec, const int __lane) { return __builtin_aarch64_vec_ldap1_lanev1di_usus ( - (__builtin_aarch64_simd_di *) __src, __vec, __lane); + (const __builtin_aarch64_simd_di *) __src, __vec, __lane); } __extension__ extern __inline uint64x2_t @@ -13464,35 +13464,39 @@ __attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) vldap1q_lane_u64 (const uint64_t *__src, uint64x2_t __vec, const int __lane) { return __builtin_aarch64_vec_ldap1_lanev2di_usus ( - (__builtin_aarch64_simd_di *) __src, __vec, __lane); + (const __builtin_aarch64_simd_di *) __src, __vec, __lane); } __extension__ extern __inline int64x1_t __attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) vldap1_lane_s64 (const int64_t *__src, int64x1_t __vec, const int __lane) { - return __builtin_aarch64_vec_ldap1_lanev1di (__src, __vec, __lane); + return __builtin_aarch64_vec_ldap1_lanev1di ( + (const __builtin_aarch64_simd_di *) __src, __vec, __lane); } __extension__ extern __inline int64x2_t __attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) vldap1q_lane_s64 (const int64_t *__src, int64x2_t __vec, const int __lane) { - return __builtin_aarch64_vec_ldap1_lanev2di (__src, __vec, __lane); + return __builtin_aarch64_vec_ldap1_lanev2di ( + (const __builtin_aarch64_simd_di *) __src, __vec, __lane); } __extension__ extern __inline float64x1_t __attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) vldap1_lane_f64 (const float64_t *__src, float64x1_t __vec, const int __lane) { - return __builtin_aarch64_vec_ldap1_lanev1df (__src, __vec, __lane); + return __builtin_aarch64_vec_ldap1_lanev1df ( + (const __builtin_aarch64_simd_df *) __src, __vec, __lane); } __extension__ extern __inline float64x2_t __attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) vldap1q_lane_f64 (const float64_t *__src, float64x2_t __vec, const int __lane) { - return __builtin_aarch64_vec_ldap1_lanev2df (__src, __vec, __lane); + return __builtin_aarch64_vec_ldap1_lanev2df ( + (const __builtin_aarch64_simd_df *) __src, __vec, __lane); } __extension__ extern __inline poly64x1_t @@ -13500,7 +13504,7 @@ __attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) vldap1_lane_p64 (const poly64_t *__src, poly64x1_t __vec, const int __lane) { return __builtin_aarch64_vec_ldap1_lanev1di_psps ( - (__builtin_aarch64_simd_di *) __src, __vec, __lane); + (const __builtin_aarch64_simd_di *) __src, __vec, __lane); } __extension__ extern __inline poly64x2_t @@ -13508,14 +13512,14 @@ __attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) vldap1q_lane_p64 (const poly64_t *__src, poly64x2_t __vec, const int __lane) { return __builtin_aarch64_vec_ldap1_lanev2di_psps ( - (__builtin_aarch64_simd_di *) __src, __vec, __lane); + (const __builtin_aarch64_simd_di *) __src, __vec, __lane); } /* vstl1_lane. */ __extension__ extern __inline void __attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) -vstl1_lane_u64 (const uint64_t *__src, uint64x1_t __vec, const int __lane) +vstl1_lane_u64 (uint64_t *__src, uint64x1_t __vec, const int __lane) { __builtin_aarch64_vec_stl1_lanev1di_sus ((__builtin_aarch64_simd_di *) __src, __vec, __lane); @@ -13533,28 +13537,32 @@ __extension__ extern __inline void __attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) vstl1_lane_s64 (int64_t *__src, int64x1_t __vec, const int __lane) { - __builtin_aarch64_vec_stl1_lanev1di (__src, __vec, __lane); + __builtin_aarch64_vec_stl1_lanev1di ((__builtin_aarch64_simd_di *) __src, + __vec, __lane); } __extension__ extern __inline void __attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) vstl1q_lane_s64 (int64_t *__src, int64x2_t __vec, const int __lane) { - __builtin_aarch64_vec_stl1_lanev2di (__src, __vec, __lane); + __builtin_aarch64_vec_stl1_lanev2di ((__builtin_aarch64_simd_di *) __src, + __vec, __lane); } __extension__ extern __inline void __attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) vstl1_lane_f64 (float64_t *__src, float64x1_t __vec, const int __lane) { - __builtin_aarch64_vec_stl1_lanev1df (__src, __vec, __lane); + __builtin_aarch64_vec_stl1_lanev1df ((__builtin_aarch64_simd_df *) __src, + __vec, __lane); } __extension__ extern __inline void __attribute__ ((__always_inline__, __gnu_inline__, __artificial__)) vstl1q_lane_f64 (float64_t *__src, float64x2_t __vec, const int __lane) { - __builtin_aarch64_vec_stl1_lanev2df (__src, __vec, __lane); + __builtin_aarch64_vec_stl1_lanev2df ((__builtin_aarch64_simd_df *) __src, + __vec, __lane); } __extension__ extern __inline void