Viennacl error msg

[ RUN      ] MatrixSum.symmetric_viennacl_backend_no_diag
unknown file: Failure
C++ exception with description "ViennaCL: FATAL ERROR: You requested to create a ViennaCL type using double precision. However, double precision is not supported by your device.
If you think that this is a bug in ViennaCL, please report it at viennacl-support@lists.sourceforge.net and supply at least the following information:
 * Operating System
 * Which OpenCL implementation (AMD, NVIDIA, etc.)
 * ViennaCL version
Many thanks in advance!" thrown in the test body.
[  FAILED  ] MatrixSum.symmetric_viennacl_backend_no_diag (0 ms)
[ RUN      ] MatrixSum.asymmetric_colwise_viennacl_backend_with_diag
Build Status = -2 ( Err = -11 )
Log: <program source>:1:27: warning: expected identifier in '#pragma OPENCL' - ignored
#pragma OPENCL EXTENSION  : enable
                          ^
<program source>:9:15: error: use of type 'double' requires cl_khr_fp64 extension to be enabled
                                        __global DATATYPE* mat, int nrows, int ncols, int offset,
              ^
<program source>:3:18: note: expanded from macro 'DATATYPE'
#define DATATYPE double
                 ^
<program source>:10:15: error: use of type 'double' requires cl_khr_fp64 extension to be enabled
                                        __global DATATYPE* result, int result_offset)
              ^
<program source>:3:18: note: expanded from macro 'DATATYPE'
#define DATATYPE double
                 ^
<program source>:17:6: error: use of type 'double' requires cl_khr_fp64 extension to be enabled
                                        DATATYPE sum = 0;
     ^
<program source>:3:18: note: expanded from macro 'DATATYPE'
#define DATATYPE double
                 ^

Sources: #pragma OPENCL EXTENSION  : enable

#define DATATYPE double
#define KERNEL_NAME colwise_sum_double
#define WORK_GROUP_SIZE_1D 256
#define WORK_GROUP_SIZE_2D 16

				__kernel void KERNEL_NAME(
					__global DATATYPE* mat, int nrows, int ncols, int offset,
					__global DATATYPE* result, int result_offset)
				{
					int j = get_global_id(0);

					if (j>=ncols)
						return;

					DATATYPE sum = 0;
					for (int i=0; i<nrows; i++)
					{
					#ifdef NO_DIAG
						if (i!=j)
					#endif
						sum += mat[offset+i+j*nrows];
					}

					result[j+result_offset] = sum;
				}
			
unknown file: Failure
C++ exception with description "ViennaCL: FATAL ERROR: CL_INVALID_PROGRAM_EXECUTABLE.
If you think that this is a bug in ViennaCL, please report it at viennacl-support@lists.sourceforge.net and supply at least the following information:
 * Operating System
 * Which OpenCL implementation (AMD, NVIDIA, etc.)
 * ViennaCL version
Many thanks in advance!" thrown in the test body.
[  FAILED  ] MatrixSum.asymmetric_colwise_viennacl_backend_with_diag (4 ms)