| [1166] | 1 | /* Copyright (C) 2020-2021 Free Software Foundation, Inc.
 | 
|---|
 | 2 | 
 | 
|---|
 | 3 |    This file is part of GCC.
 | 
|---|
 | 4 | 
 | 
|---|
 | 5 |    GCC is free software; you can redistribute it and/or modify
 | 
|---|
 | 6 |    it under the terms of the GNU General Public License as published by
 | 
|---|
 | 7 |    the Free Software Foundation; either version 3, or (at your option)
 | 
|---|
 | 8 |    any later version.
 | 
|---|
 | 9 | 
 | 
|---|
 | 10 |    GCC is distributed in the hope that it will be useful,
 | 
|---|
 | 11 |    but WITHOUT ANY WARRANTY; without even the implied warranty of
 | 
|---|
 | 12 |    MERCHANTABILITY or FITNESS FOR A PARTICULAR PURPOSE.  See the
 | 
|---|
 | 13 |    GNU General Public License for more details.
 | 
|---|
 | 14 | 
 | 
|---|
 | 15 |    Under Section 7 of GPL version 3, you are granted additional
 | 
|---|
 | 16 |    permissions described in the GCC Runtime Library Exception, version
 | 
|---|
 | 17 |    3.1, as published by the Free Software Foundation.
 | 
|---|
 | 18 | 
 | 
|---|
 | 19 |    You should have received a copy of the GNU General Public License and
 | 
|---|
 | 20 |    a copy of the GCC Runtime Library Exception along with this program;
 | 
|---|
 | 21 |    see the files COPYING3 and COPYING.RUNTIME respectively.  If not, see
 | 
|---|
 | 22 |    <http://www.gnu.org/licenses/>.  */
 | 
|---|
 | 23 | 
 | 
|---|
 | 24 | #if !defined _IMMINTRIN_H_INCLUDED
 | 
|---|
 | 25 | #error "Never use <amxbf16intrin.h> directly; include <immintrin.h> instead."
 | 
|---|
 | 26 | #endif
 | 
|---|
 | 27 | 
 | 
|---|
 | 28 | #ifndef _AMXBF16INTRIN_H_INCLUDED
 | 
|---|
 | 29 | #define _AMXBF16INTRIN_H_INCLUDED
 | 
|---|
 | 30 | 
 | 
|---|
 | 31 | #if !defined(__AMX_BF16__)
 | 
|---|
 | 32 | #pragma GCC push_options
 | 
|---|
 | 33 | #pragma GCC target("amx-bf16")
 | 
|---|
 | 34 | #define __DISABLE_AMX_BF16__
 | 
|---|
 | 35 | #endif /* __AMX_BF16__ */
 | 
|---|
 | 36 | 
 | 
|---|
 | 37 | #if defined(__x86_64__) && defined(__AMX_BF16__)
 | 
|---|
 | 38 | #define _tile_dpbf16ps_internal(dst,src1,src2)                                  \
 | 
|---|
 | 39 |   __asm__ volatile\
 | 
|---|
 | 40 |   ("{tdpbf16ps\t%%tmm"#src2", %%tmm"#src1", %%tmm"#dst"|tdpbf16ps\t%%tmm"#dst", %%tmm"#src1", %%tmm"#src2"}" ::)
 | 
|---|
 | 41 | 
 | 
|---|
 | 42 | #define _tile_dpbf16ps(dst,src1,src2)                                   \
 | 
|---|
 | 43 |   _tile_dpbf16ps_internal (dst, src1, src2)
 | 
|---|
 | 44 | 
 | 
|---|
 | 45 | #endif
 | 
|---|
 | 46 | 
 | 
|---|
 | 47 | #ifdef __DISABLE_AMX_BF16__
 | 
|---|
 | 48 | #undef __DISABLE_AMX_BF16__
 | 
|---|
 | 49 | #pragma GCC pop_options
 | 
|---|
 | 50 | #endif /* __DISABLE_AMX_BF16__ */
 | 
|---|
 | 51 | 
 | 
|---|
 | 52 | #endif /* _AMXBF16INTRIN_H_INCLUDED */
 | 
|---|