939d8309db
INTEL ADVANCED MATRIX EXTENSIONS (AMX). AMX is a new programming paradigm, it has a set of 2-dimensional registers (TILES) representing sub-arrays from a larger 2-dimensional memory image and operate on TILES. These intrinsics use direct TMM register number as its params. Spec can be found in Chapter 3 here https://software.intel.com/content/www/us/en/develop/download/intel-architecture-instruction-set-extensions-programming-reference.html Reviewed By: craig.topper Differential Revision: https://reviews.llvm.org/D83111
18 lines
1.3 KiB
C
18 lines
1.3 KiB
C
// RUN: %clang_cc1 %s -ffreestanding -triple=x86_64-unknown-unknown -target-feature +amx-tile -target-feature +amx-int8 -target-feature +amx-bf16 -emit-llvm -fsyntax-only -verify
|
|
|
|
#include <immintrin.h>
|
|
|
|
void test_amx(void *data) {
|
|
_tile_zero(16); // expected-error {{argument value 16 is outside the valid range [0, 7]}}
|
|
_tile_loadd(19, data, 16); // expected-error {{argument value 19 is outside the valid range [0, 7]}}
|
|
_tile_stream_loadd(23, data, 1); // expected-error {{argument value 23 is outside the valid range [0, 7]}}
|
|
_tile_stored(88, data, 1); // expected-error {{argument value 88 is outside the valid range [0, 7]}}
|
|
_tile_dpbssd(16, 2, 3); // expected-error {{argument value 16 is outside the valid range [0, 7]}}
|
|
_tile_dpbssd(0, 16, 3); // expected-error {{argument value 16 is outside the valid range [0, 7]}}
|
|
_tile_dpbuud(0, 2, 16); // expected-error {{argument value 16 is outside the valid range [0, 7]}}
|
|
_tile_dpbsud(1, 1, 3); // expected-error {{tile arguments must refer to different tiles}}
|
|
_tile_dpbsud(7, 1, 7); // expected-error {{tile arguments must refer to different tiles}}
|
|
_tile_dpbsud(4, 3, 3); // expected-error {{tile arguments must refer to different tiles}}
|
|
_tile_dpbf16ps(4, 3, 3); // expected-error {{tile arguments must refer to different tiles}}
|
|
}
|