#include #include #include #include #include #include #include namespace { // The managed_memory_pointer class should be identified as a // contiguous_iterator THRUST_STATIC_ASSERT( thrust::is_contiguous_iterator::pointer>::value); template struct some_object { some_object(T data) : m_data(data) {} void setter(T data) { m_data = data; } T getter() const { return m_data; } private: T m_data; }; } // namespace template void TestUniversalAllocateUnique() { // Simple test to ensure that pointers created with universal_memory_resource // can be dereferenced and used with STL code. This is necessary as some // STL implementations break when using fancy references that overload // operator&, so universal_memory_resource uses a special pointer type that // returns regular C++ references that can be safely used host-side. // These operations fail to compile with fancy references: auto raw = thrust::allocate_unique(thrust::universal_allocator{}, 42); auto obj = thrust::allocate_unique>( thrust::universal_allocator >{}, 42 ); static_assert( std::is_same >::value, "Unexpected pointer type returned from std::unique_ptr::get."); static_assert( std::is_same > >::value, "Unexpected pointer type returned from std::unique_ptr::get."); ASSERT_EQUAL(*raw, T(42)); ASSERT_EQUAL(*raw.get(), T(42)); ASSERT_EQUAL(obj->getter(), T(42)); ASSERT_EQUAL((*obj).getter(), T(42)); ASSERT_EQUAL(obj.get()->getter(), T(42)); ASSERT_EQUAL((*obj.get()).getter(), T(42)); } DECLARE_GENERIC_UNITTEST(TestUniversalAllocateUnique); template void TestUniversalIterationRaw() { auto array = thrust::allocate_unique_n( thrust::universal_allocator{}, 6, 42); static_assert( std::is_same >::value, "Unexpected pointer type returned from std::unique_ptr::get."); for (auto iter = array.get(), end = array.get() + 6; iter < end; ++iter) { ASSERT_EQUAL(*iter, T(42)); ASSERT_EQUAL(*iter.get(), T(42)); } } DECLARE_GENERIC_UNITTEST(TestUniversalIterationRaw); template void TestUniversalIterationObj() { auto array = thrust::allocate_unique_n>( thrust::universal_allocator>{}, 6, 42); static_assert( std::is_same>>::value, "Unexpected pointer type returned from std::unique_ptr::get."); for (auto iter = array.get(), end = array.get() + 6; iter < end; ++iter) { ASSERT_EQUAL(iter->getter(), T(42)); ASSERT_EQUAL((*iter).getter(), T(42)); ASSERT_EQUAL(iter.get()->getter(), T(42)); ASSERT_EQUAL((*iter.get()).getter(), T(42)); } } DECLARE_GENERIC_UNITTEST(TestUniversalIterationObj); template void TestUniversalRawPointerCast() { auto obj = thrust::allocate_unique(thrust::universal_allocator{}, 42); static_assert( std::is_same>::value, "Unexpected pointer type returned from std::unique_ptr::get."); static_assert( std::is_same::value, "Unexpected pointer type returned from thrust::raw_pointer_cast."); *thrust::raw_pointer_cast(obj.get()) = T(17); ASSERT_EQUAL(*obj, T(17)); } DECLARE_GENERIC_UNITTEST(TestUniversalRawPointerCast); template void TestUniversalThrustVector(std::size_t const n) { thrust::host_vector host(n); thrust::universal_vector universal(n); static_assert( std::is_same::type::pointer, thrust::universal_ptr>::value, "Unexpected thrust::universal_vector pointer type."); thrust::sequence(host.begin(), host.end(), 0); thrust::sequence(universal.begin(), universal.end(), 0); ASSERT_EQUAL(host.size(), n); ASSERT_EQUAL(universal.size(), n); ASSERT_EQUAL(host, universal); } DECLARE_VARIABLE_UNITTEST(TestUniversalThrustVector); // Verify that a std::vector using the universal allocator will work with // Standard Library algorithms. template void TestUniversalStdVector(std::size_t const n) { std::vector host(n); std::vector> universal(n); static_assert( std::is_same::type::pointer, thrust::universal_ptr>::value, "Unexpected std::vector pointer type."); std::iota(host.begin(), host.end(), 0); std::iota(universal.begin(), universal.end(), 0); ASSERT_EQUAL(host.size(), n); ASSERT_EQUAL(universal.size(), n); ASSERT_EQUAL(host, universal); } DECLARE_VARIABLE_UNITTEST(TestUniversalStdVector);