| 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 <amxint8intrin.h> directly; include <immintrin.h> instead."
|
|---|
| 26 | #endif
|
|---|
| 27 |
|
|---|
| 28 | #ifndef _AMXINT8INTRIN_H_INCLUDED
|
|---|
| 29 | #define _AMXINT8INTRIN_H_INCLUDED
|
|---|
| 30 |
|
|---|
| 31 | #if !defined(__AMX_INT8__)
|
|---|
| 32 | #pragma GCC push_options
|
|---|
| 33 | #pragma GCC target("amx-int8")
|
|---|
| 34 | #define __DISABLE_AMX_INT8__
|
|---|
| 35 | #endif /* __AMX_INT8__ */
|
|---|
| 36 |
|
|---|
| 37 | #if defined(__x86_64__) && defined(__AMX_INT8__)
|
|---|
| 38 | #define _tile_int8_dp_internal(name,dst,src1,src2) \
|
|---|
| 39 | __asm__ volatile \
|
|---|
| 40 | ("{"#name"\t%%tmm"#src2", %%tmm"#src1", %%tmm"#dst"|"#name"\t%%tmm"#dst", %%tmm"#src1", %%tmm"#src2"}" ::)
|
|---|
| 41 |
|
|---|
| 42 | #define _tile_dpbssd(dst,src1,src2) \
|
|---|
| 43 | _tile_int8_dp_internal (tdpbssd, dst, src1, src2)
|
|---|
| 44 |
|
|---|
| 45 | #define _tile_dpbsud(dst,src1,src2) \
|
|---|
| 46 | _tile_int8_dp_internal (tdpbsud, dst, src1, src2)
|
|---|
| 47 |
|
|---|
| 48 | #define _tile_dpbusd(dst,src1,src2) \
|
|---|
| 49 | _tile_int8_dp_internal (tdpbusd, dst, src1, src2)
|
|---|
| 50 |
|
|---|
| 51 | #define _tile_dpbuud(dst,src1,src2) \
|
|---|
| 52 | _tile_int8_dp_internal (tdpbuud, dst, src1, src2)
|
|---|
| 53 |
|
|---|
| 54 | #endif
|
|---|
| 55 |
|
|---|
| 56 | #ifdef __DISABLE_AMX_INT8__
|
|---|
| 57 | #undef __DISABLE_AMX_INT8__
|
|---|
| 58 | #pragma GCC pop_options
|
|---|
| 59 | #endif /* __DISABLE_AMX_INT8__ */
|
|---|
| 60 |
|
|---|
| 61 | #endif /* _AMXINT8INTRIN_H_INCLUDED */
|
|---|
