Движок OpenSSL RSA - ошибка проверки RSA

Question

Движок OpenSSL RSA - ошибка проверки RSA

Ниже приведен минимальный, полный и проверяемый пример того, что я хочу сделать.
По сути, я хочу реализовать движок OpenSSL RSA, который интегрирует некоторый код CUDA. Часть CUDA должна выполнять модульное возведение в степень, но это не важно в этом примере, поэтому я просто использовал BN_mod_exp (см. файл engine.c, modexp функция), чтобы упростить код. Код, который я представляю, является упрощенной версией моего проекта, и его можно очень легко собрать / скомпилировать с помощью следующих команд:

gcc -fPIC -I/usr/local/cuda/include -c engine.c
nvcc --compiler-options '-fPIC' -c my_cuda.cu -lcrypto
g++ -L/usr/local/cuda/lib64 -shared -o gpu.so engine.o my_cuda.o -lcuda -lcudart
openssl engine -t -c `pwd`/gpu.so

... вывод последней команды говорит о доступности двигателя RSA

/*engine.c*/

#include <openssl/opensslconf.h>

#include <stdio.h>
#include <string.h>
#include <openssl/crypto.h>
#include <openssl/buffer.h>
#include <openssl/engine.h>

#include <openssl/rsa.h>

#include <openssl/bn.h>
#include <openssl/err.h>
#include "my_cuda.h"

/* Constants used when creating the ENGINE */
static const char *engine_e_rsax_id = "rsa_gpu";
static const char *engine_e_rsax_name = "RSAX engine support";
static int modexp(BIGNUM *r, const BIGNUM *I, RSA *rsa, BN_CTX *ctx);// r = r ^ I mod rsa->n
static int e_rsax_rsa_finish(RSA *r);
static int e_rsax_destroy(ENGINE *e);
static int e_rsax_init(ENGINE *e);
static int e_rsax_finish(ENGINE *e);
static int e_rsax_ctrl(ENGINE *e, int cmd, long i, void *p, void (*f)(void));

static const ENGINE_CMD_DEFN e_rsax_cmd_defns[] = {
    {0, NULL, NULL, 0}
};

static ENGINE *ENGINE_rsax (void);
void ENGINE_load_rsax (void)
    {
/* On non-x86 CPUs it just returns. */
    ENGINE *toadd = ENGINE_rsax();
    if(!toadd) return;
    ENGINE_add(toadd);
    ENGINE_free(toadd);
    ERR_clear_error();
    }


static RSA_METHOD e_rsax_rsa =
{
    "Intel RSA-X method",
    NULL,
    NULL,
    NULL,
    NULL,
    modexp,
    NULL,
    NULL,
    NULL,
    RSA_FLAG_CACHE_PUBLIC|RSA_FLAG_CACHE_PRIVATE,
    NULL,
    NULL,
    NULL
};

/* This internal function is used by ENGINE_rsax() */
static int bind_helper(ENGINE *e, const char *id)
    {
        printf("%s\n", id);

    const RSA_METHOD *meth1;

    if(!ENGINE_set_id(e, engine_e_rsax_id) ||
            !ENGINE_set_name(e, engine_e_rsax_name) ||

            !ENGINE_set_RSA(e, &e_rsax_rsa) ||

            !ENGINE_set_destroy_function(e, e_rsax_destroy) ||
            !ENGINE_set_init_function(e, e_rsax_init) ||
            !ENGINE_set_finish_function(e, e_rsax_finish) ||
            !ENGINE_set_ctrl_function(e, e_rsax_ctrl) ||
            !ENGINE_set_cmd_defns(e, e_rsax_cmd_defns))
        return 0;


    meth1 = RSA_PKCS1_SSLeay();
    e_rsax_rsa.rsa_pub_enc = meth1->rsa_pub_enc;
    e_rsax_rsa.rsa_pub_dec = meth1->rsa_pub_dec;
    e_rsax_rsa.rsa_priv_enc = meth1->rsa_priv_enc;
    e_rsax_rsa.rsa_priv_dec = meth1->rsa_priv_dec;
    e_rsax_rsa.bn_mod_exp = meth1->bn_mod_exp;
    e_rsax_rsa.finish = meth1->finish;

    return 1;
    }

    /* Used to attach our own key-data to an RSA structure */
static int rsax_ex_data_idx = -1;


static int e_rsax_destroy(ENGINE *e)
{
    return 1;
}

/* (de)initialisation functions. */
static int e_rsax_init(ENGINE *e)
{

    if (rsax_ex_data_idx == -1)
        rsax_ex_data_idx = RSA_get_ex_new_index(0,
            NULL,
            NULL, NULL, NULL);

    if (rsax_ex_data_idx  == -1)
        return 0;
    return 1;
}

static int e_rsax_finish(ENGINE *e)
{
    return 1;
}

static int e_rsax_ctrl(ENGINE *e, int cmd, long i, void *p, void (*f)(void))
{
    int to_return = 1;

    switch(cmd)
        {
    /* The command isn't understood by this engine */
    default:
        to_return = 0;
        break;
        }

    return to_return;
}

