Loading src/TNL/CMakeLists.txt +1 −0 Original line number Diff line number Diff line Loading @@ -2,6 +2,7 @@ ADD_SUBDIRECTORY( Config ) ADD_SUBDIRECTORY( Containers ) ADD_SUBDIRECTORY( Debugging ) ADD_SUBDIRECTORY( Devices ) ADD_SUBDIRECTORY( Exceptions ) ADD_SUBDIRECTORY( Experimental ) ADD_SUBDIRECTORY( Functions ) ADD_SUBDIRECTORY( Images ) Loading src/TNL/Containers/Algorithms/ArrayOperationsCuda_impl.h +40 −46 Original line number Diff line number Diff line Loading @@ -14,6 +14,7 @@ #include <TNL/tnlConfig.h> #include <TNL/Math.h> #include <TNL/Exceptions/CudaSupportMissing.h> #include <TNL/Containers/Algorithms/ArrayOperations.h> #include <TNL/Containers/Algorithms/Reduction.h> #include <TNL/Containers/Algorithms/reduction-operations.h> Loading @@ -35,8 +36,7 @@ allocateMemory( Element*& data, data = 0; return checkCudaDevice; #else CudaSupportMissingMessage; return false; throw Exceptions::CudaSupportMissing(); #endif } Loading @@ -51,8 +51,7 @@ freeMemory( Element* data ) cudaFree( data ); return checkCudaDevice; #else CudaSupportMissingMessage;; return true; throw Exceptions::CudaSupportMissing(); #endif } Loading Loading @@ -129,8 +128,7 @@ setMemory( Element* data, setArrayValueCudaKernel<<< gridSize, blockSize >>>( data, size, value ); return checkCudaDevice; #else CudaSupportMissingMessage;; return false; throw Exceptions::CudaSupportMissing(); #endif } Loading Loading @@ -183,9 +181,8 @@ copyMemory( DestinationElement* destination, return checkCudaDevice; } #else CudaSupportMissingMessage;; throw Exceptions::CudaSupportMissing(); #endif return false; } template< typename Element1, Loading Loading @@ -265,11 +262,10 @@ copyMemory( DestinationElement* destination, } delete[] buffer; } return true; #else CudaSupportMissingMessage;; return false; throw Exceptions::CudaSupportMissing(); #endif return true; } Loading Loading @@ -319,8 +315,7 @@ compareMemory( const Element1* destination, delete[] host_buffer; return true; #else CudaSupportMissingMessage;; return false; throw Exceptions::CudaSupportMissing(); #endif } Loading Loading @@ -385,8 +380,7 @@ copyMemory( DestinationElement* destination, return true; } #else CudaSupportMissingMessage;; return false; throw Exceptions::CudaSupportMissing(); #endif } Loading src/TNL/Containers/Algorithms/Multireduction_impl.h +2 −2 Original line number Diff line number Diff line Loading @@ -17,6 +17,7 @@ //#define CUDA_REDUCTION_PROFILING #include <TNL/Assert.h> #include <TNL/Exceptions/CudaSupportMissing.h> #include <TNL/Containers/Algorithms/reduction-operations.h> #include <TNL/Containers/Algorithms/ArrayOperations.h> #include <TNL/Containers/Algorithms/CudaMultireductionKernel.h> Loading Loading @@ -145,8 +146,7 @@ reduce( Operation& operation, return checkCudaDevice; #else CudaSupportMissingMessage; return false; throw Exceptions::CudaSupportMissing(); #endif }; Loading src/TNL/Containers/Algorithms/Reduction_impl.h +2 −2 Original line number Diff line number Diff line Loading @@ -15,6 +15,7 @@ //#define CUDA_REDUCTION_PROFILING #include <TNL/Assert.h> #include <TNL/Exceptions/CudaSupportMissing.h> #include <TNL/Containers/Algorithms/reduction-operations.h> #include <TNL/Containers/Algorithms/ArrayOperations.h> #include <TNL/Containers/Algorithms/CudaReductionKernel.h> Loading Loading @@ -161,8 +162,7 @@ reductionOnCudaDevice( Operation& operation, return checkCudaDevice; #else CudaSupportMissingMessage;; return false; throw Exceptions::CudaSupportMissing(); #endif }; Loading src/TNL/Containers/Algorithms/VectorOperationsCuda_impl.h +54 −55 Original line number Diff line number Diff line Loading @@ -11,6 +11,7 @@ #pragma once #include <TNL/tnlConfig.h> #include <TNL/Exceptions/CudaSupportMissing.h> #include <TNL/Containers/Algorithms/VectorOperations.h> #include <TNL/Containers/Algorithms/cuda-prefix-sum.h> #include <TNL/Containers/Algorithms/CublasWrapper.h> Loading Loading @@ -430,7 +431,7 @@ vectorScalarMultiplication( Vector& v, alpha ); checkCudaDevice; #else CudaSupportMissingMessage;; throw Exceptions::CudaSupportMissing(); #endif } Loading Loading @@ -521,7 +522,7 @@ addVector( Vector1& y, thisMultiplicator); checkCudaDevice; #else CudaSupportMissingMessage;; throw Exceptions::CudaSupportMissing(); #endif } Loading Loading @@ -596,10 +597,8 @@ addVectors( Vector1& v, thisMultiplicator); checkCudaDevice; #else CudaSupportMissingMessage;; throw Exceptions::CudaSupportMissing(); #endif } template< typename Vector > Loading @@ -623,7 +622,7 @@ computePrefixSum( Vector& v, operation, Algorithms::inclusivePrefixSum ); #else CudaSupportMissingMessage;; throw Exceptions::CudaSupportMissing(); #endif } Loading Loading
src/TNL/CMakeLists.txt +1 −0 Original line number Diff line number Diff line Loading @@ -2,6 +2,7 @@ ADD_SUBDIRECTORY( Config ) ADD_SUBDIRECTORY( Containers ) ADD_SUBDIRECTORY( Debugging ) ADD_SUBDIRECTORY( Devices ) ADD_SUBDIRECTORY( Exceptions ) ADD_SUBDIRECTORY( Experimental ) ADD_SUBDIRECTORY( Functions ) ADD_SUBDIRECTORY( Images ) Loading
src/TNL/Containers/Algorithms/ArrayOperationsCuda_impl.h +40 −46 Original line number Diff line number Diff line Loading @@ -14,6 +14,7 @@ #include <TNL/tnlConfig.h> #include <TNL/Math.h> #include <TNL/Exceptions/CudaSupportMissing.h> #include <TNL/Containers/Algorithms/ArrayOperations.h> #include <TNL/Containers/Algorithms/Reduction.h> #include <TNL/Containers/Algorithms/reduction-operations.h> Loading @@ -35,8 +36,7 @@ allocateMemory( Element*& data, data = 0; return checkCudaDevice; #else CudaSupportMissingMessage; return false; throw Exceptions::CudaSupportMissing(); #endif } Loading @@ -51,8 +51,7 @@ freeMemory( Element* data ) cudaFree( data ); return checkCudaDevice; #else CudaSupportMissingMessage;; return true; throw Exceptions::CudaSupportMissing(); #endif } Loading Loading @@ -129,8 +128,7 @@ setMemory( Element* data, setArrayValueCudaKernel<<< gridSize, blockSize >>>( data, size, value ); return checkCudaDevice; #else CudaSupportMissingMessage;; return false; throw Exceptions::CudaSupportMissing(); #endif } Loading Loading @@ -183,9 +181,8 @@ copyMemory( DestinationElement* destination, return checkCudaDevice; } #else CudaSupportMissingMessage;; throw Exceptions::CudaSupportMissing(); #endif return false; } template< typename Element1, Loading Loading @@ -265,11 +262,10 @@ copyMemory( DestinationElement* destination, } delete[] buffer; } return true; #else CudaSupportMissingMessage;; return false; throw Exceptions::CudaSupportMissing(); #endif return true; } Loading Loading @@ -319,8 +315,7 @@ compareMemory( const Element1* destination, delete[] host_buffer; return true; #else CudaSupportMissingMessage;; return false; throw Exceptions::CudaSupportMissing(); #endif } Loading Loading @@ -385,8 +380,7 @@ copyMemory( DestinationElement* destination, return true; } #else CudaSupportMissingMessage;; return false; throw Exceptions::CudaSupportMissing(); #endif } Loading
src/TNL/Containers/Algorithms/Multireduction_impl.h +2 −2 Original line number Diff line number Diff line Loading @@ -17,6 +17,7 @@ //#define CUDA_REDUCTION_PROFILING #include <TNL/Assert.h> #include <TNL/Exceptions/CudaSupportMissing.h> #include <TNL/Containers/Algorithms/reduction-operations.h> #include <TNL/Containers/Algorithms/ArrayOperations.h> #include <TNL/Containers/Algorithms/CudaMultireductionKernel.h> Loading Loading @@ -145,8 +146,7 @@ reduce( Operation& operation, return checkCudaDevice; #else CudaSupportMissingMessage; return false; throw Exceptions::CudaSupportMissing(); #endif }; Loading
src/TNL/Containers/Algorithms/Reduction_impl.h +2 −2 Original line number Diff line number Diff line Loading @@ -15,6 +15,7 @@ //#define CUDA_REDUCTION_PROFILING #include <TNL/Assert.h> #include <TNL/Exceptions/CudaSupportMissing.h> #include <TNL/Containers/Algorithms/reduction-operations.h> #include <TNL/Containers/Algorithms/ArrayOperations.h> #include <TNL/Containers/Algorithms/CudaReductionKernel.h> Loading Loading @@ -161,8 +162,7 @@ reductionOnCudaDevice( Operation& operation, return checkCudaDevice; #else CudaSupportMissingMessage;; return false; throw Exceptions::CudaSupportMissing(); #endif }; Loading
src/TNL/Containers/Algorithms/VectorOperationsCuda_impl.h +54 −55 Original line number Diff line number Diff line Loading @@ -11,6 +11,7 @@ #pragma once #include <TNL/tnlConfig.h> #include <TNL/Exceptions/CudaSupportMissing.h> #include <TNL/Containers/Algorithms/VectorOperations.h> #include <TNL/Containers/Algorithms/cuda-prefix-sum.h> #include <TNL/Containers/Algorithms/CublasWrapper.h> Loading Loading @@ -430,7 +431,7 @@ vectorScalarMultiplication( Vector& v, alpha ); checkCudaDevice; #else CudaSupportMissingMessage;; throw Exceptions::CudaSupportMissing(); #endif } Loading Loading @@ -521,7 +522,7 @@ addVector( Vector1& y, thisMultiplicator); checkCudaDevice; #else CudaSupportMissingMessage;; throw Exceptions::CudaSupportMissing(); #endif } Loading Loading @@ -596,10 +597,8 @@ addVectors( Vector1& v, thisMultiplicator); checkCudaDevice; #else CudaSupportMissingMessage;; throw Exceptions::CudaSupportMissing(); #endif } template< typename Vector > Loading @@ -623,7 +622,7 @@ computePrefixSum( Vector& v, operation, Algorithms::inclusivePrefixSum ); #else CudaSupportMissingMessage;; throw Exceptions::CudaSupportMissing(); #endif } Loading