1/*===---- complex - CUDA wrapper for <new> ------------------------------=== 2 * 3 * Permission is hereby granted, free of charge, to any person obtaining a copy 4 * of this software and associated documentation files (the "Software"), to deal 5 * in the Software without restriction, including without limitation the rights 6 * to use, copy, modify, merge, publish, distribute, sublicense, and/or sell 7 * copies of the Software, and to permit persons to whom the Software is 8 * furnished to do so, subject to the following conditions: 9 * 10 * The above copyright notice and this permission notice shall be included in 11 * all copies or substantial portions of the Software. 12 * 13 * THE SOFTWARE IS PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND, EXPRESS OR 14 * IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF MERCHANTABILITY, 15 * FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT. IN NO EVENT SHALL THE 16 * AUTHORS OR COPYRIGHT HOLDERS BE LIABLE FOR ANY CLAIM, DAMAGES OR OTHER 17 * LIABILITY, WHETHER IN AN ACTION OF CONTRACT, TORT OR OTHERWISE, ARISING FROM, 18 * OUT OF OR IN CONNECTION WITH THE SOFTWARE OR THE USE OR OTHER DEALINGS IN 19 * THE SOFTWARE. 20 * 21 *===-----------------------------------------------------------------------=== 22 */ 23 24#ifndef __CLANG_CUDA_WRAPPERS_NEW 25#define __CLANG_CUDA_WRAPPERS_NEW 26 27#include_next <new> 28 29#pragma push_macro("CUDA_NOEXCEPT") 30#if __cplusplus >= 201103L 31#define CUDA_NOEXCEPT noexcept 32#else 33#define CUDA_NOEXCEPT 34#endif 35 36// Device overrides for non-placement new and delete. 37__device__ inline void *operator new(__SIZE_TYPE__ size) { 38 if (size == 0) { 39 size = 1; 40 } 41 return ::malloc(size); 42} 43__device__ inline void *operator new(__SIZE_TYPE__ size, 44 const std::nothrow_t &) CUDA_NOEXCEPT { 45 return ::operator new(size); 46} 47 48__device__ inline void *operator new[](__SIZE_TYPE__ size) { 49 return ::operator new(size); 50} 51__device__ inline void *operator new[](__SIZE_TYPE__ size, 52 const std::nothrow_t &) { 53 return ::operator new(size); 54} 55 56__device__ inline void operator delete(void* ptr) CUDA_NOEXCEPT { 57 if (ptr) { 58 ::free(ptr); 59 } 60} 61__device__ inline void operator delete(void *ptr, 62 const std::nothrow_t &) CUDA_NOEXCEPT { 63 ::operator delete(ptr); 64} 65 66__device__ inline void operator delete[](void* ptr) CUDA_NOEXCEPT { 67 ::operator delete(ptr); 68} 69__device__ inline void operator delete[](void *ptr, 70 const std::nothrow_t &) CUDA_NOEXCEPT { 71 ::operator delete(ptr); 72} 73 74// Sized delete, C++14 only. 75#if __cplusplus >= 201402L 76__device__ inline void operator delete(void *ptr, 77 __SIZE_TYPE__ size) CUDA_NOEXCEPT { 78 ::operator delete(ptr); 79} 80__device__ inline void operator delete[](void *ptr, 81 __SIZE_TYPE__ size) CUDA_NOEXCEPT { 82 ::operator delete(ptr); 83} 84#endif 85 86// Device overrides for placement new and delete. 87__device__ inline void *operator new(__SIZE_TYPE__, void *__ptr) CUDA_NOEXCEPT { 88 return __ptr; 89} 90__device__ inline void *operator new[](__SIZE_TYPE__, void *__ptr) CUDA_NOEXCEPT { 91 return __ptr; 92} 93__device__ inline void operator delete(void *, void *) CUDA_NOEXCEPT {} 94__device__ inline void operator delete[](void *, void *) CUDA_NOEXCEPT {} 95 96#pragma pop_macro("CUDA_NOEXCEPT") 97 98#endif // include guard 99