mirror of
https://github.com/KhronosGroup/OpenCL-CTS.git
synced 2026-03-19 14:09:03 +00:00
a31e253397
* Adds testing for CL_PROGRAM_IL Added a test to check SpirV as an IL for programs built with IL which includes a negative test for programs built without IL. Added a test_fail macro. Fixes #164 Change-Id: I908241242b369551806e43b90ab414f895d5c8f7 Signed-off-by: Ellen Norris-Thompson <ellen.norris-thompson@arm.com> * COMPUTE-11739 Removing unused platform and device_version Fixes #164 Change-Id: Ib1168f6396132b69996d07166e1b593fa933d245 Signed-off-by: Ellen Norris-Thompson <ellen.norris-thompson@arm.com>
105 lines
3.7 KiB
C++
105 lines
3.7 KiB
C++
/******************************************************************
|
|
Copyright (c) 2020 The Khronos Group Inc. All Rights Reserved.
|
|
|
|
This code is protected by copyright laws and contains material proprietary to
|
|
the Khronos Group, Inc. This is UNPUBLISHED PROPRIETARY SOURCE CODE that may not
|
|
be disclosed in whole or in part to third parties, and may not be reproduced,
|
|
republished, distributed, transmitted, displayed, broadcast or otherwise
|
|
exploited in any manner without the express prior written permission of Khronos
|
|
Group. The receipt or possession of this code does not convey any rights to
|
|
reproduce, disclose, or distribute its contents, or to manufacture, use, or sell
|
|
anything that it may describe, in whole or in part other than under the terms of
|
|
the Khronos Adopters Agreement or Khronos Conformance Test Source License
|
|
Agreement as executed between Khronos and the recipient.
|
|
******************************************************************/
|
|
|
|
#include "testBase.h"
|
|
|
|
const char *sample_kernel_code_single_line[] = {
|
|
"__kernel void sample_test(__global float *src, __global int *dst)\n"
|
|
"{\n"
|
|
" int tid = get_global_id(0);\n"
|
|
"\n"
|
|
" dst[tid] = (int)src[tid];\n"
|
|
"\n"
|
|
"}\n"
|
|
};
|
|
|
|
TEST_SPIRV_FUNC(get_program_il)
|
|
{
|
|
clProgramWrapper source_program;
|
|
size_t il_size = -1;
|
|
int error;
|
|
|
|
/* If a program has been created with clCreateProgramWithIL, CL_PROGRAM_IL
|
|
* should return the program IL it was created with and it's size */
|
|
if (gCoreILProgram || is_extension_available(deviceID, "cl_khr_il_program"))
|
|
{
|
|
clProgramWrapper il_program;
|
|
std::string spvStr = "op_function_none";
|
|
const char *spvName = spvStr.c_str();
|
|
|
|
std::vector<unsigned char> spirv_binary = readSPIRV(spvName);
|
|
|
|
int file_bytes = spirv_binary.size();
|
|
if (file_bytes == 0)
|
|
{
|
|
test_fail("ERROR: SPIRV file %s not found!\n", spvName);
|
|
}
|
|
|
|
/* Create program with IL */
|
|
unsigned char *spirv_buffer = &spirv_binary[0];
|
|
|
|
error = get_program_with_il(il_program, deviceID, context, spvName);
|
|
|
|
SPIRV_CHECK_ERROR(error, "Unable to create program with IL.");
|
|
if (il_program == NULL)
|
|
{
|
|
test_fail("ERROR: Unable to create test program!\n");
|
|
}
|
|
|
|
/* Check program IL is the same as the source IL */
|
|
unsigned char *buffer = new unsigned char[file_bytes];
|
|
error = clGetProgramInfo(il_program, CL_PROGRAM_IL, file_bytes, buffer,
|
|
&il_size);
|
|
SPIRV_CHECK_ERROR(error, "Unable to get program info.");
|
|
|
|
if (il_size != file_bytes)
|
|
{
|
|
test_fail("ERROR: Returned IL size is not the same as source IL "
|
|
"size (%lu "
|
|
"!= %lu)!\n",
|
|
il_size, file_bytes);
|
|
}
|
|
|
|
if (memcmp(buffer, spirv_buffer, file_bytes) != 0)
|
|
{
|
|
test_fail("ERROR: Returned IL is not the same as source IL!\n");
|
|
}
|
|
|
|
delete[] buffer;
|
|
}
|
|
|
|
/* CL_PROGRAM_IL shouldn't return IL value unless program is created with
|
|
* clCreateProgramWithIL */
|
|
error = create_single_kernel_helper_create_program(
|
|
context, &source_program, 1, sample_kernel_code_single_line);
|
|
if (source_program == NULL)
|
|
{
|
|
test_fail("ERROR: Unable to create test program!\n");
|
|
}
|
|
|
|
if (gCompilationMode != kSpir_v)
|
|
{
|
|
error =
|
|
clGetProgramInfo(source_program, CL_PROGRAM_IL, 0, NULL, &il_size);
|
|
SPIRV_CHECK_ERROR(error, "Unable to get program il length");
|
|
if (il_size != 0)
|
|
{
|
|
test_fail(
|
|
"ERROR: Returned length of non-IL program IL is non-zero!\n");
|
|
}
|
|
}
|
|
|
|
return 0;
|
|
} |