Development Notes – California Sunshine

CLion from JetBrains provides very good support on CUDA development. This post will mainly talk about how to create a CUDA project in CLion in Windows and how to solve problem when using CUDA 11.2.

Prerequisites

Before creating CUDA project in CLion, please install the following softwares.

CUDA Toolkit 11.2 for Windows. Check this link.
Visual Studio 2019 Community. Check this link.

After installation, in CLion, make sure your Toolchain’s architecture is amd64.

Create CUDA Project In CLion

When creating new project in CLion, simply select “CUDA Executable” as the template.

Let’s modify the default main.cu and test if CUDA is working.

#include <iostream>

using namespace std;

static void HandleError( cudaError_t err,
                         const char *file,
                         int line ) {
    if (err != cudaSuccess) {
        printf( "%s in %s at line %d\n", cudaGetErrorString( err ),
                file, line );
        exit( EXIT_FAILURE );
    }
}
#define HANDLE_ERROR( err ) (HandleError( err, __FILE__, __LINE__ ))

__global__ void add(int a, int b, int* c) {
    *c = a + b;
}

int main() {
    int count;
    HANDLE_ERROR(cudaGetDeviceCount(&count));

    cout << "Found " << count << " device(s)" << endl;

    for (int i = 0; i < count; ++i) {
        cudaDeviceProp prop;

        HANDLE_ERROR(cudaGetDeviceProperties(&prop, i));
        cout << "Device name: " << prop.name << endl;
        cout << "Total Memory: " << prop.totalGlobalMem / 1024.0 / 1024.0 << "MB" << endl;
        cout << "Max Threads per Block: " << prop.maxThreadsPerBlock << endl;
        cout << "Compute capability: " << prop.major << "." << prop.minor << endl;
    }

    int result;
    int* devResult;

    HANDLE_ERROR(cudaMalloc((void**)&devResult, sizeof(int)));

    add<<<1, 1>>>(7, 8, devResult);

    HANDLE_ERROR(cudaMemcpy(&result, devResult, sizeof(int), cudaMemcpyDeviceToHost));

    cout << "7 + 8 = " << result << endl;

    cudaFree(devResult);

    return 0;
}

#include <iostream>

using namespace std;

