Skip to content
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.

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

Porting rocPRIM onto HIP-Clang #22

Closed
aaronenyeshi opened this issue Aug 16, 2018 · 18 comments
Closed

Porting rocPRIM onto HIP-Clang #22

aaronenyeshi opened this issue Aug 16, 2018 · 18 comments

Comments

@aaronenyeshi
Copy link
Contributor

Hi rocPRIM team, I'm working on porting rocPRIM to be compiled with HIP-Clang. I'm running into some issues that I'm not sure how to resolve since I don't understand the nature of the test. Here is what it looks like:

/root/rocPRIM/test/rocprim/test_hip_block_histogram.cpp:167:73: error: implicit conversion from
      'unsigned long' to 'unsigned char' changes value from 1023 to 255 [-Werror,-Wconstant-conversion]
    std::vector<T> output = test_utils::get_random_data<T>(size, 0, bin - 1);
                            ~~~~~~~~~~                              ~~~~^~~
/root/rocPRIM/build/gtest/include/gtest/internal/gtest-internal.h:468:43: note: in instantiation of member
      function 'RocprimBlockHistogramInputArrayTests_Histogram_Test<params<unsigned char, unsigned char,
      1024, 1, 1024, rocprim::block_histogram_algorithm::using_sort> >::TestBody' requested here
  virtual Test* CreateTest() { return new TestClass; }
                                          ^
/root/rocPRIM/build/gtest/include/gtest/internal/gtest-internal.h:634:13: note: in instantiation of member
      function
      'testing::internal::TestFactoryImpl<RocprimBlockHistogramInputArrayTests_Histogram_Test<params<unsigned
      char, unsigned char, 1024, 1, 1024, rocprim::block_histogram_algorithm::using_sort> > >::CreateTest'
      requested here
        new TestFactoryImpl<TestClass>);
            ^

I've had this same error for a few other tests as well. I think that HIP-Clang compiler is a little more strict than the HCC option. Let me know what I should do to fix this. Thanks!

@jszuppe
Copy link
Contributor

jszuppe commented Aug 16, 2018

If you just want to make sure everything compiles, then you can locally remove -Werror flag that is set in main CMakeLists. You can then post all warnings here, so we can remove them.

@aaronenyeshi
Copy link
Contributor Author

Thanks, I'll work on the other build failures

@aaronenyeshi
Copy link
Contributor Author

aaronenyeshi commented Aug 24, 2018

I need some help with changing the implementation here: https://github.com/ROCmSoftwarePlatform/rocPRIM/blob/master/rocprim/include/rocprim/device/detail/device_reduce_by_key.hpp#L343

It seems that in CUDA specs, __shared__ variables cannot have an initialization as part of their declaration. So when compiling this code, I get:

In file included from /root/rocPRIM/test/rocprim/test_hip_device_run_length_encode.cpp:36:
In file included from /root/rocPRIM/rocprim/include/rocprim/rocprim.hpp:74:
In file included from /root/rocPRIM/rocprim/include/rocprim/device/device_reduce_by_key_hip.hpp:34:
/root/rocPRIM/rocprim/include/rocprim/device/detail/device_reduce_by_key.hpp:361:7: error: initialization
      is not supported for __shared__ variables.
    } storage;
      ^~~~~~~ 

I tried alternatives like using typedef, and initializing later. Or removing the __shared__ attribute, but these choices fix build issue, but causes seg faults during run.

@jszuppe
Copy link
Contributor

jszuppe commented Aug 24, 2018

I guess some type in that structure has nontivial default ctor. Is this the only place with that problem?

@aaronenyeshi
Copy link
Contributor Author

Seems to only occur in rocprim.hip.device_run_length_encode and hipcub.DeviceRunLengthEncode, both showing errors here

@jszuppe
Copy link
Contributor

jszuppe commented Aug 24, 2018

My guess is that result_type in https://github.com/ROCmSoftwarePlatform/rocPRIM/blob/master/rocprim/include/rocprim/device/detail/device_reduce_by_key.hpp#L342 does not have trivial default ctor.

