 
         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!=3010
     }
 };
 VariableUnitTest<TestUniqueCopyByKey, IntegralTypes> TestUniqueCopyByKeyInstance;

    ASSERT_EQUAL(output_values[0], 0);
    ASSERT_EQUAL(output_values[1], 2);
    ASSERT_EQUAL(output_values[2], 7);
}
DECLARE_VECTOR_UNITTEST(TestUniqueCopyByKeySimple);


{
    void operator()(const size_t n)
    {
// XXX disable tests on 3.1
#if defined(__CUDACC__) && CUDA_VERSION!=3010
        typedef unsigned int V; // ValueType

        thrust::host_vector<K>   h_keys = unittest::random_integers<bool>(n);
