Skip to content
Snippets Groups Projects
Commit 29181ce4 authored by Charles Villard's avatar Charles Villard Committed by Maxence Naud
Browse files

edit: TensorImpl: try to fix template ?

parent cf94ef7a
No related branches found
No related tags found
2 merge requests!75Update 0.5.1 -> 0.6.0,!40Fix template compilation and warnings
Hide whitespace changes
Inline Side-by-side
include/aidge/backend/cuda/data/TensorImpl.hpp
+ 12
− 9
View file @ 29181ce4
...@@ -21,20 +21,23 @@ ...@@ -21,20 +21,23 @@
namespace Aidge { namespace Aidge {
template <typename SRC_T, typename DST_T> template <typename SRC_T, typename DST_T>
typename std::enable_if<!std::is_same<half_float::half, DST_T>::value && !std::is_same<half_float::half, SRC_T>::value>::type std::enable_if_t<
thrust_copy(const SRC_T* /*srcData*/, DST_T* /*dstData*/, size_t /*size*/); !(std::is_same<half_float::half, DST_T>::value
|| std::is_same<half_float::half, SRC_T>::value)>
thrust_copy(const SRC_T* srcData, DST_T* dstData, size_t size);
template <typename SRC_T, typename DST_T = half_float::half> void
typename std::enable_if<!std::is_same<half_float::half, SRC_T>::value>::type thrust_copy(const half_float::half* srcData, half_float::half* dstData, size_t size);
thrust_copy(const SRC_T *srcData, half_float::half *dstData, size_t size);
template <typename SRC_T = half_float::half, typename DST_T> template <typename DST_T>
typename std::enable_if<!std::is_same<half_float::half, DST_T>::value>::type std::enable_if_t<!std::is_same<half_float::half, DST_T>::value>
thrust_copy(const half_float::half* srcData, DST_T* dstData, size_t size); thrust_copy(const half_float::half* srcData, DST_T* dstData, size_t size);
template <typename SRC_T = half_float::half, typename DST_T = half_float::half> template <typename SRC_T>
void thrust_copy(const half_float::half* srcData, half_float::half* dstData, size_t size); std::enable_if_t<!std::is_same<half_float::half, SRC_T>::value>
thrust_copy(const SRC_T* srcData, half_float::half* dstData, size_t size);
/** /**
* @brief Abstract class for the TensorImpl_cuda class template. * @brief Abstract class for the TensorImpl_cuda class template.
......
src/data/TensorImpl.cu
+ 181
− 166
View file @ 29181ce4
...@@ -14,17 +14,6 @@ ...@@ -14,17 +14,6 @@
#include <thrust/equal.h> #include <thrust/equal.h>
#include <thrust/device_ptr.h> #include <thrust/device_ptr.h>
template <typename SRC_T, typename DST_T>
typename std::enable_if<!std::is_same<half_float::half, DST_T>::value &&
!std::is_same<half_float::half, SRC_T>::value>
::type
Aidge::thrust_copy(const SRC_T* srcData, DST_T* dstData, size_t size)
{
const thrust::device_ptr<const SRC_T> thrustSrcPtr(srcData);
thrust::device_ptr<DST_T> thrustDstPtr(dstData);
thrust::copy(thrustSrcPtr, thrustSrcPtr + size, thrustDstPtr);
}
template <typename SRC_T> template <typename SRC_T>
__global__ void __global__ void
cudaCopyToH_kernel(const SRC_T* srcData, cudaCopyToH_kernel(const SRC_T* srcData,
...@@ -39,15 +28,6 @@ cudaCopyToH_kernel(const SRC_T* srcData, ...@@ -39,15 +28,6 @@ cudaCopyToH_kernel(const SRC_T* srcData,
} }
} }
template <typename SRC_T, typename DST_T>
typename std::enable_if<!std::is_same<half_float::half, SRC_T>::value>::type
Aidge::thrust_copy(const SRC_T* srcData, half_float::half* dstData, size_t size)
{
cudaCopyToH_kernel<SRC_T><<<(size + 255) / 256, 256>>>
(srcData, reinterpret_cast<__half*>(dstData), size);
CHECK_CUDA_STATUS(cudaPeekAtLastError());
}
template <typename DST_T> template <typename DST_T>
__global__ void __global__ void
cudaCopyFromH_kernel(const __half* srcData, cudaCopyFromH_kernel(const __half* srcData,
...@@ -62,15 +42,6 @@ cudaCopyFromH_kernel(const __half* srcData, ...@@ -62,15 +42,6 @@ cudaCopyFromH_kernel(const __half* srcData,
} }
} }
template <typename SRC_T, typename DST_T>
typename std::enable_if<!std::is_same<half_float::half, DST_T>::value>::type
Aidge::thrust_copy(const half_float::half* srcData, DST_T* dstData, size_t size)
{
cudaCopyFromH_kernel<DST_T><<<(size + 255) / 256, 256>>>
(reinterpret_cast<const __half*>(srcData), dstData, size);
CHECK_CUDA_STATUS(cudaPeekAtLastError());
}
__global__ void __global__ void
cudaCopyHToH_kernel(const __half* srcData, cudaCopyHToH_kernel(const __half* srcData,
__half* dstData, __half* dstData,
...@@ -84,14 +55,6 @@ cudaCopyHToH_kernel(const __half* srcData, ...@@ -84,14 +55,6 @@ cudaCopyHToH_kernel(const __half* srcData,
} }
} }
template <typename SRC_T, typename DST_T>
void Aidge::thrust_copy(const half_float::half* srcData, half_float::half* dstData, size_t size)
{
cudaCopyHToH_kernel<<<(size + 255) / 256, 256>>>
(reinterpret_cast<const __half*>(srcData), reinterpret_cast<__half*>(dstData), size);
CHECK_CUDA_STATUS(cudaPeekAtLastError());
}
template <class T> template <class T>
bool Aidge::TensorImpl_cuda<T>::operator==(const TensorImpl &otherImpl) const { bool Aidge::TensorImpl_cuda<T>::operator==(const TensorImpl &otherImpl) const {
const auto& otherImplCuda = static_cast<const TensorImpl_cuda<T>&>(otherImpl); const auto& otherImplCuda = static_cast<const TensorImpl_cuda<T>&>(otherImpl);
...@@ -104,135 +67,187 @@ bool Aidge::TensorImpl_cuda<T>::operator==(const TensorImpl &otherImpl) const { ...@@ -104,135 +67,187 @@ bool Aidge::TensorImpl_cuda<T>::operator==(const TensorImpl &otherImpl) const {
return thrust::equal(thrustData, thrustData + mNbElts, thrustOtherData); return thrust::equal(thrustData, thrustData + mNbElts, thrustOtherData);
} }
//// Thrust copy
template <typename SRC_T, typename DST_T>
std::enable_if_t<
!(std::is_same<half_float::half, DST_T>::value
|| std::is_same<half_float::half, SRC_T>::value)>
Aidge::thrust_copy(const SRC_T* srcData, DST_T* dstData, size_t size)
{
const thrust::device_ptr<const SRC_T> thrustSrcPtr(srcData);
thrust::device_ptr<DST_T> thrustDstPtr(dstData);
thrust::copy(thrustSrcPtr, thrustSrcPtr + size, thrustDstPtr);
}
void
Aidge::thrust_copy(const half_float::half* srcData, half_float::half* dstData, size_t size)
{
cudaCopyHToH_kernel<<<(size + 255) / 256, 256>>>
(reinterpret_cast<const __half*>(srcData), reinterpret_cast<__half*>(dstData), size);
CHECK_CUDA_STATUS(cudaPeekAtLastError());
}
template <typename DST_T>
std::enable_if_t<!std::is_same<half_float::half, DST_T>::value>
Aidge::thrust_copy(const half_float::half* srcData, DST_T* dstData, size_t size)
{
cudaCopyFromH_kernel<DST_T><<<(size + 255) / 256, 256>>>
(reinterpret_cast<const __half*>(srcData), dstData, size);
CHECK_CUDA_STATUS(cudaPeekAtLastError());
}
template <typename SRC_T>
std::enable_if_t<!std::is_same<half_float::half, SRC_T>::value>
Aidge::thrust_copy(const SRC_T* srcData, half_float::half* dstData, size_t size)
{
cudaCopyToH_kernel<SRC_T><<<(size + 255) / 256, 256>>>
(srcData, reinterpret_cast<__half*>(dstData), size);
CHECK_CUDA_STATUS(cudaPeekAtLastError());
}
/// End Thrust copy
// double // double
template void Aidge::thrust_copy<>(double const*, double*, size_t); template<> void Aidge::thrust_copy(double const*, double*, size_t);
template void Aidge::thrust_copy<>(double const*, float*, size_t); template<> void Aidge::thrust_copy(double const*, float*, size_t);
template void Aidge::thrust_copy<>(double const*, half_float::half*, size_t); template<> void Aidge::thrust_copy(double const*, half_float::half*, size_t);
template void Aidge::thrust_copy<>(double const*, int64_t*, size_t); template<> void Aidge::thrust_copy(double const*, int64_t*, size_t);
template void Aidge::thrust_copy<>(double const*, int32_t*, size_t); template<> void Aidge::thrust_copy(double const*, int32_t*, size_t);
template void Aidge::thrust_copy<>(double const*, int16_t*, size_t); template<> void Aidge::thrust_copy(double const*, int16_t*, size_t);
template void Aidge::thrust_copy<>(double const*, int8_t*, size_t); template<> void Aidge::thrust_copy(double const*, int8_t*, size_t);
template void Aidge::thrust_copy<>(double const*, uint64_t*, size_t); template<> void Aidge::thrust_copy(double const*, uint64_t*, size_t);
template void Aidge::thrust_copy<>(double const*, uint32_t*, size_t); template<> void Aidge::thrust_copy(double const*, uint32_t*, size_t);
template void Aidge::thrust_copy<>(double const*, uint16_t*, size_t); template<> void Aidge::thrust_copy(double const*, uint16_t*, size_t);
template void Aidge::thrust_copy<>(double const*, uint8_t*, size_t); template<> void Aidge::thrust_copy(double const*, uint8_t*, size_t);
// float // float
template void Aidge::thrust_copy<>(float const*, double*, size_t); template<> void Aidge::thrust_copy(float const*, double*, size_t);
template void Aidge::thrust_copy<>(float const*, float*, size_t); template<> void Aidge::thrust_copy(float const*, float*, size_t);
template void Aidge::thrust_copy<>(float const*, half_float::half*, size_t); template<> void Aidge::thrust_copy(float const*, half_float::half*, size_t);
template void Aidge::thrust_copy<>(float const*, int64_t*, size_t); template<> void Aidge::thrust_copy(float const*, int64_t*, size_t);
template void Aidge::thrust_copy<>(float const*, int32_t*, size_t); template<> void Aidge::thrust_copy(float const*, int32_t*, size_t);
template void Aidge::thrust_copy<>(float const*, int16_t*, size_t); template<> void Aidge::thrust_copy(float const*, int16_t*, size_t);
template void Aidge::thrust_copy<>(float const*, int8_t*, size_t); template<> void Aidge::thrust_copy(float const*, int8_t*, size_t);
template void Aidge::thrust_copy<>(float const*, uint64_t*, size_t); template<> void Aidge::thrust_copy(float const*, uint64_t*, size_t);
template void Aidge::thrust_copy<>(float const*, uint32_t*, size_t); template<> void Aidge::thrust_copy(float const*, uint32_t*, size_t);
template void Aidge::thrust_copy<>(float const*, uint16_t*, size_t); template<> void Aidge::thrust_copy(float const*, uint16_t*, size_t);
template void Aidge::thrust_copy<>(float const*, uint8_t*, size_t); template<> void Aidge::thrust_copy(float const*, uint8_t*, size_t);
// half_float::half // half_float::half
template void Aidge::thrust_copy<>(half_float::half const*, double*, size_t); template<> void Aidge::thrust_copy(half_float::half const*, double*, size_t);
template void Aidge::thrust_copy<>(half_float::half const*, float*, size_t); template<> void Aidge::thrust_copy(half_float::half const*, float*, size_t);
template void Aidge::thrust_copy<>(half_float::half const*, half_float::half*, size_t); //template<> void Aidge::thrust_copy(const half_float::half*, half_float::half*, size_t);
template void Aidge::thrust_copy<>(half_float::half const*, int64_t*, size_t); template<> void Aidge::thrust_copy(half_float::half const*, int64_t*, size_t);
template void Aidge::thrust_copy<>(half_float::half const*, int32_t*, size_t); template<> void Aidge::thrust_copy(half_float::half const*, int32_t*, size_t);
template void Aidge::thrust_copy<>(half_float::half const*, int16_t*, size_t); template<> void Aidge::thrust_copy(half_float::half const*, int16_t*, size_t);
template void Aidge::thrust_copy<>(half_float::half const*, int8_t*, size_t); template<> void Aidge::thrust_copy(half_float::half const*, int8_t*, size_t);
template void Aidge::thrust_copy<>(half_float::half const*, uint64_t*, size_t); template<> void Aidge::thrust_copy(half_float::half const*, uint64_t*, size_t);
template void Aidge::thrust_copy<>(half_float::half const*, uint32_t*, size_t); template<> void Aidge::thrust_copy(half_float::half const*, uint32_t*, size_t);
template void Aidge::thrust_copy<>(half_float::half const*, uint16_t*, size_t); template<> void Aidge::thrust_copy(half_float::half const*, uint16_t*, size_t);
template void Aidge::thrust_copy<>(half_float::half const*, uint8_t*, size_t); template<> void Aidge::thrust_copy(half_float::half const*, uint8_t*, size_t);
// int64_t
template void Aidge::thrust_copy<>(int64_t const*, double*, size_t); // int64_t
template void Aidge::thrust_copy<>(int64_t const*, float*, size_t); template<> void Aidge::thrust_copy(int64_t const*, double*, size_t);
template void Aidge::thrust_copy<>(int64_t const*, half_float::half*, size_t); template<> void Aidge::thrust_copy(int64_t const*, float*, size_t);
template void Aidge::thrust_copy<>(int64_t const*, int64_t*, size_t); template<> void Aidge::thrust_copy(int64_t const*, half_float::half*, size_t);
template void Aidge::thrust_copy<>(int64_t const*, int32_t*, size_t); template<> void Aidge::thrust_copy(int64_t const*, int64_t*, size_t);
template void Aidge::thrust_copy<>(int64_t const*, int16_t*, size_t); template<> void Aidge::thrust_copy(int64_t const*, int32_t*, size_t);
template void Aidge::thrust_copy<>(int64_t const*, int8_t*, size_t); template<> void Aidge::thrust_copy(int64_t const*, int16_t*, size_t);
template void Aidge::thrust_copy<>(int64_t const*, uint64_t*, size_t); template<> void Aidge::thrust_copy(int64_t const*, int8_t*, size_t);
template void Aidge::thrust_copy<>(int64_t const*, uint32_t*, size_t); template<> void Aidge::thrust_copy(int64_t const*, uint64_t*, size_t);
template void Aidge::thrust_copy<>(int64_t const*, uint16_t*, size_t); template<> void Aidge::thrust_copy(int64_t const*, uint32_t*, size_t);
template void Aidge::thrust_copy<>(int64_t const*, uint8_t*, size_t); template<> void Aidge::thrust_copy(int64_t const*, uint16_t*, size_t);
// int32_t template<> void Aidge::thrust_copy(int64_t const*, uint8_t*, size_t);
template void Aidge::thrust_copy<>(int32_t const*, double*, size_t);
template void Aidge::thrust_copy<>(int32_t const*, float*, size_t); // int32_t
template void Aidge::thrust_copy<>(int32_t const*, half_float::half*, size_t); template<> void Aidge::thrust_copy(int32_t const*, double*, size_t);
template void Aidge::thrust_copy<>(int32_t const*, int64_t*, size_t); template<> void Aidge::thrust_copy(int32_t const*, float*, size_t);
template void Aidge::thrust_copy<>(int32_t const*, int32_t*, size_t); template<> void Aidge::thrust_copy(int32_t const*, half_float::half*, size_t);
template void Aidge::thrust_copy<>(int32_t const*, int16_t*, size_t); template<> void Aidge::thrust_copy(int32_t const*, int64_t*, size_t);
template void Aidge::thrust_copy<>(int32_t const*, int8_t*, size_t); template<> void Aidge::thrust_copy(int32_t const*, int32_t*, size_t);
template void Aidge::thrust_copy<>(int32_t const*, uint64_t*, size_t); template<> void Aidge::thrust_copy(int32_t const*, int16_t*, size_t);
template void Aidge::thrust_copy<>(int32_t const*, uint32_t*, size_t); template<> void Aidge::thrust_copy(int32_t const*, int8_t*, size_t);
template void Aidge::thrust_copy<>(int32_t const*, uint16_t*, size_t); template<> void Aidge::thrust_copy(int32_t const*, uint64_t*, size_t);
template void Aidge::thrust_copy<>(int32_t const*, uint8_t*, size_t); template<> void Aidge::thrust_copy(int32_t const*, uint32_t*, size_t);
// int16_t template<> void Aidge::thrust_copy(int32_t const*, uint16_t*, size_t);
template void Aidge::thrust_copy<>(int16_t const*, double*, size_t); template<> void Aidge::thrust_copy(int32_t const*, uint8_t*, size_t);
template void Aidge::thrust_copy<>(int16_t const*, float*, size_t);
template void Aidge::thrust_copy<>(int16_t const*, half_float::half*, size_t); // int16_t
template void Aidge::thrust_copy<>(int16_t const*, int64_t*, size_t); template<> void Aidge::thrust_copy(int16_t const*, double*, size_t);
template void Aidge::thrust_copy<>(int16_t const*, int32_t*, size_t); template<> void Aidge::thrust_copy(int16_t const*, float*, size_t);
template void Aidge::thrust_copy<>(int16_t const*, int16_t*, size_t); template<> void Aidge::thrust_copy(int16_t const*, half_float::half*, size_t);
template void Aidge::thrust_copy<>(int16_t const*, int8_t*, size_t); template<> void Aidge::thrust_copy(int16_t const*, int64_t*, size_t);
template void Aidge::thrust_copy<>(int16_t const*, uint64_t*, size_t); template<> void Aidge::thrust_copy(int16_t const*, int32_t*, size_t);
template void Aidge::thrust_copy<>(int16_t const*, uint32_t*, size_t); template<> void Aidge::thrust_copy(int16_t const*, int16_t*, size_t);
template void Aidge::thrust_copy<>(int16_t const*, uint16_t*, size_t); template<> void Aidge::thrust_copy(int16_t const*, int8_t*, size_t);
template void Aidge::thrust_copy<>(int16_t const*, uint8_t*, size_t); template<> void Aidge::thrust_copy(int16_t const*, uint64_t*, size_t);
// int8_t template<> void Aidge::thrust_copy(int16_t const*, uint32_t*, size_t);
template void Aidge::thrust_copy<>(int8_t const*, double*, size_t); template<> void Aidge::thrust_copy(int16_t const*, uint16_t*, size_t);
template void Aidge::thrust_copy<>(int8_t const*, float*, size_t); template<> void Aidge::thrust_copy(int16_t const*, uint8_t*, size_t);
template void Aidge::thrust_copy<>(int8_t const*, half_float::half*, size_t);
template void Aidge::thrust_copy<>(int8_t const*, int64_t*, size_t); // int8_t
template void Aidge::thrust_copy<>(int8_t const*, int32_t*, size_t); template<> void Aidge::thrust_copy(int8_t const*, double*, size_t);
template void Aidge::thrust_copy<>(int8_t const*, int16_t*, size_t); template<> void Aidge::thrust_copy(int8_t const*, float*, size_t);
template void Aidge::thrust_copy<>(int8_t const*, int8_t*, size_t); template<> void Aidge::thrust_copy(int8_t const*, half_float::half*, size_t);
template void Aidge::thrust_copy<>(int8_t const*, uint64_t*, size_t); template<> void Aidge::thrust_copy(int8_t const*, int64_t*, size_t);
template void Aidge::thrust_copy<>(int8_t const*, uint32_t*, size_t); template<> void Aidge::thrust_copy(int8_t const*, int32_t*, size_t);
template void Aidge::thrust_copy<>(int8_t const*, uint16_t*, size_t); template<> void Aidge::thrust_copy(int8_t const*, int16_t*, size_t);
template void Aidge::thrust_copy<>(int8_t const*, uint8_t*, size_t); template<> void Aidge::thrust_copy(int8_t const*, int8_t*, size_t);
// uint64_t template<> void Aidge::thrust_copy(int8_t const*, uint64_t*, size_t);
template void Aidge::thrust_copy<>(uint64_t const*, double*, size_t); template<> void Aidge::thrust_copy(int8_t const*, uint32_t*, size_t);
template void Aidge::thrust_copy<>(uint64_t const*, float*, size_t); template<> void Aidge::thrust_copy(int8_t const*, uint16_t*, size_t);
template void Aidge::thrust_copy<>(uint64_t const*, half_float::half*, size_t); template<> void Aidge::thrust_copy(int8_t const*, uint8_t*, size_t);
template void Aidge::thrust_copy<>(uint64_t const*, int64_t*, size_t);
template void Aidge::thrust_copy<>(uint64_t const*, int32_t*, size_t); // uint64_t
template void Aidge::thrust_copy<>(uint64_t const*, int16_t*, size_t); template<> void Aidge::thrust_copy(uint64_t const*, double*, size_t);
template void Aidge::thrust_copy<>(uint64_t const*, int8_t*, size_t); template<> void Aidge::thrust_copy(uint64_t const*, float*, size_t);
template void Aidge::thrust_copy<>(uint64_t const*, uint64_t*, size_t); template<> void Aidge::thrust_copy(uint64_t const*, half_float::half*, size_t);
template void Aidge::thrust_copy<>(uint64_t const*, uint32_t*, size_t); template<> void Aidge::thrust_copy(uint64_t const*, int64_t*, size_t);
template void Aidge::thrust_copy<>(uint64_t const*, uint16_t*, size_t); template<> void Aidge::thrust_copy(uint64_t const*, int32_t*, size_t);
template void Aidge::thrust_copy<>(uint64_t const*, uint8_t*, size_t); template<> void Aidge::thrust_copy(uint64_t const*, int16_t*, size_t);
// uint32_t template<> void Aidge::thrust_copy(uint64_t const*, int8_t*, size_t);
template void Aidge::thrust_copy<>(uint32_t const*, double*, size_t); template<> void Aidge::thrust_copy(uint64_t const*, uint64_t*, size_t);
template void Aidge::thrust_copy<>(uint32_t const*, float*, size_t); template<> void Aidge::thrust_copy(uint64_t const*, uint32_t*, size_t);
template void Aidge::thrust_copy<>(uint32_t const*, half_float::half*, size_t); template<> void Aidge::thrust_copy(uint64_t const*, uint16_t*, size_t);
template void Aidge::thrust_copy<>(uint32_t const*, int64_t*, size_t); template<> void Aidge::thrust_copy(uint64_t const*, uint8_t*, size_t);
template void Aidge::thrust_copy<>(uint32_t const*, int32_t*, size_t);
template void Aidge::thrust_copy<>(uint32_t const*, int16_t*, size_t); // uint32_t
template void Aidge::thrust_copy<>(uint32_t const*, int8_t*, size_t); template<> void Aidge::thrust_copy(uint32_t const*, double*, size_t);
template void Aidge::thrust_copy<>(uint32_t const*, uint64_t*, size_t); template<> void Aidge::thrust_copy(uint32_t const*, float*, size_t);
template void Aidge::thrust_copy<>(uint32_t const*, uint32_t*, size_t); template<> void Aidge::thrust_copy(uint32_t const*, half_float::half*, size_t);
template void Aidge::thrust_copy<>(uint32_t const*, uint16_t*, size_t); template<> void Aidge::thrust_copy(uint32_t const*, int64_t*, size_t);
template void Aidge::thrust_copy<>(uint32_t const*, uint8_t*, size_t); template<> void Aidge::thrust_copy(uint32_t const*, int32_t*, size_t);
// uint16_t template<> void Aidge::thrust_copy(uint32_t const*, int16_t*, size_t);
template void Aidge::thrust_copy<>(uint16_t const*, double*, size_t); template<> void Aidge::thrust_copy(uint32_t const*, int8_t*, size_t);
template void Aidge::thrust_copy<>(uint16_t const*, float*, size_t); template<> void Aidge::thrust_copy(uint32_t const*, uint64_t*, size_t);
template void Aidge::thrust_copy<>(uint16_t const*, half_float::half*, size_t); template<> void Aidge::thrust_copy(uint32_t const*, uint32_t*, size_t);
template void Aidge::thrust_copy<>(uint16_t const*, int64_t*, size_t); template<> void Aidge::thrust_copy(uint32_t const*, uint16_t*, size_t);
template void Aidge::thrust_copy<>(uint16_t const*, int32_t*, size_t); template<> void Aidge::thrust_copy(uint32_t const*, uint8_t*, size_t);
template void Aidge::thrust_copy<>(uint16_t const*, int16_t*, size_t);
template void Aidge::thrust_copy<>(uint16_t const*, int8_t*, size_t); // uint16_t
template void Aidge::thrust_copy<>(uint16_t const*, uint64_t*, size_t); template<> void Aidge::thrust_copy(uint16_t const*, double*, size_t);
template void Aidge::thrust_copy<>(uint16_t const*, uint32_t*, size_t); template<> void Aidge::thrust_copy(uint16_t const*, float*, size_t);
template void Aidge::thrust_copy<>(uint16_t const*, uint16_t*, size_t); template<> void Aidge::thrust_copy(uint16_t const*, half_float::half*, size_t);
template void Aidge::thrust_copy<>(uint16_t const*, uint8_t*, size_t); template<> void Aidge::thrust_copy(uint16_t const*, int64_t*, size_t);
// uint8_t template<> void Aidge::thrust_copy(uint16_t const*, int32_t*, size_t);
template void Aidge::thrust_copy<>(uint8_t const*, double*, size_t); template<> void Aidge::thrust_copy(uint16_t const*, int16_t*, size_t);
template void Aidge::thrust_copy<>(uint8_t const*, float*, size_t); template<> void Aidge::thrust_copy(uint16_t const*, int8_t*, size_t);
template void Aidge::thrust_copy<>(uint8_t const*, half_float::half*, size_t); template<> void Aidge::thrust_copy(uint16_t const*, uint64_t*, size_t);
template void Aidge::thrust_copy<>(uint8_t const*, int64_t*, size_t); template<> void Aidge::thrust_copy(uint16_t const*, uint32_t*, size_t);
template void Aidge::thrust_copy<>(uint8_t const*, int32_t*, size_t); template<> void Aidge::thrust_copy(uint16_t const*, uint16_t*, size_t);
template void Aidge::thrust_copy<>(uint8_t const*, int16_t*, size_t); template<> void Aidge::thrust_copy(uint16_t const*, uint8_t*, size_t);
template void Aidge::thrust_copy<>(uint8_t const*, int8_t*, size_t);
template void Aidge::thrust_copy<>(uint8_t const*, uint64_t*, size_t); // uint8_t
template void Aidge::thrust_copy<>(uint8_t const*, uint32_t*, size_t); template<> void Aidge::thrust_copy(uint8_t const*, double*, size_t);
template void Aidge::thrust_copy<>(uint8_t const*, uint16_t*, size_t); template<> void Aidge::thrust_copy(uint8_t const*, float*, size_t);
template void Aidge::thrust_copy<>(uint8_t const*, uint8_t*, size_t); template<> void Aidge::thrust_copy(uint8_t const*, half_float::half*, size_t);
template<> void Aidge::thrust_copy(uint8_t const*, int64_t*, size_t);
template<> void Aidge::thrust_copy(uint8_t const*, int32_t*, size_t);
template<> void Aidge::thrust_copy(uint8_t const*, int16_t*, size_t);
template<> void Aidge::thrust_copy(uint8_t const*, int8_t*, size_t);
template<> void Aidge::thrust_copy(uint8_t const*, uint64_t*, size_t);
template<> void Aidge::thrust_copy(uint8_t const*, uint32_t*, size_t);
template<> void Aidge::thrust_copy(uint8_t const*, uint16_t*, size_t);
template<> void Aidge::thrust_copy(uint8_t const*, uint8_t*, size_t);
0% or .
You are about to add 0 people to the discussion. Proceed with caution.
Finish editing this message first!
Please register or to comment

Copyright © Eclipse Foundation, Inc. All Rights Reserved.     Privacy Policy | Terms of Use | Copyright Agent