You would need to replace it with raw storage: detail::raw_storage<result_type> carry_in;, this is a special wrapper which allows us to use types without trivial ctor in shared memory. In order to get reference of type result_type from modified storage.carry_in you just need to call get() on it, see https://github.com/ROCmSoftwarePlatform/rocPRIM/blob/master/rocprim/include/rocprim/detail/various.hpp#L214.

@aaronenyeshi
Copy link
Contributor Author

You're right, it seems the compiler cannot accept result_type carry_in with attribute __shared__ because sometimes we call this function with result_type as rocprim::tuple<unsigned int, unsigned int> which has ctor. I will try your raw_storage method

@jszuppe
Copy link
Contributor

jszuppe commented Aug 24, 2018

On Monday I'll pass that issue to my colleague who implemented that function. It's odd that hcc did not complain about it, IIRC it complained about such or similar situations in other places.

@aaronenyeshi
Copy link
Contributor Author

I tried your method and it seems to work partially. Of the 26 tests in rocprim.hip.device_run_length_encode, only 3 are failing now. I'll make a PR so your colleague has reference for what I tried.

@jszuppe
Copy link
Contributor

jszuppe commented Aug 24, 2018

Ok, thanks. We'll look into it. If you can, please provide test output in the PR. Question: are you certain that __shfl* functions work correctly on hip-clang?

@aaronenyeshi
Copy link
Contributor Author

I think it should work in the same way as HCC. The implementation follows that in HCC. Do you know any tests in rocPRIM will test these shfl functions extensively?

@jszuppe
Copy link
Contributor

jszuppe commented Aug 24, 2018

I think it should work in the same way as HCC.

That would mean they don't work for HIP, unless it [hip-clang] already includes change you made.

Do you know any tests in rocPRIM will test these shfl functions extensively?

No, we don't have any direct test for shfl functions. However, implementations of warp reduction and warp scan are quite straightforward, if they fail it's a strong indication there's something not right.

@aaronenyeshi
Copy link
Contributor Author

Yes HIP-Clang is built with the master branch of HIP. It isn't completed yet, and still in the works. the master branch does include the change for shfl that I made.

Okay, currently with HIP-Clang, my results look like this with -Werror disabled.

78% tests passed, 12 tests failed out of 55

Total Test time (real) = 142.08 sec

The following tests FAILED:
         10 - rocprim.hip.block_scan (Failed)
         16 - rocprim.hip.device_merge_sort (Failed)
         17 - rocprim.hip.device_partition (OTHER_FAULT)
         21 - rocprim.hip.device_run_length_encode (Failed)
         22 - rocprim.hip.device_scan (Failed)
         26 - rocprim.hip.device_select (Failed)
         29 - rocprim.hip.texture_cache_iterator (Not Run)
         41 - hipcub.BlockRadixSort (Failed)
         43 - hipcub.BlockScan (Failed)
         47 - hipcub.DeviceRunLengthEncode (Failed)
         49 - hipcub.DeviceScan (Failed)
         52 - hipcub.DeviceSelect (Failed)
Errors while running CTest

@jszuppe
Copy link
Contributor

jszuppe commented Aug 24, 2018

You can't compile rocprim.hip.texture_cache_iterator test?

@aaronenyeshi
Copy link
Contributor Author

No there is still build/link issue:

[ 50%] Building CXX object test/rocprim/CMakeFiles/test_hip_texture_cache_iterator.dir/test_hip_texture_cache_iterator.cpp.o
[100%] Linking CXX executable test_hip_texture_cache_iterator
warning: Linking two modules of different data layouts: '/tmp/libgtest-147987.o' is '' whereas 'llvm-link' is 'e-p:64:64-p1:64:64-p2:32:32-p3:32:32-p4:64:64-p5:32:32-p6:32:32-i64:64-v16:16-v24:32-v32:32-v48:64-v96:128-v192:256-v256:256-v512:512-v1024:1024-v2048:2048-n32:64-S32-A5'

warning: Linking two modules of different data layouts: '/tmp/libgtest_main-a0994b.o' is '' whereas 'llvm-link' is 'e-p:64:64-p1:64:64-p2:32:32-p3:32:32-p4:64:64-p5:32:32-p6:32:32-i64:64-v16:16-v24:32-v32:32-v48:64-v96:128-v192:256-v256:256-v512:512-v1024:1024-v2048:2048-n32:64-S32-A5'

