Skip to content

[SYCL][NFC] Extend ABI tests to cover device code #2725

New issue

Have a question about this project? Sign up for a free GitHub account to open an issue and contact its maintainers and the community.

Sign up for GitHub

By clicking “Sign up for GitHub”, you agree to our terms of service and privacy statement. We’ll occasionally send you account related emails.

Already on GitHub? Sign in to your account

Merged
merged 2 commits into from
Nov 5, 2020
Merged

[SYCL][NFC] Extend ABI tests to cover device code #2725

Show file tree
Hide file tree
Changes from all commits
Commits
Show all changes
2 commits
Select commit Hold shift + click to select a range
4f23f9b
[SYCL][NFC] Extend ABI tests to cover device code
Nov 3, 2020
e7d40b3
Test fix
Nov 3, 2020
File filter

Filter by extension

Filter by extension
Conversations
Failed to load comments.
Loading
Jump to
Jump to file
Failed to load files.
Loading
Diff view
Diff view
70 changes: 70 additions & 0 deletions sycl/test/abi/layout_accessors_device.cpp
View file
Open in desktop
Original file line number Diff line number Diff line change
@@ -0,0 +1,70 @@
// RUN: %clangxx -fsycl -fsycl-device-only -c -fno-color-diagnostics -Xclang -fdump-record-layouts %s | FileCheck %s
// REQUIRES: linux

// clang-format off

#include <CL/sycl/accessor.hpp>

using namespace cl::sycl;

//----------------------------------------------------------------------------//
// Global buffer accessor.
//----------------------------------------------------------------------------//

SYCL_EXTERNAL void hostAcc(accessor<int, 1, access::mode::read, access::target::global_buffer> Acc) {
(void)Acc.get_size();
}
// CHECK: 0 | class cl::sycl::accessor<int, 1, cl::sycl::access::mode::read, cl::sycl::access::target::global_buffer, cl::sycl::access::placeholder::false_t, class cl::sycl::ONEAPI::accessor_property_list<> >
// CHECK-NEXT: 0 | class cl::sycl::detail::accessor_common<int, 1, cl::sycl::access::mode::read, cl::sycl::access::target::global_buffer, cl::sycl::access::placeholder::false_t, class cl::sycl::ONEAPI::accessor_property_list<> > (base) (empty)
// CHECK-NEXT: 0 | class cl::sycl::detail::AccessorImplDevice<1> impl
// CHECK-NEXT: 0 | class cl::sycl::id<1> Offset
// CHECK-NEXT: 0 | class cl::sycl::detail::array<1> (base)
// CHECK-NEXT: 0 | size_t [1] common_array
// CHECK-NEXT: 8 | class cl::sycl::range<1> AccessRange
// CHECK-NEXT: 8 | class cl::sycl::detail::array<1> (base)
// CHECK-NEXT: 8 | size_t [1] common_array
// CHECK-NEXT: 16 | class cl::sycl::range<1> MemRange
// CHECK-NEXT: 16 | class cl::sycl::detail::array<1> (base)
// CHECK-NEXT: 16 | size_t [1] common_array
// CHECK-NEXT: 24 | union cl::sycl::accessor<int, 1, cl::sycl::access::mode::read, cl::sycl::access::target::global_buffer, cl::sycl::access::placeholder::false_t, class cl::sycl::ONEAPI::accessor_property_list<> >
// CHECK-NEXT: 24 | cl::sycl::accessor<int, 1, cl::sycl::access::mode::read, cl::sycl::access::target::global_buffer, cl::sycl::access::placeholder::false_t, class cl::sycl::ONEAPI::accessor_property_list<> >::ConcreteASPtrType MData
// CHECK-NEXT: | [sizeof=32, dsize=32, align=8,
// CHECK-NEXT: | nvsize=32, nvalign=8]

//----------------------------------------------------------------------------//
// Local accessor.
//----------------------------------------------------------------------------//

