1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
|
// RUN: %clang_cc1 %s -ffreestanding -triple=x86_64-unknown-unknown \
// RUN: -target-feature +amx-movrs -emit-llvm -o - -Wall -Werror -pedantic \
// RUN: -Wno-gnu-statement-expression| FileCheck %s
#include <immintrin.h>
#include <stddef.h>
#define STRIDE 32
char buf[1024];
void test_tile_loadd(short row) {
// CHECK-LABEL: define dso_local void @test_tile_loadd(
// CHECK: call x86_amx @llvm.x86.tileloaddrs64.internal(i16 %{{.*}}, i16 %{{.*}}, ptr %{{.*}}, i64 %{{.*}})
// CHECK-NEXT: call <256 x i32> @llvm.x86.cast.tile.to.vector.v256i32(x86_amx %{{.*}})
__tile1024i a = {row, 8};
__tile_loaddrs(&a, buf, STRIDE);
}
void test_tile_loaddt1(short row) {
// CHECK-LABEL: define dso_local void @test_tile_loaddt1(
// CHECK: call x86_amx @llvm.x86.tileloaddrst164.internal(i16 %{{.*}}, i16 %{{.*}}, ptr %{{.*}}, i64 %{{.*}})
// CHECK-NEXT: call <256 x i32> @llvm.x86.cast.tile.to.vector.v256i32(x86_amx %{{.*}})
__tile1024i a = {row, 8};
__tile_stream_loaddrs(&a, buf, STRIDE);
}
void test_tile_loadd_macro(void *data) {
// CHECK-LABEL: define dso_local void @test_tile_loadd_macro(
// CHECK: call void @llvm.x86.tileloaddrs64(i8 {{.*}}, ptr %{{.*}}, i64 {{.*}})
// CHECK: call void @llvm.x86.tileloaddrst164(i8 {{.*}}, ptr %{{.*}}, i64 {{.*}})
_tile_loaddrs(4, data, STRIDE);
_tile_stream_loaddrs(2, data, STRIDE);
}
|