warning: Linking two modules of different data layouts: '/tmp/libhip_hcc-eb0fe5.o' is '' whereas 'llvm-link' is 'e-p:64:64-p1:64:64-p2:32:32-p3:32:32-p4:64:64-p5:32:32-p6:32:32-i64:64-v16:16-v24:32-v32:32-v48:64-v96:128-v192:256-v256:256-v512:512-v1024:1024-v2048:2048-n32:64-S32-A5'

warning: Linking two modules of different data layouts: '/tmp/libhip_device-f273aa.o' is '' whereas 'llvm-link' is 'e-p:64:64-p1:64:64-p2:32:32-p3:32:32-p4:64:64-p5:32:32-p6:32:32-i64:64-v16:16-v24:32-v32:32-v48:64-v96:128-v192:256-v256:256-v512:512-v1024:1024-v2048:2048-n32:64-S32-A5'

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EN10test_utils16custom_test_typeIfEENS_22texture_cache_iteratorIS4_lEEPS4_9transformIS4_EEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator", i64, %"struct.test_utils::custom_test_type"*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EN10test_utils16custom_test_typeIfEENS_22texture_cache_iteratorIS4_lEEPS4_9transformIS4_EEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator", i64, %"struct.test_utils::custom_test_type"*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EN10test_utils16custom_test_typeIfEENS_22texture_cache_iteratorIS4_lEEPS4_9transformIS4_EEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator", i64, %"struct.test_utils::custom_test_type"*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EN10test_utils16custom_test_typeIfEENS_22texture_cache_iteratorIS4_lEEPS4_9transformIS4_EEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator", i64, %"struct.test_utils::custom_test_type"*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EN10test_utils16custom_test_typeIfEENS_22texture_cache_iteratorIS4_lEEPS4_9transformIS4_EEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator", i64, %"struct.test_utils::custom_test_type"*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EN10test_utils16custom_test_typeIfEENS_22texture_cache_iteratorIS4_lEEPS4_9transformIS4_EEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator", i64, %"struct.test_utils::custom_test_type"*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EN10test_utils16custom_test_typeIfEENS_22texture_cache_iteratorIS4_lEEPS4_9transformIS4_EEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator", i64, %"struct.test_utils::custom_test_type"*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EN10test_utils16custom_test_typeIfEENS_22texture_cache_iteratorIS4_lEEPS4_9transformIS4_EEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator", i64, %"struct.test_utils::custom_test_type"*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EN10test_utils16custom_test_typeIfEENS_22texture_cache_iteratorIS4_lEEPS4_9transformIS4_EEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator", i64, %"struct.test_utils::custom_test_type"*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EN10test_utils16custom_test_typeIfEENS_22texture_cache_iteratorIS4_lEEPS4_9transformIS4_EEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator", i64, %"struct.test_utils::custom_test_type"*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EN10test_utils16custom_test_typeIfEENS_22texture_cache_iteratorIS4_lEEPS4_9transformIS4_EEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator", i64, %"struct.test_utils::custom_test_type"*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EN10test_utils16custom_test_typeIfEENS_22texture_cache_iteratorIS4_lEEPS4_9transformIS4_EEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator", i64, %"struct.test_utils::custom_test_type"*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EN10test_utils16custom_test_typeIfEENS_22texture_cache_iteratorIS4_lEEPS4_9transformIS4_EEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator", i64, %"struct.test_utils::custom_test_type"*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EN10test_utils16custom_test_typeIfEENS_22texture_cache_iteratorIS4_lEEPS4_9transformIS4_EEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator", i64, %"struct.test_utils::custom_test_type"*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EN10test_utils16custom_test_typeIfEENS_22texture_cache_iteratorIS4_lEEPS4_9transformIS4_EEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator", i64, %"struct.test_utils::custom_test_type"*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EN10test_utils16custom_test_typeIfEENS_22texture_cache_iteratorIS4_lEEPS4_9transformIS4_EEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator", i64, %"struct.test_utils::custom_test_type"*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EN10test_utils16custom_test_typeIiEENS_22texture_cache_iteratorIS4_lEEPS4_9transformIS4_EEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.0", i64, %"struct.test_utils::custom_test_type.1"*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EN10test_utils16custom_test_typeIiEENS_22texture_cache_iteratorIS4_lEEPS4_9transformIS4_EEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.0", i64, %"struct.test_utils::custom_test_type.1"*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EN10test_utils16custom_test_typeIiEENS_22texture_cache_iteratorIS4_lEEPS4_9transformIS4_EEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.0", i64, %"struct.test_utils::custom_test_type.1"*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EN10test_utils16custom_test_typeIiEENS_22texture_cache_iteratorIS4_lEEPS4_9transformIS4_EEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.0", i64, %"struct.test_utils::custom_test_type.1"*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EN10test_utils16custom_test_typeIiEENS_22texture_cache_iteratorIS4_lEEPS4_9transformIS4_EEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.0", i64, %"struct.test_utils::custom_test_type.1"*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EN10test_utils16custom_test_typeIiEENS_22texture_cache_iteratorIS4_lEEPS4_9transformIS4_EEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.0", i64, %"struct.test_utils::custom_test_type.1"*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EN10test_utils16custom_test_typeIiEENS_22texture_cache_iteratorIS4_lEEPS4_9transformIS4_EEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.0", i64, %"struct.test_utils::custom_test_type.1"*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EN10test_utils16custom_test_typeIiEENS_22texture_cache_iteratorIS4_lEEPS4_9transformIS4_EEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.0", i64, %"struct.test_utils::custom_test_type.1"*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EN10test_utils16custom_test_typeIiEENS_22texture_cache_iteratorIS4_lEEPS4_9transformIS4_EEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.0", i64, %"struct.test_utils::custom_test_type.1"*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EN10test_utils16custom_test_typeIiEENS_22texture_cache_iteratorIS4_lEEPS4_9transformIS4_EEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.0", i64, %"struct.test_utils::custom_test_type.1"*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EN10test_utils16custom_test_typeIiEENS_22texture_cache_iteratorIS4_lEEPS4_9transformIS4_EEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.0", i64, %"struct.test_utils::custom_test_type.1"*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EN10test_utils16custom_test_typeIiEENS_22texture_cache_iteratorIS4_lEEPS4_9transformIS4_EEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.0", i64, %"struct.test_utils::custom_test_type.1"*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EN10test_utils16custom_test_typeIiEENS_22texture_cache_iteratorIS4_lEEPS4_9transformIS4_EEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.0", i64, %"struct.test_utils::custom_test_type.1"*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EN10test_utils16custom_test_typeIiEENS_22texture_cache_iteratorIS4_lEEPS4_9transformIS4_EEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.0", i64, %"struct.test_utils::custom_test_type.1"*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EN10test_utils16custom_test_typeIiEENS_22texture_cache_iteratorIS4_lEEPS4_9transformIS4_EEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.0", i64, %"struct.test_utils::custom_test_type.1"*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EN10test_utils16custom_test_typeIiEENS_22texture_cache_iteratorIS4_lEEPS4_9transformIS4_EEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.0", i64, %"struct.test_utils::custom_test_type.1"*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EyNS_22texture_cache_iteratorIylEEPy9transformIyEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.3", i64, i64*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EyNS_22texture_cache_iteratorIylEEPy9transformIyEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.3", i64, i64*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EyNS_22texture_cache_iteratorIylEEPy9transformIyEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.3", i64, i64*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EyNS_22texture_cache_iteratorIylEEPy9transformIyEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.3", i64, i64*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EyNS_22texture_cache_iteratorIylEEPy9transformIyEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.3", i64, i64*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EyNS_22texture_cache_iteratorIylEEPy9transformIyEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.3", i64, i64*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EyNS_22texture_cache_iteratorIylEEPy9transformIyEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.3", i64, i64*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EyNS_22texture_cache_iteratorIylEEPy9transformIyEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.3", i64, i64*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EyNS_22texture_cache_iteratorIylEEPy9transformIyEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.3", i64, i64*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EyNS_22texture_cache_iteratorIylEEPy9transformIyEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.3", i64, i64*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EyNS_22texture_cache_iteratorIylEEPy9transformIyEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.3", i64, i64*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EyNS_22texture_cache_iteratorIylEEPy9transformIyEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.3", i64, i64*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EyNS_22texture_cache_iteratorIylEEPy9transformIyEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.3", i64, i64*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EyNS_22texture_cache_iteratorIylEEPy9transformIyEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.3", i64, i64*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EyNS_22texture_cache_iteratorIylEEPy9transformIyEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.3", i64, i64*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj8EyNS_22texture_cache_iteratorIylEEPy9transformIyEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.3", i64, i64*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EfNS_22texture_cache_iteratorIflEEPf9transformIfEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.5", i64, float*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EfNS_22texture_cache_iteratorIflEEPf9transformIfEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.5", i64, float*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EfNS_22texture_cache_iteratorIflEEPf9transformIfEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.5", i64, float*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EfNS_22texture_cache_iteratorIflEEPf9transformIfEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.5", i64, float*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EfNS_22texture_cache_iteratorIflEEPf9transformIfEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.5", i64, float*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EfNS_22texture_cache_iteratorIflEEPf9transformIfEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.5", i64, float*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EfNS_22texture_cache_iteratorIflEEPf9transformIfEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.5", i64, float*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EfNS_22texture_cache_iteratorIflEEPf9transformIfEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.5", i64, float*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EfNS_22texture_cache_iteratorIflEEPf9transformIfEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.5", i64, float*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EfNS_22texture_cache_iteratorIflEEPf9transformIfEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.5", i64, float*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EfNS_22texture_cache_iteratorIflEEPf9transformIfEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.5", i64, float*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EfNS_22texture_cache_iteratorIflEEPf9transformIfEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.5", i64, float*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EfNS_22texture_cache_iteratorIflEEPf9transformIfEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.5", i64, float*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EfNS_22texture_cache_iteratorIflEEPf9transformIfEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.5", i64, float*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EfNS_22texture_cache_iteratorIflEEPf9transformIfEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.5", i64, float*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EfNS_22texture_cache_iteratorIflEEPf9transformIfEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.5", i64, float*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EfNS_22texture_cache_iteratorIflEEPf9transformIfEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.5", i64, float*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EfNS_22texture_cache_iteratorIflEEPf9transformIfEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.5", i64, float*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EfNS_22texture_cache_iteratorIflEEPf9transformIfEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.5", i64, float*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EfNS_22texture_cache_iteratorIflEEPf9transformIfEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.5", i64, float*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EfNS_22texture_cache_iteratorIflEEPf9transformIfEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.5", i64, float*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EfNS_22texture_cache_iteratorIflEEPf9transformIfEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.5", i64, float*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EfNS_22texture_cache_iteratorIflEEPf9transformIfEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.5", i64, float*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EfNS_22texture_cache_iteratorIflEEPf9transformIfEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.5", i64, float*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EfNS_22texture_cache_iteratorIflEEPf9transformIfEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.5", i64, float*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EfNS_22texture_cache_iteratorIflEEPf9transformIfEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.5", i64, float*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EfNS_22texture_cache_iteratorIflEEPf9transformIfEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.5", i64, float*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EfNS_22texture_cache_iteratorIflEEPf9transformIfEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.5", i64, float*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EfNS_22texture_cache_iteratorIflEEPf9transformIfEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.5", i64, float*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EfNS_22texture_cache_iteratorIflEEPf9transformIfEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.5", i64, float*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EfNS_22texture_cache_iteratorIflEEPf9transformIfEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.5", i64, float*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EfNS_22texture_cache_iteratorIflEEPf9transformIfEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.5", i64, float*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EhNS_22texture_cache_iteratorIhlEEPh9transformIhEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.7", i64, i8*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EhNS_22texture_cache_iteratorIhlEEPh9transformIhEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.7", i64, i8*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EhNS_22texture_cache_iteratorIhlEEPh9transformIhEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.7", i64, i8*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EhNS_22texture_cache_iteratorIhlEEPh9transformIhEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.7", i64, i8*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EhNS_22texture_cache_iteratorIhlEEPh9transformIhEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.7", i64, i8*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EhNS_22texture_cache_iteratorIhlEEPh9transformIhEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.7", i64, i8*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EhNS_22texture_cache_iteratorIhlEEPh9transformIhEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.7", i64, i8*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EhNS_22texture_cache_iteratorIhlEEPh9transformIhEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.7", i64, i8*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EhNS_22texture_cache_iteratorIhlEEPh9transformIhEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.7", i64, i8*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EhNS_22texture_cache_iteratorIhlEEPh9transformIhEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.7", i64, i8*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EhNS_22texture_cache_iteratorIhlEEPh9transformIhEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.7", i64, i8*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EhNS_22texture_cache_iteratorIhlEEPh9transformIhEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.7", i64, i8*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EhNS_22texture_cache_iteratorIhlEEPh9transformIhEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.7", i64, i8*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EhNS_22texture_cache_iteratorIhlEEPh9transformIhEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.7", i64, i8*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EhNS_22texture_cache_iteratorIhlEEPh9transformIhEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.7", i64, i8*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EhNS_22texture_cache_iteratorIhlEEPh9transformIhEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.7", i64, i8*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EhNS_22texture_cache_iteratorIhlEEPh9transformIhEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.7", i64, i8*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EhNS_22texture_cache_iteratorIhlEEPh9transformIhEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.7", i64, i8*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EhNS_22texture_cache_iteratorIhlEEPh9transformIhEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.7", i64, i8*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EhNS_22texture_cache_iteratorIhlEEPh9transformIhEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.7", i64, i8*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EhNS_22texture_cache_iteratorIhlEEPh9transformIhEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.7", i64, i8*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EhNS_22texture_cache_iteratorIhlEEPh9transformIhEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.7", i64, i8*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EhNS_22texture_cache_iteratorIhlEEPh9transformIhEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.7", i64, i8*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EhNS_22texture_cache_iteratorIhlEEPh9transformIhEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.7", i64, i8*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EhNS_22texture_cache_iteratorIhlEEPh9transformIhEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.7", i64, i8*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EhNS_22texture_cache_iteratorIhlEEPh9transformIhEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.7", i64, i8*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EhNS_22texture_cache_iteratorIhlEEPh9transformIhEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.7", i64, i8*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EhNS_22texture_cache_iteratorIhlEEPh9transformIhEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.7", i64, i8*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EhNS_22texture_cache_iteratorIhlEEPh9transformIhEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.7", i64, i8*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EhNS_22texture_cache_iteratorIhlEEPh9transformIhEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.7", i64, i8*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EhNS_22texture_cache_iteratorIhlEEPh9transformIhEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.7", i64, i8*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EhNS_22texture_cache_iteratorIhlEEPh9transformIhEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.7", i64, i8*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EjNS_22texture_cache_iteratorIjlEEPj9transformIjEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EjNS_22texture_cache_iteratorIjlEEPj9transformIjEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EjNS_22texture_cache_iteratorIjlEEPj9transformIjEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EjNS_22texture_cache_iteratorIjlEEPj9transformIjEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EjNS_22texture_cache_iteratorIjlEEPj9transformIjEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EjNS_22texture_cache_iteratorIjlEEPj9transformIjEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EjNS_22texture_cache_iteratorIjlEEPj9transformIjEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EjNS_22texture_cache_iteratorIjlEEPj9transformIjEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EjNS_22texture_cache_iteratorIjlEEPj9transformIjEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EjNS_22texture_cache_iteratorIjlEEPj9transformIjEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EjNS_22texture_cache_iteratorIjlEEPj9transformIjEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EjNS_22texture_cache_iteratorIjlEEPj9transformIjEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EjNS_22texture_cache_iteratorIjlEEPj9transformIjEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EjNS_22texture_cache_iteratorIjlEEPj9transformIjEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EjNS_22texture_cache_iteratorIjlEEPj9transformIjEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EjNS_22texture_cache_iteratorIjlEEPj9transformIjEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EjNS_22texture_cache_iteratorIjlEEPj9transformIjEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EjNS_22texture_cache_iteratorIjlEEPj9transformIjEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EjNS_22texture_cache_iteratorIjlEEPj9transformIjEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EjNS_22texture_cache_iteratorIjlEEPj9transformIjEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EjNS_22texture_cache_iteratorIjlEEPj9transformIjEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EjNS_22texture_cache_iteratorIjlEEPj9transformIjEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EjNS_22texture_cache_iteratorIjlEEPj9transformIjEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EjNS_22texture_cache_iteratorIjlEEPj9transformIjEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EjNS_22texture_cache_iteratorIjlEEPj9transformIjEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EjNS_22texture_cache_iteratorIjlEEPj9transformIjEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EjNS_22texture_cache_iteratorIjlEEPj9transformIjEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EjNS_22texture_cache_iteratorIjlEEPj9transformIjEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EjNS_22texture_cache_iteratorIjlEEPj9transformIjEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EjNS_22texture_cache_iteratorIjlEEPj9transformIjEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EjNS_22texture_cache_iteratorIjlEEPj9transformIjEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EjNS_22texture_cache_iteratorIjlEEPj9transformIjEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EiNS_22texture_cache_iteratorIilEEPi9transformIiEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EiNS_22texture_cache_iteratorIilEEPi9transformIiEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EiNS_22texture_cache_iteratorIilEEPi9transformIiEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EiNS_22texture_cache_iteratorIilEEPi9transformIiEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EiNS_22texture_cache_iteratorIilEEPi9transformIiEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EiNS_22texture_cache_iteratorIilEEPi9transformIiEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EiNS_22texture_cache_iteratorIilEEPi9transformIiEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EiNS_22texture_cache_iteratorIilEEPi9transformIiEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EiNS_22texture_cache_iteratorIilEEPi9transformIiEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EiNS_22texture_cache_iteratorIilEEPi9transformIiEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EiNS_22texture_cache_iteratorIilEEPi9transformIiEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EiNS_22texture_cache_iteratorIilEEPi9transformIiEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EiNS_22texture_cache_iteratorIilEEPi9transformIiEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EiNS_22texture_cache_iteratorIilEEPi9transformIiEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EiNS_22texture_cache_iteratorIilEEPi9transformIiEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EiNS_22texture_cache_iteratorIilEEPi9transformIiEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EiNS_22texture_cache_iteratorIilEEPi9transformIiEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EiNS_22texture_cache_iteratorIilEEPi9transformIiEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EiNS_22texture_cache_iteratorIilEEPi9transformIiEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EiNS_22texture_cache_iteratorIilEEPi9transformIiEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EiNS_22texture_cache_iteratorIilEEPi9transformIiEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EiNS_22texture_cache_iteratorIilEEPi9transformIiEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EiNS_22texture_cache_iteratorIilEEPi9transformIiEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EiNS_22texture_cache_iteratorIilEEPi9transformIiEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EiNS_22texture_cache_iteratorIilEEPi9transformIiEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EiNS_22texture_cache_iteratorIilEEPi9transformIiEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EiNS_22texture_cache_iteratorIilEEPi9transformIiEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EiNS_22texture_cache_iteratorIilEEPi9transformIiEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EiNS_22texture_cache_iteratorIilEEPi9transformIiEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EiNS_22texture_cache_iteratorIilEEPi9transformIiEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EiNS_22texture_cache_iteratorIilEEPi9transformIiEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