SYCL_EXTERNAL void hostAcc(accessor<int, 1, access::mode::read_write, access::target::local> Acc) {
(void)Acc.get_size();
}
// CHECK: 0 | class cl::sycl::accessor<int, 1, cl::sycl::access::mode::read_write, cl::sycl::access::target::local, cl::sycl::access::placeholder::false_t, class cl::sycl::ONEAPI::accessor_property_list<> >
// CHECK-NEXT: 0 | class cl::sycl::detail::accessor_common<int, 1, cl::sycl::access::mode::read_write, cl::sycl::access::target::local, cl::sycl::access::placeholder::false_t, class cl::sycl::ONEAPI::accessor_property_list<> > (base) (empty)
// CHECK-NEXT: 0 | class cl::sycl::detail::LocalAccessorBaseDevice<1> impl
// CHECK-NEXT: 0 | class cl::sycl::range<1> AccessRange
// CHECK-NEXT: 0 | class cl::sycl::detail::array<1> (base)
// CHECK-NEXT: 0 | size_t [1] common_array
// CHECK-NEXT: 8 | class cl::sycl::range<1> MemRange
// CHECK-NEXT: 8 | class cl::sycl::detail::array<1> (base)
// CHECK-NEXT: 8 | size_t [1] common_array
// CHECK-NEXT: 16 | class cl::sycl::id<1> Offset
// CHECK-NEXT: 16 | class cl::sycl::detail::array<1> (base)
// CHECK-NEXT: 16 | size_t [1] common_array
// CHECK-NEXT: 24 | cl::sycl::accessor<int, 1, cl::sycl::access::mode::read_write, cl::sycl::access::target::local, cl::sycl::access::placeholder::false_t, class cl::sycl::ONEAPI::accessor_property_list<> >::ConcreteASPtrType MData
// CHECK-NEXT: | [sizeof=32, dsize=32, align=8,
// CHECK-NEXT: | nvsize=32, nvalign=8]

//----------------------------------------------------------------------------//
// Image accessor.
//----------------------------------------------------------------------------//

SYCL_EXTERNAL void hostAcc(accessor<int4, 1, access::mode::read, access::target::image> Acc) {
(void)Acc.get_count();
}

// CHECK: 0 | class cl::sycl::accessor<class cl::sycl::vec<int, 4>, 1, cl::sycl::access::mode::read, cl::sycl::access::target::image, cl::sycl::access::placeholder::false_t, class cl::sycl::ONEAPI::accessor_property_list<> >
// CHECK-NEXT: 0 | class cl::sycl::detail::image_accessor<class cl::sycl::vec<int, 4>, 1, cl::sycl::access::mode::read, cl::sycl::access::target::image, cl::sycl::access::placeholder::false_t> (base)
// CHECK-NEXT: 0 | cl::sycl::detail::image_accessor<class cl::sycl::vec<int, 4>, 1, cl::sycl::access::mode::read, cl::sycl::access::target::image, cl::sycl::access::placeholder::false_t>::OCLImageTy MImageObj
// CHECK-NEXT: 8 | char [24] MPadding
// CHECK-NEXT: | [sizeof=32, dsize=32, align=8,
// CHECK-NEXT: | nvsize=32, nvalign=8]
0 sycl/test/abi/layout_accessors.cpp → sycl/test/abi/layout_accessors_host.cpp
View file
Open in desktop
File renamed without changes.
35 changes: 26 additions & 9 deletions sycl/test/abi/layout_array.cpp
View file
Open in desktop
Original file line number Diff line number Diff line change
@@ -1,4 +1,5 @@
// RUN: %clangxx -fsycl -c -fno-color-diagnostics -Xclang -fdump-record-layouts %s | FileCheck %s
// RUN: %clangxx -fsycl -fsycl-device-only -c -fno-color-diagnostics -Xclang -fdump-record-layouts %s | FileCheck %s
// REQUIRES: linux

// clang-format off
Expand All @@ -7,7 +8,7 @@
#include <CL/sycl.hpp>


void range(sycl::range<2>) {}
SYCL_EXTERNAL void range(sycl::range<2>) {}

// CHECK: 0 | class cl::sycl::range<2>
// CHECK-NEXT: 0 | class cl::sycl::detail::array<2> (base)
Expand All @@ -17,17 +18,17 @@ void range(sycl::range<2>) {}

//----------------------------