static void HandleError( cudaError_t err,

const char *file,

int line ) {

if (err != cudaSuccess) {

printf( "%s in %s at line %d\n", cudaGetErrorString( err ),

file, line );

exit( EXIT_FAILURE );

}

#define HANDLE_ERROR( err ) (HandleError( err, __FILE__, __LINE__ ))

__global__ void add(int a, int b, int* c) {

*c = a + b;

}

int main() {

int count;

HANDLE_ERROR(cudaGetDeviceCount(&count));

cout << "Found " << count << " device(s)" << endl;

for (int i = 0; i < count; ++i) {

cudaDeviceProp prop;

HANDLE_ERROR(cudaGetDeviceProperties(&prop, i));

cout << "Device name: " << prop.name << endl;

cout << "Total Memory: " << prop.totalGlobalMem / 1024.0 / 1024.0 << "MB" << endl;

cout << "Max Threads per Block: " << prop.maxThreadsPerBlock << endl;

cout << "Compute capability: " << prop.major << "." << prop.minor << endl;

}

int result;

int* devResult;

HANDLE_ERROR(cudaMalloc((void**)&devResult, sizeof(int)));

add<<<1, 1>>>(7, 8, devResult);

HANDLE_ERROR(cudaMemcpy(&result, devResult, sizeof(int), cudaMemcpyDeviceToHost));

cout << "7 + 8 = " << result << endl;

cudaFree(devResult);

return 0;

}

After build and run, you should see the following output.

H:\source\CLionProjects\CudaInLion\cmake-build-debug\CudaInLion.exe
Found 1 device(s)
Device name: GeForce GTX 970
Total Memory: 4096MB
Max Threads per Block: 1024
Compute capability: 5.2
7 + 8 = 15

H:\source\CLionProjects\CudaInLion\cmake-build-debug\CudaInLion.exe

Found 1 device(s)

Device name: GeForce GTX 970

Total Memory: 4096MB

Max Threads per Block: 1024

Compute capability: 5.2

7 + 8 = 15

Now CUDA is working in CLion project!

Trouble shooting

When having the issue related to vcvars64.bat…

At the beginning, I got the following issue

“Could not set up the environment for Microsoft Visual Studio using ‘C:/Program Files (x86)/Microsoft Visual Studio/2019/Community/VC/Tools/MSVC/14.26.28801/bin/HostX64/x64/../../../../../../../VC/Auxiliary/Build/vcvars64.bat’

After some searching, the problem is due to %PATH% is too long. You need to remove the unnecessary paths from %PATH%. Actually, if you see any double quote in %PATH%, please also remove them.

When having the issue “Use of undeclared identifier cudaConfigureCall“

I also saw the following issue,

You probably are using CUDA 11. In this version, the version.txt file was removed. Instead, version.json was introduced. To solve this issue, you can simply create a version.txt with following context and copy it to where the CUDA is installed.

CUDA Version 11.2

1	CUDA Version 11.2

After opening the CLion, the problem will be gone.

References

In our development machine, I don’t have the root permission to install MySQL server. But our SonarQube needs it.

Fortunately, if you using the MySQL TAR archive, “root” is not required to launch mysqld but you need specify the configuration file. The default one uses some folders which need root to access.

Here is the sample mysqld configuration. You can also start from a configuration file in folder support-files.

# For advice on how to change settings please see
# http://dev.mysql.com/doc/refman/5.6/en/server-configuration-defaults.html

[mysqld]
user=yli

# Remove leading # and set to the amount of RAM for the most important data
# cache in MySQL. Start at 70% of total RAM for dedicated server, else 10%.
# innodb_buffer_pool_size = 128M

# Remove leading # to turn on a very important data integrity option: logging
# changes to the binary log between backups.
# log_bin

# These are commonly set, remove the # and set as required.
basedir = /home/yli/mysql-5.6.16-linux-glibc2.5-x86_64
datadir = /home/yli/sonar_mysql_db
# port = .....
# server_id = .....
# socket = .....

# Remove leading # to set options mainly useful for reporting servers.
# The server defaults are faster for transactions and fast SELECTs.
# Adjust sizes as needed, experiment to find the optimal values.
# join_buffer_size = 128M
# sort_buffer_size = 2M
# read_rnd_buffer_size = 2M 

sql_mode=NO_ENGINE_SUBSTITUTION,STRICT_TRANS_TABLES

# For advice on how to change settings please see

# http://dev.mysql.com/doc/refman/5.6/en/server-configuration-defaults.html

[mysqld]

user=yli

# Remove leading # and set to the amount of RAM for the most important data

# cache in MySQL. Start at 70% of total RAM for dedicated server, else 10%.

# innodb_buffer_pool_size = 128M

# Remove leading # to turn on a very important data integrity option: logging

# changes to the binary log between backups.

# log_bin

# These are commonly set, remove the # and set as required.

basedir = /home/yli/mysql-5.6.16-linux-glibc2.5-x86_64

datadir = /home/yli/sonar_mysql_db

# port = .....

# server_id = .....

# socket = .....

# Remove leading # to set options mainly useful for reporting servers.

# The server defaults are faster for transactions and fast SELECTs.

# Adjust sizes as needed, experiment to find the optimal values.

# join_buffer_size = 128M

# sort_buffer_size = 2M

# read_rnd_buffer_size = 2M

sql_mode=NO_ENGINE_SUBSTITUTION,STRICT_TRANS_TABLES

Basically, you need specify the basedir and datadir to tell mysql where it’s installed and where the database files should be put.

Other settings can keep the same as defaults in my case. Then I start the server instance. Option “–defaults-file” is important.

[yli@my_laptop ~/mysql-5.6.16-linux-glibc2.5-x86_64]$ bin/mysqld --defaults-file=/home/yli/mysql-5.6.16-linux-glibc2.5-x86_64/my.cnf

1	[yli@my_laptop ~/mysql-5.6.16-linux-glibc2.5-x86_64]$ bin/mysqld --defaults-file=/home/yli/mysql-5.6.16-linux-glibc2.5-x86_64/my.cnf

References

How to find configuration file MySQL uses?

Category: Development Notes

CUDA Development with CLion