This is the mail archive of the
gcc-patches@gcc.gnu.org
mailing list for the GCC project.
Re: [GCC][PATCH][AArch32] ACLE intrinsics bfloat16 vmmla and vfma<b/t> for AArch32 AdvSIMD
- From: Delia Burduv <Delia dot Burduv at arm dot com>
- To: "gcc-patches at gcc dot gnu dot org" <gcc-patches at gcc dot gnu dot org>
- Cc: "nickc at redhat dot com" <nickc at redhat dot com>, Richard Earnshaw <Richard dot Earnshaw at arm dot com>, Ramana Radhakrishnan <Ramana dot Radhakrishnan at arm dot com>, Kyrylo Tkachov <Kyrylo dot Tkachov at arm dot com>
- Date: Tue, 28 Jan 2020 16:44:19 +0000
- Subject: Re: [GCC][PATCH][AArch32] ACLE intrinsics bfloat16 vmmla and vfma<b/t> for AArch32 AdvSIMD
- 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
- 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-SenderADCheck; bh=xiqi4OU6VANEjfcHAse1cdSGwLXzlAyZgkj5CmQc9qU=; b=QgOjXZUqYFvH/YdnhVdEpCKqjMD9hGXsq9CvVRC1BZQsSygd2D9+Q7jU9Dp+nhVwuQiXDZRLwAnHPvdtmbp/oCCZ19wycQfo1kt5A945C9N5O5nNVMA6rOLx6UO9H/yuX5xc7+NIB30u3cND3O3bFq9DAku515dIyZyNBzWmQg6I65z7DwZ29xRs2UCBTQCaQHTFTjKvGQTFDKVoDhKlY5yEW5XSPrfaFZvJBhqN6Kk8xxpSFwMaWXJLixLCy+4ZYlfmR2IUX8W9BTlMWprqFDS5QVYbhWbOM/V1XgLsWDtr1PuALfP9zqEa+7+U3bNO+jDFdIka4DJOq71r1V4cWg==
- Arc-seal: i=1; a=rsa-sha256; s=arcselector9901; d=microsoft.com; cv=none; b=Umnrknz+rlJRaqsE8tFvNZMQFEKbAz7C4lwBjXtqM3e2fgmo4RhyhADxZovz56TdeQlQgoAmRbOc8Tgv7z5JMpCTC3OsNZJ57E+cYRhBKlRKUOu8FkL2/RhzUyljZ+IIOvhjYHwvc5qcTVOzMXOLkxb/HVp/D2ZJFLj7ImzkMvo/HVqKjUHmqEyzHoIPprsgUh0PBq4JGsZGUBuPKEnAtCcat3IeABT/f57exsOPquUvrM3xTEG3qW8mKW83k5yRsFyGAlF4UhtKnpXfCzXyYFbQNMdRf5u49x8JgyY5gjqkkJr+7wVKs+SBxXHJztdpmQSokt2AOUAB4mFB/29pEA==
- Original-authentication-results: spf=none (sender IP is ) smtp.mailfrom=Delia dot Burduv at arm dot com;
- References: <1994305c-a05b-774b-15da-5f1474b7c841@arm.com>,<a0ef840e-d3f9-ce55-d56c-035e33d1afa5@arm.com>
Ping.
________________________________
From: Delia Burduv <delia.burduv@arm.com>
Sent: 22 January 2020 17:26
To: gcc-patches@gcc.gnu.org <gcc-patches@gcc.gnu.org>
Cc: nickc@redhat.com <nickc@redhat.com>; Richard Earnshaw <Richard.Earnshaw@arm.com>; Ramana Radhakrishnan <Ramana.Radhakrishnan@arm.com>; Kyrylo Tkachov <Kyrylo.Tkachov@arm.com>
Subject: Re: [GCC][PATCH][AArch32] ACLE intrinsics bfloat16 vmmla and vfma<b/t> for AArch32 AdvSIMD
Ping.
I have read Richard Sandiford's comments on the AArch64 patches and I
will apply what is relevant to this patch as well. Particularly, I will
change the tests to use the exact input and output registers and I will
change the types of the rtl patterns.
On 12/20/19 6:44 PM, Delia Burduv wrote:
> This patch adds the ARMv8.6 ACLE intrinsics for vmmla, vfmab and vfmat
> as part of the BFloat16 extension.
> (https://developer.arm.com/docs/101028/latest.)
> The intrinsics are declared in arm_neon.h and the RTL patterns are
> defined in neon.md.
> Two new tests are added to check assembler output and lane indices.
>
> This patch depends on the Arm back-end patche.
> (https://gcc.gnu.org/ml/gcc-patches/2019-12/msg01448.html)
>
> Tested for regression on arm-none-eabi and armeb-none-eabi. I don't have
> commit rights, so if this is ok can someone please commit it for me?
>
> gcc/ChangeLog:
>
> 2019-11-12 Delia Burduv <delia.burduv@arm.com>
>
> * config/arm/arm_neon.h (vbfmmlaq_f32): New.
> (vbfmlalbq_f32): New.
> (vbfmlaltq_f32): New.
> (vbfmlalbq_lane_f32): New.
> (vbfmlaltq_lane_f32): New.
> (vbfmlalbq_laneq_f32): New.
> (vbfmlaltq_laneq_f32): New.
> * config/arm/arm_neon_builtins.def (vbfmmla): New.
> (vbfmab): New.
> (vbfmat): New.
> (vbfmab_lane): New.
> (vbfmat_lane): New.
> (vbfmab_laneq): New.
> (vbfmat_laneq): New.
> * config/arm/iterators.md (BF_MA): New int iterator.
> (bt): New int attribute.
> (VQXBF): Copy of VQX with V8BF.
> (V_HALF): Added V8BF.
> * config/arm/neon.md (neon_vbfmmlav8hi): New insn.
> (neon_vbfma<bt>v8hi): New insn.
> (neon_vbfma<bt>_lanev8hi): New insn.
> (neon_vbfma<bt>_laneqv8hi): New expand.
> (neon_vget_high<mode>): Changed iterator to VQXBF.
> * config/arm/unspecs.md (UNSPEC_BFMMLA): New UNSPEC.
> (UNSPEC_BFMAB): New UNSPEC.
> (UNSPEC_BFMAT): New UNSPEC.
>
> 2019-11-12 Delia Burduv <delia.burduv@arm.com>
>
> * gcc.target/arm/simd/bf16_ma_1.c: New test.
> * gcc.target/arm/simd/bf16_ma_2.c: New test.
> * gcc.target/arm/simd/bf16_mmla_1.c: New test.