void id(sycl::id<2>) {}
SYCL_EXTERNAL void id(sycl::id<2>) {}

// CHECK: 0 | class cl::sycl::id<3>
// CHECK-NEXT: 0 | class cl::sycl::detail::array<3> (base)
// CHECK-NEXT: 0 | size_t [3] common_array
// CHECK-NEXT: | [sizeof=24, dsize=24, align=8,
// CHECK-NEXT: | nvsize=24, nvalign=8]
// CHECK: 0 | class cl::sycl::id<2>
// CHECK-NEXT: 0 | class cl::sycl::detail::array<2> (base)
// CHECK-NEXT: 0 | size_t [2] common_array
// CHECK-NEXT: | [sizeof=16, dsize=16, align=8,
// CHECK-NEXT: | nvsize=16, nvalign=8]

//----------------------------

void item(sycl::item<2>) {}
SYCL_EXTERNAL void item(sycl::item<2>) {}

// CHECK: 0 | class cl::sycl::item<2, true>
// CHECK-NEXT: 0 | struct cl::sycl::detail::ItemBase<2, true> MImpl
Expand All @@ -45,7 +46,7 @@ void item(sycl::item<2>) {}

//----------------------------

void nd_item(sycl::nd_item<2>) {}
SYCL_EXTERNAL void nd_item(sycl::nd_item<2>) {}

// CHECK: 0 | class cl::sycl::nd_item<2>
// CHECK-NEXT: 0 | class cl::sycl::item<2, true> globalItem
Expand Down Expand Up @@ -82,3 +83,19 @@ void nd_item(sycl::nd_item<2>) {}
// CHECK-NEXT: 128 | size_t [2] common_array
// CHECK-NEXT: | [sizeof=144, dsize=144, align=8,
// CHECK-NEXT: | nvsize=144, nvalign=8]

//----------------------------

SYCL_EXTERNAL void nd_range(sycl::nd_range<2>) {}
// CHECK: 0 | class cl::sycl::nd_range<2>
// CHECK-NEXT: 0 | class cl::sycl::range<2> globalSize
// CHECK-NEXT: 0 | class cl::sycl::detail::array<2> (base)
// CHECK-NEXT: 0 | size_t [2] common_array
// CHECK-NEXT: 16 | class cl::sycl::range<2> localSize
// CHECK-NEXT: 16 | class cl::sycl::detail::array<2> (base)
// CHECK-NEXT: 16 | size_t [2] common_array
// CHECK-NEXT: 32 | class cl::sycl::id<2> offset
// CHECK-NEXT: 32 | class cl::sycl::detail::array<2> (base)
// CHECK-NEXT: 32 | size_t [2] common_array
// CHECK-NEXT: | [sizeof=48, dsize=48, align=8,
// CHECK-NEXT: | nvsize=48, nvalign=8]
5 changes: 3 additions & 2 deletions sycl/test/abi/layout_vec.cpp
View file
Open in desktop
Original file line number Diff line number Diff line change
@@ -1,11 +1,12 @@
// RUN: %clangxx -fsycl -c -fno-color-diagnostics -Xclang -fdump-record-layouts %s | FileCheck %s
// RUN: %clangxx -fsycl -fsycl-device-only -c -fno-color-diagnostics -Xclang -fdump-record-layouts %s | FileCheck %s
// REQUIRES: linux

// clang-format off

#include <CL/sycl/types.hpp>

void foo(sycl::vec<int, 4>) {}
SYCL_EXTERNAL void foo(sycl::vec<int, 4>) {}

// CHECK: 0 | class cl::sycl::vec<int, 4>
// CHECK-NEXT: 0 | cl::sycl::vec<int, 4>::DataType m_Data
Expand All @@ -14,7 +15,7 @@ void foo(sycl::vec<int, 4>) {}

//--------------------------------------

void foo(sycl::vec<bool, 16>) {}
SYCL_EXTERNAL void foo(sycl::vec<bool, 16>) {}

// CHECK: 0 | class cl::sycl::vec<_Bool, 16>
// CHECK-NEXT: 0 | cl::sycl::vec<_Bool, 16>::DataType m_Data
Expand Down