 {
     void operator()(const size_t n)
     {
-// XXX disable tests on 3.1
-#if defined(__CUDACC__) && CUDA_VERSION==3000
         typedef unsigned int V; // ValueType
 
         thrust::host_vector<K>   h_keys = unittest::random_integers<bool>(n);


        ASSERT_EQUAL(h_keys_output, d_keys_output);
        ASSERT_EQUAL(h_vals_output, d_vals_output);
#else
	KNOWN_FAILURE;
#endif //#if defined(__CUDACC__) && CUDA_VERSION==3000
    }
};
VariableUnitTest<TestUniqueCopyByKey, IntegralTypes> TestUniqueCopyByKeyInstance;



template<typename Vector>
void TestUniqueByKeySimple(void)
{
    typedef typename Vector::value_type T;

    Vector keys;
