 
 int main() {
     cudaMallocManaged(&volume, STORAGE_SIZE);
+	printf("B init\n");
     init_volume();
 
     uchar *input, *output;

// ******************************************************************

// ******************************************************************
// FS Operation
__device__ u32 open(char *name, int type) {
    u32 fp = 0;
    printf("Open %s %d\n", name, type);
    return fp;
}

__device__ void write(uchar *src, int len, u32 fp) {
    // Not implement
    printf("Write %s %d %d\n", src, len, fp);
}

__device__ void read(uchar *dst, int len, u32 fp) {
    // Not implement
    printf("Read %s %d %d\n", dst, len, fp);
}

__device__ void gsys(int type) {
    // Not implement
    printf("Gsys %d\n", type);
}

__device__ void gsys(int type, char *name) {
    // Not implement
    printf("Gsys %d %s\n", type, name);
}


        output[i] = 0;
    }
    loadBinaryFile(DATAFILE, input, MAX_FILE_SIZE);
	printf("F init\n");

    cudaSetDevice(2);
    mykernel<<<1, 1>>>(input, output);
