ahmed/OpenCL-CTS
1
0
Fork 0
mirror of https://github.com/KhronosGroup/OpenCL-CTS.git synced 2026-03-19 06:09:01 +00:00
Code Issues Packages Projects Releases Wiki Activity

Adds testing for CL_PROGRAM_IL (#919)

Browse Source 
* 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>
This commit is contained in:
ellnor01
2020-08-28 15:31:52 +01:00
committed by GitHub
parent c001dc2d9c
commit a31e253397
2 changed files with 110 additions and 0 deletions
Download Patch File Download Diff File Expand all files Collapse all files

105
test_conformance/spirv_new/test_get_program_il.cpp Normal file
View File

@@ -0,0 +1,105 @@
/******************************************************************
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;
}