IMPLEMENT_DYNAMIC_BIND_FN(bind_helper)
IMPLEMENT_DYNAMIC_CHECK_FN()

static ENGINE *ENGINE_rsax(void)
{
    ENGINE *ret = ENGINE_new();
    if(!ret)
        return NULL;
    if(!bind_helper(ret, engine_e_rsax_id))
        {
        ENGINE_free(ret);
        return NULL;
        }
    return ret;
}

static int modexp(BIGNUM *r, const BIGNUM *I, RSA *rsa, BN_CTX *ctx)// r = r ^ I mod rsa->n
{
    modexp512();
    return BN_mod_exp(r, r, I, rsa->n, ctx);
}

... следующие два файла предназначены для демонстрации и воспроизводят мой проект

/*my_cuda.cu*/
#include <cuda_runtime.h>
#include <stdio.h>
extern "C" {
#include "my_cuda.h"
}

__global__ void dummy_gpu_kernel(){
   // stuff here
}
extern "C"
void modexp512(){
   dummy_gpu_kernel<<<1,1>>>();
}

...

/*my_cuda.h*/
#ifndef MY_DUMMY
#define MY_DUMMY

void modexp512();

#endif

Теперь я хочу сделать несколько тестов скорости, используя

$ openssl speed rsa512 -engine `pwd`/gpu.so

и я получаю следующую ошибку

/full/path/gpu.so
engine "rsa_gpu" set.
Doing 512 bit private rsa's for 10s: 575412 512 bit private RSA's in 10.02s
RSA verify failure.  No RSA verify will be done.
140592781633184:error:0407006A:rsa routines:RSA_padding_check_PKCS1_type_1:block type is not 01:rsa_pk1.c:100:
140592781633184:error:04067072:rsa routines:RSA_EAY_PUBLIC_DECRYPT:padding check failed:rsa_eay.c:721:
OpenSSL 1.0.1f 6 Jan 2014
built on: Mon Feb 29 18:11:15 UTC 2016
options:bn(64,64) rc4(16x,int) des(idx,cisc,16,int) aes(partial) blowfish(idx) 
compiler: cc -fPIC -DOPENSSL_PIC -DOPENSSL_THREADS -D_REENTRANT -DDSO_DLFCN -DHAVE_DLFCN_H -m64 -DL_ENDIAN -DTERMIO -g -O2 -fstack-protector --param=ssp-buffer-size=4 -Wformat -Werror=format-security -D_FORTIFY_SOURCE=2 -Wl,-Bsymbolic-functions -Wl,-z,relro -Wa,--noexecstack -Wall -DMD32_REG_T=int -DOPENSSL_IA32_SSE2 -DOPENSSL_BN_ASM_MONT -DOPENSSL_BN_ASM_MONT5 -DOPENSSL_BN_ASM_GF2m -DSHA1_ASM -DSHA256_ASM -DSHA512_ASM -DMD5_ASM -DAES_ASM -DVPAES_ASM -DBSAES_ASM -DWHIRLPOOL_ASM -DGHASH_ASM

Я искал эти ошибки в интернете, но безуспешно. Мой вопрос: как я могу избавиться от этого "Ошибка проверки RSA. Проверка RSA не будет выполнена". ошибка? Кажется, что OpenSSL не доверяет моей реализации или что-то.
Я удалил свой предыдущий пост, потому что он не может быть скомпилирован и проверен. Этот пример может проверить любой, у кого установлены OpenSSL и CUDA[необязательно]. Но так как часть CUDA не важна в этом примере, и кто-то хочет попробовать это, он / она должен закомментировать #include "my_cuda.h" а также modexp512(); от engine.c файл и измените процесс сборки соответственно, то есть:

gcc -fPIC -c engine.c
g++ -shared -o gpu.so -lcrypto engine.o

и попробуйте ту же команду

$ openssl speed rsa512 -engine `pwd`/gpu.so

2

openssl openssl-engine

Источник

user3474387 04 апр '16 в 07:07

1 ответ

Решение

Другие вопросы по тегам openssl openssl-engine

user233596 09 апр '16 в 03:37 2016-04-09 03:37 · Accepted Answer · 2016-04-09 03:37

Я немного повозился с этим, потому что нашел его интересным. Я не уверен, что вы делаете что-то не так. Я не уверен как rsa->_method_mod_n следует использовать, но я заменил ваш modexp на это:

static int modexp(BIGNUM *r, const BIGNUM *I, RSA *rsa, BN_CTX *ctx)
{
    const RSA_METHOD *meth = RSA_PKCS1_SSLeay();
    return meth->rsa_mod_exp(r, I, rsa, ctx);
}

и это работало нормально, а затем это:

static int modexp(BIGNUM *r, const BIGNUM *I, RSA *rsa, BN_CTX *ctx)
{
    const RSA_METHOD *meth = RSA_PKCS1_SSLeay();
    return meth->bn_mod_exp(r, (const BIGNUM*) r, I, rsa->n, ctx, rsa->_method_mod_n);
}

и это не удалось именно так, как вы описываете.

В обоих случаях я использую функции метода OpenSSL, так как при чтении исходного кода openssl можно предположить, что их следует использовать.