iExperimental support for blake2bp - dedup - deduplicating backup program Err bitreich.org 70 hgit clone git://bitreich.org/dedup/ git://enlrupgkhuxnvlhsf6lc3fziv5h2hhfrinws65d7roiv6bfj7d652fid.onion/dedup/ URL:git://bitreich.org/dedup/ git://enlrupgkhuxnvlhsf6lc3fziv5h2hhfrinws65d7roiv6bfj7d652fid.onion/dedup/ bitreich.org 70 1Log /scm/dedup/log.gph bitreich.org 70 1Files /scm/dedup/files.gph bitreich.org 70 1Refs /scm/dedup/refs.gph bitreich.org 70 1Tags /scm/dedup/tag bitreich.org 70 1README /scm/dedup/file/README.gph bitreich.org 70 1LICENSE /scm/dedup/file/LICENSE.gph bitreich.org 70 i--- Err bitreich.org 70 1commit 8b7879e94f29387e867047c890d1441ddaa3546f /scm/dedup/commit/8b7879e94f29387e867047c890d1441ddaa3546f.gph bitreich.org 70 1parent 61ae15985e29c27b7d0a6cce11a9bcee3f06be26 /scm/dedup/commit/61ae15985e29c27b7d0a6cce11a9bcee3f06be26.gph bitreich.org 70 hAuthor: sin URL:mailto:sin@2f30.org bitreich.org 70 iDate: Sat, 6 Apr 2019 17:19:27 +0100 Err bitreich.org 70 i Err bitreich.org 70 iExperimental support for blake2bp Err bitreich.org 70 i Err bitreich.org 70 iDiffstat: Err bitreich.org 70 i M Makefile | 6 ++++-- Err bitreich.org 70 i M README | 1 + Err bitreich.org 70 i A blake2bp-ref.c | 359 +++++++++++++++++++++++++++++++ Err bitreich.org 70 i M dedup.c | 24 ++++++++++++------------ Err bitreich.org 70 i Err bitreich.org 70 i4 files changed, 376 insertions(+), 14 deletions(-) Err bitreich.org 70 i--- Err bitreich.org 70 1diff --git a/Makefile b/Makefile /scm/dedup/file/Makefile.gph bitreich.org 70 i@@ -14,6 +14,7 @@ SRC = \ Err bitreich.org 70 i $(BIN).c \ Err bitreich.org 70 i $(HDR) \ Err bitreich.org 70 i blake2b-ref.c \ Err bitreich.org 70 i+ blake2bp-ref.c \ Err bitreich.org 70 i chunker.c \ Err bitreich.org 70 i compress.c \ Err bitreich.org 70 i icache.c \ Err bitreich.org 70 i@@ -25,6 +26,7 @@ SRC = \ Err bitreich.org 70 i OBJ = \ Err bitreich.org 70 i $(BIN).o \ Err bitreich.org 70 i blake2b-ref.o \ Err bitreich.org 70 i+ blake2bp-ref.o \ Err bitreich.org 70 i chunker.o \ Err bitreich.org 70 i compress.o \ Err bitreich.org 70 i icache.o \ Err bitreich.org 70 i@@ -41,10 +43,10 @@ DISTFILES = \ Err bitreich.org 70 i Makefile \ Err bitreich.org 70 i README \ Err bitreich.org 70 i Err bitreich.org 70 i-CFLAGS = -g -O2 -Wall Err bitreich.org 70 i+CFLAGS = -g -O2 -Wall -fopenmp Err bitreich.org 70 i CPPFLAGS = -I/usr/local/include -D_FILE_OFFSET_BITS=64 Err bitreich.org 70 i LDFLAGS = -L/usr/local/lib Err bitreich.org 70 i-LDLIBS = -llz4 Err bitreich.org 70 i+LDLIBS = -llz4 -lomp Err bitreich.org 70 i Err bitreich.org 70 i all: $(BIN) Err bitreich.org 70 i Err bitreich.org 70 1diff --git a/README b/README /scm/dedup/file/README.gph bitreich.org 70 i@@ -41,6 +41,7 @@ Dependencies Err bitreich.org 70 i ============ Err bitreich.org 70 i Err bitreich.org 70 i - liblz4 Err bitreich.org 70 i+ - libomp Err bitreich.org 70 i Err bitreich.org 70 i Contact Err bitreich.org 70 i ======= Err bitreich.org 70 1diff --git a/blake2bp-ref.c b/blake2bp-ref.c /scm/dedup/file/blake2bp-ref.c.gph bitreich.org 70 i@@ -0,0 +1,359 @@ Err bitreich.org 70 i+/* Err bitreich.org 70 i+ BLAKE2 reference source code package - reference C implementations Err bitreich.org 70 i+ Err bitreich.org 70 i+ Copyright 2012, Samuel Neves . You may use this under the Err bitreich.org 70 i+ terms of the CC0, the OpenSSL Licence, or the Apache Public License 2.0, at Err bitreich.org 70 i+ your option. The terms of these licenses can be found at: Err bitreich.org 70 i+ Err bitreich.org 70 i+ - CC0 1.0 Universal : http://creativecommons.org/publicdomain/zero/1.0 Err bitreich.org 70 i+ - OpenSSL license : https://www.openssl.org/source/license.html Err bitreich.org 70 i+ - Apache 2.0 : http://www.apache.org/licenses/LICENSE-2.0 Err bitreich.org 70 i+ Err bitreich.org 70 i+ More information about the BLAKE2 hash function can be found at Err bitreich.org 70 i+ https://blake2.net. Err bitreich.org 70 i+*/ Err bitreich.org 70 i+ Err bitreich.org 70 i+#include Err bitreich.org 70 i+#include Err bitreich.org 70 i+#include Err bitreich.org 70 i+#include Err bitreich.org 70 i+ Err bitreich.org 70 i+#if defined(_OPENMP) Err bitreich.org 70 i+#include Err bitreich.org 70 i+#endif Err bitreich.org 70 i+ Err bitreich.org 70 i+#include "blake2.h" Err bitreich.org 70 i+#include "blake2-impl.h" Err bitreich.org 70 i+ Err bitreich.org 70 i+#define PARALLELISM_DEGREE 4 Err bitreich.org 70 i+ Err bitreich.org 70 i+/* Err bitreich.org 70 i+ blake2b_init_param defaults to setting the expecting output length Err bitreich.org 70 i+ from the digest_length parameter block field. Err bitreich.org 70 i+ Err bitreich.org 70 i+ In some cases, however, we do not want this, as the output length Err bitreich.org 70 i+ of these instances is given by inner_length instead. Err bitreich.org 70 i+*/ Err bitreich.org 70 i+static int blake2bp_init_leaf_param( blake2b_state *S, const blake2b_param *P ) Err bitreich.org 70 i+{ Err bitreich.org 70 i+ int err = blake2b_init_param(S, P); Err bitreich.org 70 i+ S->outlen = P->inner_length; Err bitreich.org 70 i+ return err; Err bitreich.org 70 i+} Err bitreich.org 70 i+ Err bitreich.org 70 i+static int blake2bp_init_leaf( blake2b_state *S, size_t outlen, size_t keylen, uint64_t offset ) Err bitreich.org 70 i+{ Err bitreich.org 70 i+ blake2b_param P[1]; Err bitreich.org 70 i+ P->digest_length = (uint8_t)outlen; Err bitreich.org 70 i+ P->key_length = (uint8_t)keylen; Err bitreich.org 70 i+ P->fanout = PARALLELISM_DEGREE; Err bitreich.org 70 i+ P->depth = 2; Err bitreich.org 70 i+ store32( &P->leaf_length, 0 ); Err bitreich.org 70 i+ store32( &P->node_offset, offset ); Err bitreich.org 70 i+ store32( &P->xof_length, 0 ); Err bitreich.org 70 i+ P->node_depth = 0; Err bitreich.org 70 i+ P->inner_length = BLAKE2B_OUTBYTES; Err bitreich.org 70 i+ memset( P->reserved, 0, sizeof( P->reserved ) ); Err bitreich.org 70 i+ memset( P->salt, 0, sizeof( P->salt ) ); Err bitreich.org 70 i+ memset( P->personal, 0, sizeof( P->personal ) ); Err bitreich.org 70 i+ return blake2bp_init_leaf_param( S, P ); Err bitreich.org 70 i+} Err bitreich.org 70 i+ Err bitreich.org 70 i+static int blake2bp_init_root( blake2b_state *S, size_t outlen, size_t keylen ) Err bitreich.org 70 i+{ Err bitreich.org 70 i+ blake2b_param P[1]; Err bitreich.org 70 i+ P->digest_length = (uint8_t)outlen; Err bitreich.org 70 i+ P->key_length = (uint8_t)keylen; Err bitreich.org 70 i+ P->fanout = PARALLELISM_DEGREE; Err bitreich.org 70 i+ P->depth = 2; Err bitreich.org 70 i+ store32( &P->leaf_length, 0 ); Err bitreich.org 70 i+ store32( &P->node_offset, 0 ); Err bitreich.org 70 i+ store32( &P->xof_length, 0 ); Err bitreich.org 70 i+ P->node_depth = 1; Err bitreich.org 70 i+ P->inner_length = BLAKE2B_OUTBYTES; Err bitreich.org 70 i+ memset( P->reserved, 0, sizeof( P->reserved ) ); Err bitreich.org 70 i+ memset( P->salt, 0, sizeof( P->salt ) ); Err bitreich.org 70 i+ memset( P->personal, 0, sizeof( P->personal ) ); Err bitreich.org 70 i+ return blake2b_init_param( S, P ); Err bitreich.org 70 i+} Err bitreich.org 70 i+ Err bitreich.org 70 i+ Err bitreich.org 70 i+int blake2bp_init( blake2bp_state *S, size_t outlen ) Err bitreich.org 70 i+{ Err bitreich.org 70 i+ size_t i; Err bitreich.org 70 i+ Err bitreich.org 70 i+ if( !outlen || outlen > BLAKE2B_OUTBYTES ) return -1; Err bitreich.org 70 i+ Err bitreich.org 70 i+ memset( S->buf, 0, sizeof( S->buf ) ); Err bitreich.org 70 i+ S->buflen = 0; Err bitreich.org 70 i+ S->outlen = outlen; Err bitreich.org 70 i+ Err bitreich.org 70 i+ if( blake2bp_init_root( S->R, outlen, 0 ) < 0 ) Err bitreich.org 70 i+ return -1; Err bitreich.org 70 i+ Err bitreich.org 70 i+ for( i = 0; i < PARALLELISM_DEGREE; ++i ) Err bitreich.org 70 i+ if( blake2bp_init_leaf( S->S[i], outlen, 0, i ) < 0 ) return -1; Err bitreich.org 70 i+ Err bitreich.org 70 i+ S->R->last_node = 1; Err bitreich.org 70 i+ S->S[PARALLELISM_DEGREE - 1]->last_node = 1; Err bitreich.org 70 i+ return 0; Err bitreich.org 70 i+} Err bitreich.org 70 i+ Err bitreich.org 70 i+int blake2bp_init_key( blake2bp_state *S, size_t outlen, const void *key, size_t keylen ) Err bitreich.org 70 i+{ Err bitreich.org 70 i+ size_t i; Err bitreich.org 70 i+ Err bitreich.org 70 i+ if( !outlen || outlen > BLAKE2B_OUTBYTES ) return -1; Err bitreich.org 70 i+ Err bitreich.org 70 i+ if( !key || !keylen || keylen > BLAKE2B_KEYBYTES ) return -1; Err bitreich.org 70 i+ Err bitreich.org 70 i+ memset( S->buf, 0, sizeof( S->buf ) ); Err bitreich.org 70 i+ S->buflen = 0; Err bitreich.org 70 i+ S->outlen = outlen; Err bitreich.org 70 i+ Err bitreich.org 70 i+ if( blake2bp_init_root( S->R, outlen, keylen ) < 0 ) Err bitreich.org 70 i+ return -1; Err bitreich.org 70 i+ Err bitreich.org 70 i+ for( i = 0; i < PARALLELISM_DEGREE; ++i ) Err bitreich.org 70 i+ if( blake2bp_init_leaf( S->S[i], outlen, keylen, i ) < 0 ) return -1; Err bitreich.org 70 i+ Err bitreich.org 70 i+ S->R->last_node = 1; Err bitreich.org 70 i+ S->S[PARALLELISM_DEGREE - 1]->last_node = 1; Err bitreich.org 70 i+ { Err bitreich.org 70 i+ uint8_t block[BLAKE2B_BLOCKBYTES]; Err bitreich.org 70 i+ memset( block, 0, BLAKE2B_BLOCKBYTES ); Err bitreich.org 70 i+ memcpy( block, key, keylen ); Err bitreich.org 70 i+ Err bitreich.org 70 i+ for( i = 0; i < PARALLELISM_DEGREE; ++i ) Err bitreich.org 70 i+ blake2b_update( S->S[i], block, BLAKE2B_BLOCKBYTES ); Err bitreich.org 70 i+ Err bitreich.org 70 i+ secure_zero_memory( block, BLAKE2B_BLOCKBYTES ); /* Burn the key from stack */ Err bitreich.org 70 i+ } Err bitreich.org 70 i+ return 0; Err bitreich.org 70 i+} Err bitreich.org 70 i+ Err bitreich.org 70 i+ Err bitreich.org 70 i+int blake2bp_update( blake2bp_state *S, const void *pin, size_t inlen ) Err bitreich.org 70 i+{ Err bitreich.org 70 i+ const unsigned char * in = (const unsigned char *)pin; Err bitreich.org 70 i+ size_t left = S->buflen; Err bitreich.org 70 i+ size_t fill = sizeof( S->buf ) - left; Err bitreich.org 70 i+ size_t i; Err bitreich.org 70 i+ Err bitreich.org 70 i+ if( left && inlen >= fill ) Err bitreich.org 70 i+ { Err bitreich.org 70 i+ memcpy( S->buf + left, in, fill ); Err bitreich.org 70 i+ Err bitreich.org 70 i+ for( i = 0; i < PARALLELISM_DEGREE; ++i ) Err bitreich.org 70 i+ blake2b_update( S->S[i], S->buf + i * BLAKE2B_BLOCKBYTES, BLAKE2B_BLOCKBYTES ); Err bitreich.org 70 i+ Err bitreich.org 70 i+ in += fill; Err bitreich.org 70 i+ inlen -= fill; Err bitreich.org 70 i+ left = 0; Err bitreich.org 70 i+ } Err bitreich.org 70 i+ Err bitreich.org 70 i+#if defined(_OPENMP) Err bitreich.org 70 i+ #pragma omp parallel shared(S), num_threads(PARALLELISM_DEGREE) Err bitreich.org 70 i+#else Err bitreich.org 70 i+ Err bitreich.org 70 i+ for( i = 0; i < PARALLELISM_DEGREE; ++i ) Err bitreich.org 70 i+#endif Err bitreich.org 70 i+ { Err bitreich.org 70 i+#if defined(_OPENMP) Err bitreich.org 70 i+ size_t i = omp_get_thread_num(); Err bitreich.org 70 i+#endif Err bitreich.org 70 i+ size_t inlen__ = inlen; Err bitreich.org 70 i+ const unsigned char *in__ = ( const unsigned char * )in; Err bitreich.org 70 i+ in__ += i * BLAKE2B_BLOCKBYTES; Err bitreich.org 70 i+ Err bitreich.org 70 i+ while( inlen__ >= PARALLELISM_DEGREE * BLAKE2B_BLOCKBYTES ) Err bitreich.org 70 i+ { Err bitreich.org 70 i+ blake2b_update( S->S[i], in__, BLAKE2B_BLOCKBYTES ); Err bitreich.org 70 i+ in__ += PARALLELISM_DEGREE * BLAKE2B_BLOCKBYTES; Err bitreich.org 70 i+ inlen__ -= PARALLELISM_DEGREE * BLAKE2B_BLOCKBYTES; Err bitreich.org 70 i+ } Err bitreich.org 70 i+ } Err bitreich.org 70 i+ Err bitreich.org 70 i+ in += inlen - inlen % ( PARALLELISM_DEGREE * BLAKE2B_BLOCKBYTES ); Err bitreich.org 70 i+ inlen %= PARALLELISM_DEGREE * BLAKE2B_BLOCKBYTES; Err bitreich.org 70 i+ Err bitreich.org 70 i+ if( inlen > 0 ) Err bitreich.org 70 i+ memcpy( S->buf + left, in, inlen ); Err bitreich.org 70 i+ Err bitreich.org 70 i+ S->buflen = left + inlen; Err bitreich.org 70 i+ return 0; Err bitreich.org 70 i+} Err bitreich.org 70 i+ Err bitreich.org 70 i+int blake2bp_final( blake2bp_state *S, void *out, size_t outlen ) Err bitreich.org 70 i+{ Err bitreich.org 70 i+ uint8_t hash[PARALLELISM_DEGREE][BLAKE2B_OUTBYTES]; Err bitreich.org 70 i+ size_t i; Err bitreich.org 70 i+ Err bitreich.org 70 i+ if(out == NULL || outlen < S->outlen) { Err bitreich.org 70 i+ return -1; Err bitreich.org 70 i+ } Err bitreich.org 70 i+ Err bitreich.org 70 i+ for( i = 0; i < PARALLELISM_DEGREE; ++i ) Err bitreich.org 70 i+ { Err bitreich.org 70 i+ if( S->buflen > i * BLAKE2B_BLOCKBYTES ) Err bitreich.org 70 i+ { Err bitreich.org 70 i+ size_t left = S->buflen - i * BLAKE2B_BLOCKBYTES; Err bitreich.org 70 i+ Err bitreich.org 70 i+ if( left > BLAKE2B_BLOCKBYTES ) left = BLAKE2B_BLOCKBYTES; Err bitreich.org 70 i+ Err bitreich.org 70 i+ blake2b_update( S->S[i], S->buf + i * BLAKE2B_BLOCKBYTES, left ); Err bitreich.org 70 i+ } Err bitreich.org 70 i+ Err bitreich.org 70 i+ blake2b_final( S->S[i], hash[i], BLAKE2B_OUTBYTES ); Err bitreich.org 70 i+ } Err bitreich.org 70 i+ Err bitreich.org 70 i+ for( i = 0; i < PARALLELISM_DEGREE; ++i ) Err bitreich.org 70 i+ blake2b_update( S->R, hash[i], BLAKE2B_OUTBYTES ); Err bitreich.org 70 i+ Err bitreich.org 70 i+ return blake2b_final( S->R, out, S->outlen ); Err bitreich.org 70 i+} Err bitreich.org 70 i+ Err bitreich.org 70 i+int blake2bp( void *out, size_t outlen, const void *in, size_t inlen, const void *key, size_t keylen ) Err bitreich.org 70 i+{ Err bitreich.org 70 i+ uint8_t hash[PARALLELISM_DEGREE][BLAKE2B_OUTBYTES]; Err bitreich.org 70 i+ blake2b_state S[PARALLELISM_DEGREE][1]; Err bitreich.org 70 i+ blake2b_state FS[1]; Err bitreich.org 70 i+ size_t i; Err bitreich.org 70 i+ Err bitreich.org 70 i+ /* Verify parameters */ Err bitreich.org 70 i+ if ( NULL == in && inlen > 0 ) return -1; Err bitreich.org 70 i+ Err bitreich.org 70 i+ if ( NULL == out ) return -1; Err bitreich.org 70 i+ Err bitreich.org 70 i+ if( NULL == key && keylen > 0 ) return -1; Err bitreich.org 70 i+ Err bitreich.org 70 i+ if( !outlen || outlen > BLAKE2B_OUTBYTES ) return -1; Err bitreich.org 70 i+ Err bitreich.org 70 i+ if( keylen > BLAKE2B_KEYBYTES ) return -1; Err bitreich.org 70 i+ Err bitreich.org 70 i+ for( i = 0; i < PARALLELISM_DEGREE; ++i ) Err bitreich.org 70 i+ if( blake2bp_init_leaf( S[i], outlen, keylen, i ) < 0 ) return -1; Err bitreich.org 70 i+ Err bitreich.org 70 i+ S[PARALLELISM_DEGREE - 1]->last_node = 1; /* mark last node */ Err bitreich.org 70 i+ Err bitreich.org 70 i+ if( keylen > 0 ) Err bitreich.org 70 i+ { Err bitreich.org 70 i+ uint8_t block[BLAKE2B_BLOCKBYTES]; Err bitreich.org 70 i+ memset( block, 0, BLAKE2B_BLOCKBYTES ); Err bitreich.org 70 i+ memcpy( block, key, keylen ); Err bitreich.org 70 i+ Err bitreich.org 70 i+ for( i = 0; i < PARALLELISM_DEGREE; ++i ) Err bitreich.org 70 i+ blake2b_update( S[i], block, BLAKE2B_BLOCKBYTES ); Err bitreich.org 70 i+ Err bitreich.org 70 i+ secure_zero_memory( block, BLAKE2B_BLOCKBYTES ); /* Burn the key from stack */ Err bitreich.org 70 i+ } Err bitreich.org 70 i+ Err bitreich.org 70 i+#if defined(_OPENMP) Err bitreich.org 70 i+ #pragma omp parallel shared(S,hash), num_threads(PARALLELISM_DEGREE) Err bitreich.org 70 i+#else Err bitreich.org 70 i+ Err bitreich.org 70 i+ for( i = 0; i < PARALLELISM_DEGREE; ++i ) Err bitreich.org 70 i+#endif Err bitreich.org 70 i+ { Err bitreich.org 70 i+#if defined(_OPENMP) Err bitreich.org 70 i+ size_t i = omp_get_thread_num(); Err bitreich.org 70 i+#endif Err bitreich.org 70 i+ size_t inlen__ = inlen; Err bitreich.org 70 i+ const unsigned char *in__ = ( const unsigned char * )in; Err bitreich.org 70 i+ in__ += i * BLAKE2B_BLOCKBYTES; Err bitreich.org 70 i+ Err bitreich.org 70 i+ while( inlen__ >= PARALLELISM_DEGREE * BLAKE2B_BLOCKBYTES ) Err bitreich.org 70 i+ { Err bitreich.org 70 i+ blake2b_update( S[i], in__, BLAKE2B_BLOCKBYTES ); Err bitreich.org 70 i+ in__ += PARALLELISM_DEGREE * BLAKE2B_BLOCKBYTES; Err bitreich.org 70 i+ inlen__ -= PARALLELISM_DEGREE * BLAKE2B_BLOCKBYTES; Err bitreich.org 70 i+ } Err bitreich.org 70 i+ Err bitreich.org 70 i+ if( inlen__ > i * BLAKE2B_BLOCKBYTES ) Err bitreich.org 70 i+ { Err bitreich.org 70 i+ const size_t left = inlen__ - i * BLAKE2B_BLOCKBYTES; Err bitreich.org 70 i+ const size_t len = left <= BLAKE2B_BLOCKBYTES ? left : BLAKE2B_BLOCKBYTES; Err bitreich.org 70 i+ blake2b_update( S[i], in__, len ); Err bitreich.org 70 i+ } Err bitreich.org 70 i+ Err bitreich.org 70 i+ blake2b_final( S[i], hash[i], BLAKE2B_OUTBYTES ); Err bitreich.org 70 i+ } Err bitreich.org 70 i+ Err bitreich.org 70 i+ if( blake2bp_init_root( FS, outlen, keylen ) < 0 ) Err bitreich.org 70 i+ return -1; Err bitreich.org 70 i+ Err bitreich.org 70 i+ FS->last_node = 1; /* Mark as last node */ Err bitreich.org 70 i+ Err bitreich.org 70 i+ for( i = 0; i < PARALLELISM_DEGREE; ++i ) Err bitreich.org 70 i+ blake2b_update( FS, hash[i], BLAKE2B_OUTBYTES ); Err bitreich.org 70 i+ Err bitreich.org 70 i+ return blake2b_final( FS, out, outlen );; Err bitreich.org 70 i+} Err bitreich.org 70 i+ Err bitreich.org 70 i+#if defined(BLAKE2BP_SELFTEST) Err bitreich.org 70 i+#include Err bitreich.org 70 i+#include "blake2-kat.h" Err bitreich.org 70 i+int main( void ) Err bitreich.org 70 i+{ Err bitreich.org 70 i+ uint8_t key[BLAKE2B_KEYBYTES]; Err bitreich.org 70 i+ uint8_t buf[BLAKE2_KAT_LENGTH]; Err bitreich.org 70 i+ size_t i, step; Err bitreich.org 70 i+ Err bitreich.org 70 i+ for( i = 0; i < BLAKE2B_KEYBYTES; ++i ) Err bitreich.org 70 i+ key[i] = ( uint8_t )i; Err bitreich.org 70 i+ Err bitreich.org 70 i+ for( i = 0; i < BLAKE2_KAT_LENGTH; ++i ) Err bitreich.org 70 i+ buf[i] = ( uint8_t )i; Err bitreich.org 70 i+ Err bitreich.org 70 i+ /* Test simple API */ Err bitreich.org 70 i+ for( i = 0; i < BLAKE2_KAT_LENGTH; ++i ) Err bitreich.org 70 i+ { Err bitreich.org 70 i+ uint8_t hash[BLAKE2B_OUTBYTES]; Err bitreich.org 70 i+ blake2bp( hash, BLAKE2B_OUTBYTES, buf, i, key, BLAKE2B_KEYBYTES ); Err bitreich.org 70 i+ Err bitreich.org 70 i+ if( 0 != memcmp( hash, blake2bp_keyed_kat[i], BLAKE2B_OUTBYTES ) ) Err bitreich.org 70 i+ { Err bitreich.org 70 i+ goto fail; Err bitreich.org 70 i+ } Err bitreich.org 70 i+ } Err bitreich.org 70 i+ Err bitreich.org 70 i+ /* Test streaming API */ Err bitreich.org 70 i+ for(step = 1; step < BLAKE2B_BLOCKBYTES; ++step) { Err bitreich.org 70 i+ for (i = 0; i < BLAKE2_KAT_LENGTH; ++i) { Err bitreich.org 70 i+ uint8_t hash[BLAKE2B_OUTBYTES]; Err bitreich.org 70 i+ blake2bp_state S; Err bitreich.org 70 i+ uint8_t * p = buf; Err bitreich.org 70 i+ size_t mlen = i; Err bitreich.org 70 i+ int err = 0; Err bitreich.org 70 i+ Err bitreich.org 70 i+ if( (err = blake2bp_init_key(&S, BLAKE2B_OUTBYTES, key, BLAKE2B_KEYBYTES)) < 0 ) { Err bitreich.org 70 i+ goto fail; Err bitreich.org 70 i+ } Err bitreich.org 70 i+ Err bitreich.org 70 i+ while (mlen >= step) { Err bitreich.org 70 i+ if ( (err = blake2bp_update(&S, p, step)) < 0 ) { Err bitreich.org 70 i+ goto fail; Err bitreich.org 70 i+ } Err bitreich.org 70 i+ mlen -= step; Err bitreich.org 70 i+ p += step; Err bitreich.org 70 i+ } Err bitreich.org 70 i+ if ( (err = blake2bp_update(&S, p, mlen)) < 0) { Err bitreich.org 70 i+ goto fail; Err bitreich.org 70 i+ } Err bitreich.org 70 i+ if ( (err = blake2bp_final(&S, hash, BLAKE2B_OUTBYTES)) < 0) { Err bitreich.org 70 i+ goto fail; Err bitreich.org 70 i+ } Err bitreich.org 70 i+ Err bitreich.org 70 i+ if (0 != memcmp(hash, blake2bp_keyed_kat[i], BLAKE2B_OUTBYTES)) { Err bitreich.org 70 i+ goto fail; Err bitreich.org 70 i+ } Err bitreich.org 70 i+ } Err bitreich.org 70 i+ } Err bitreich.org 70 i+ Err bitreich.org 70 i+ puts( "ok" ); Err bitreich.org 70 i+ return 0; Err bitreich.org 70 i+fail: Err bitreich.org 70 i+ puts("error"); Err bitreich.org 70 i+ return -1; Err bitreich.org 70 i+} Err bitreich.org 70 i+#endif Err bitreich.org 70 1diff --git a/dedup.c b/dedup.c /scm/dedup/file/dedup.c.gph bitreich.org 70 i@@ -104,17 +104,17 @@ free_snap(struct snap *snap) Err bitreich.org 70 i static void Err bitreich.org 70 i hash_snap(struct snap *snap, uint8_t *md) Err bitreich.org 70 i { Err bitreich.org 70 i- blake2b_state ctx; Err bitreich.org 70 i+ blake2bp_state ctx; Err bitreich.org 70 i uint64_t i; Err bitreich.org 70 i Err bitreich.org 70 i- blake2b_init(&ctx, MD_SIZE); Err bitreich.org 70 i+ blake2bp_init(&ctx, MD_SIZE); Err bitreich.org 70 i for (i = 0; i < snap->nr_blk_descs; i++) { Err bitreich.org 70 i struct blk_desc *blk_desc; Err bitreich.org 70 i Err bitreich.org 70 i blk_desc = &snap->blk_desc[i]; Err bitreich.org 70 i- blake2b_update(&ctx, blk_desc->md, sizeof(blk_desc->md)); Err bitreich.org 70 i+ blake2bp_update(&ctx, blk_desc->md, sizeof(blk_desc->md)); Err bitreich.org 70 i } Err bitreich.org 70 i- blake2b_final(&ctx, md, MD_SIZE); Err bitreich.org 70 i+ blake2bp_final(&ctx, md, MD_SIZE); Err bitreich.org 70 i } Err bitreich.org 70 i Err bitreich.org 70 i static struct snap * Err bitreich.org 70 i@@ -180,11 +180,11 @@ free_buf(uint8_t *buf) Err bitreich.org 70 i static void Err bitreich.org 70 i hash_blk(uint8_t *buf, size_t size, uint8_t *md) Err bitreich.org 70 i { Err bitreich.org 70 i- blake2b_state ctx; Err bitreich.org 70 i+ blake2bp_state ctx; Err bitreich.org 70 i Err bitreich.org 70 i- blake2b_init(&ctx, MD_SIZE); Err bitreich.org 70 i- blake2b_update(&ctx, buf, size); Err bitreich.org 70 i- blake2b_final(&ctx, md, MD_SIZE); Err bitreich.org 70 i+ blake2bp_init(&ctx, MD_SIZE); Err bitreich.org 70 i+ blake2bp_update(&ctx, buf, size); Err bitreich.org 70 i+ blake2bp_final(&ctx, md, MD_SIZE); Err bitreich.org 70 i } Err bitreich.org 70 i Err bitreich.org 70 i static void Err bitreich.org 70 i@@ -337,15 +337,15 @@ check_snap(struct snap *snap, void *arg) Err bitreich.org 70 i buf = alloc_buf(compr_size(BLKSIZE_MAX)); Err bitreich.org 70 i for (i = 0; i < snap->nr_blk_descs; i++) { Err bitreich.org 70 i uint8_t md[MD_SIZE]; Err bitreich.org 70 i- blake2b_state ctx; Err bitreich.org 70 i+ blake2bp_state ctx; Err bitreich.org 70 i struct blk_desc *blk_desc; Err bitreich.org 70 i Err bitreich.org 70 i blk_desc = &snap->blk_desc[i]; Err bitreich.org 70 i read_blk(buf, blk_desc); Err bitreich.org 70 i Err bitreich.org 70 i- blake2b_init(&ctx, MD_SIZE); Err bitreich.org 70 i- blake2b_update(&ctx, buf, blk_desc->size); Err bitreich.org 70 i- blake2b_final(&ctx, md, MD_SIZE); Err bitreich.org 70 i+ blake2bp_init(&ctx, MD_SIZE); Err bitreich.org 70 i+ blake2bp_update(&ctx, buf, blk_desc->size); Err bitreich.org 70 i+ blake2bp_final(&ctx, md, MD_SIZE); Err bitreich.org 70 i Err bitreich.org 70 i if (memcmp(blk_desc->md, md, sizeof(blk_desc->md)) == 0) Err bitreich.org 70 i continue; Err bitreich.org 70 .