error: <unknown>:0:0: in function _ZN7rocprim6detail16transform_kernelILj256ELj16EiNS_22texture_cache_iteratorIilEEPi9transformIiEEEvT2_mT3_T4_ void (%"class.rocprim::texture_cache_iterator.9", i64, i32*, %struct.transform): unsupported indirect call to function __ockl_image_sample_1D

clang-7: error: amdgcn-link command failed with exit code 1 (use -v to see invocation)
[100%] Built target test_hip_texture_cache_iterator

@jszuppe
Copy link
Contributor

jszuppe commented Aug 24, 2018

ok, linking problem.

@VecSmith
Copy link
Contributor

@aaronenyeshi, we've been thinking that you can take full control of the develop-hip-clang branch, push any commits that you wish into that branch. If you want our opinion about some change instead of pushing directly into develop-hip-clang you can create a PR against develop-hip-clang and ask us for review. We may not be able to test the changes using our CI (with stable ROCm and using hcc), however we can still review them. If there are bugfixes or other changes that can be added to develop you can still create a PR against the develop branch. What do you think about such workflow?

@aaronenyeshi
Copy link
Contributor Author

That sounds like a good workflow to me. Thank you @ncrkblacksmith

Sign up for free to join this conversation on GitHub. Already have an account? Sign in to comment
Projects
None yet
Development

No branches or pull requests

3 participants