From 52a8a9708e093ffcf936ba5a5bdbd1123ab05e82 Mon Sep 17 00:00:00 2001 From: x Date: Sun, 19 Mar 2017 13:20:20 +0100 Subject: [PATCH] BitUtil: c/c++ header --- bitutil.h | 192 ++++++++++++++++++++++++++---------------------------- 1 file changed, 92 insertions(+), 100 deletions(-) diff --git a/bitutil.h b/bitutil.h index 625f9a9..cc79777 100644 --- a/bitutil.h +++ b/bitutil.h @@ -21,18 +21,18 @@ - twitter : https://twitter.com/powturbo - email : powturbo [_AT_] gmail [_DOT_] com **/ -// "Integer Compression" +// "Integer Compression: max.bits, delta, zigzag, xor" #include -#define BITFORSET_(_out_, _n_, _start_, _inc_) do { unsigned _i;\ +#define BITFORSET_(_out_, _n_, _start_, _mindelta_) do { unsigned _i;\ for(_i = 0; _i != (_n_&~3); _i+=4) {\ - _out_[_i+0] = _start_+(_i )*_inc_;\ - _out_[_i+1] = _start_+(_i+1)*_inc_;\ - _out_[_i+2] = _start_+(_i+2)*_inc_;\ - _out_[_i+3] = _start_+(_i+3)*_inc_;\ + _out_[_i+0] = _start_+(_i )*_mindelta_;\ + _out_[_i+1] = _start_+(_i+1)*_mindelta_;\ + _out_[_i+2] = _start_+(_i+2)*_mindelta_;\ + _out_[_i+3] = _start_+(_i+3)*_mindelta_;\ }\ while(_i != _n_)\ - _out_[_i] = _start_+_i*_inc_, ++_i;\ + _out_[_i] = _start_+_i*_mindelta_, ++_i;\ } while(0) #define BITSIZE_(_in_, _n_, _b_, _usize_) { typeof(_in_[0]) *_ip,_u=0;\ @@ -47,27 +47,28 @@ #define BITSIZE16(_in_, _n_, _b_) BITSIZE_(_in_, _n_, _b_, 16) #define BITSIZE64(_in_, _n_, _b_) BITSIZE_(_in_, _n_, _b_, 64) -static inline unsigned char zigzagenc8( char x) { return x << 1 ^ x >> 7; } -static inline unsigned char zigzagdec8( unsigned short x) { return x >> 1 ^ -(x & 1); } +static inline unsigned char zigzagenc8( char x) { return x << 1 ^ x >> 7; } +static inline unsigned char zigzagdec8( unsigned short x) { return x >> 1 ^ -(x & 1); } -static inline unsigned short zigzagenc16(short x) { return x << 1 ^ x >> 15; } -static inline unsigned short zigzagdec16(unsigned short x) { return x >> 1 ^ -(x & 1); } +static inline unsigned short zigzagenc16(short x) { return x << 1 ^ x >> 15; } +static inline unsigned short zigzagdec16(unsigned short x) { return x >> 1 ^ -(x & 1); } -static inline unsigned zigzagenc31(int x) { x = (x << 2 | ((x>>30)& 2)) ^ x >> 31; return x; } // for signed x -static inline unsigned zigzagdec31(unsigned x) { return (x >> 2 | (x& 2)<<30 ) ^ -(x & 1); } +static inline unsigned zigzagenc31(int x) { x = (x << 2 | ((x>>30)& 2)) ^ x >> 31; return x; } // for signed x +static inline unsigned zigzagdec31(unsigned x) { return (x >> 2 | (x& 2)<<30 ) ^ -(x & 1); } static inline unsigned long long zigzagenc63(long long x) { x = (x << 2 | ((x>>62)& 2)) ^ x >> 63; return x; } // for signed x static inline unsigned long long zigzagdec63(unsigned long long x) { return (x >> 2 | (x& 2)<<62 ) ^ -(x & 1); } -static inline unsigned zigzagenc32(int x) { return x << 1 ^ x >> 31; } -static inline unsigned zigzagdec32(unsigned x) { return x >> 1 ^ -(x & 1); } +static inline unsigned zigzagenc32(int x) { return x << 1 ^ x >> 31; } +static inline unsigned zigzagdec32(unsigned x) { return x >> 1 ^ -(x & 1); } -static inline uint64_t zigzagenc64(int64_t x) { return x << 1 ^ x >> 63; } -static inline uint64_t zigzagdec64(uint64_t x) { return x >> 1 ^ -(x & 1); } +static inline uint64_t zigzagenc64(int64_t x) { return x << 1 ^ x >> 63; } +static inline uint64_t zigzagdec64(uint64_t x) { return x >> 1 ^ -(x & 1); } #ifdef __AVX2__ #include -#include -//#define DELTA256x32(_v_, _sv_,_iv_) ? + +#define DELTA256x32(_v_, _sv_) _mm256_sub_epi32(_v_, _mm256_or_si256(_mm256_srli_si256( _mm256_permute2x128_si256(_sv_, _sv_, _MM_SHUFFLE(2, 0, 0, 1)), 12),\ + _mm256_alignr_epi8(_v_, _mm256_permute2x128_si256(_v_, _v_, _MM_SHUFFLE(0, 0, 2, 0)), 12))) #define SCAN256x32( _v_, _sv_) {\ _v_ = _mm256_add_epi32(_v_, _mm256_slli_si256(_v_, 4));\ @@ -99,7 +100,7 @@ static inline uint64_t zigzagdec64(uint64_t x) { return x >> 1 ^ -(x #define HOR128x32(_v_,_b_) _v_ = _mm_or_si128(_v_, _mm_srli_si128(_v_, 8)); _v_ = _mm_or_si128(_v_, _mm_srli_si128(_v_, 4)); _b_ = (unsigned)_mm_cvtsi128_si32(_v_) #endif - #if 0 //def __AVX2__ + #if defined(__AVX2__) && defined(USE_AVX2) #define BITSIZE32(_in_, _n_, _b_) { typeof(_in_[0]) *_ip; __m256i _v = _mm256_setzero_si256();\ for(_ip = _in_; _ip != _in_+(_n_&~(8-1)); _ip+=8)\ _v = _mm256_or_si256(_v, _mm256_loadu_si256((__m256i*)_ip));\ @@ -113,18 +114,18 @@ static inline uint64_t zigzagdec64(uint64_t x) { return x >> 1 ^ -(x do _mm256_storeu_si256(_ov++, _sv_); while(_ov < _ove);\ } while(0) -#define BITFORZERO32(_out_, _n_, _start_, _inc_) do {\ - __m256i _sv = _mm256_set1_epi32(_start_), *_ov=(__m256i *)(_out_), *_ove = (__m256i *)(_out_ + _n_), _cv = _mm256_set_epi32(7+_inc_,6+_inc_,5+_inc_,4+_inc_,3*_inc_,2*_inc_,1*_inc_,0); \ +#define BITFORZERO32(_out_, _n_, _start_, _mindelta_) do {\ + __m256i _sv = _mm256_set1_epi32(_start_), *_ov=(__m256i *)(_out_), *_ove = (__m256i *)(_out_ + _n_), _cv = _mm256_set_epi32(7+_mindelta_,6+_mindelta_,5+_mindelta_,4+_mindelta_,3*_mindelta_,2*_mindelta_,1*_mindelta_,0); \ _sv = _mm256_add_epi32(_sv, _cv);\ _cv = _mm256_set1_epi32(4);\ do { _mm256_storeu_si256(_ov++, _sv); _sv = _mm256_add_epi32(_sv, _cv); } while(_ov < _ove);\ } while(0) -#define BITDIZERO32(_out_, _n_, _start_, _inc_) do { __m256i _sv = _mm256_set1_epi32(_start_), _cv = _mm256_set_epi32(7+_inc_,6+_inc_,5+_inc_,4+_inc_,3+_inc_,2+_inc_,1+_inc_,_inc_), *_ov=(__m256i *)(_out_), *_ove = (__m256i *)(_out_ + _n_);\ - _sv = _mm256_add_epi32(_sv, _cv); _cv = _mm256_set1_epi32(4*_inc_); do { _mm256_storeu_si256(_ov++, _sv), _sv = _mm256_add_epi32(_sv, _cv); } while(_ov < _ove);\ +#define BITDIZERO32(_out_, _n_, _start_, _mindelta_) do { __m256i _sv = _mm256_set1_epi32(_start_), _cv = _mm256_set_epi32(7+_mindelta_,6+_mindelta_,5+_mindelta_,4+_mindelta_,3+_mindelta_,2+_mindelta_,1+_mindelta_,_mindelta_), *_ov=(__m256i *)(_out_), *_ove = (__m256i *)(_out_ + _n_);\ + _sv = _mm256_add_epi32(_sv, _cv); _cv = _mm256_set1_epi32(4*_mindelta_); do { _mm256_storeu_si256(_ov++, _sv), _sv = _mm256_add_epi32(_sv, _cv); } while(_ov < _ove);\ } while(0) - #elif defined(__SSE2__) + #elif defined(__SSE2__) // ------------- #define BITSIZE32(_in_, _n_, _b_) { typeof(_in_[0]) *_ip; __m128i _v = _mm_setzero_si128();\ for(_ip = _in_; _ip != _in_+(_n_&~(4-1)); _ip+=4)\ _v = _mm_or_si128(_v, _mm_loadu_si128((__m128i*)_ip));\ @@ -139,25 +140,25 @@ static inline uint64_t zigzagdec64(uint64_t x) { return x >> 1 ^ -(x do _mm_storeu_si128(_ov++, _sv_); while(_ov < _ove); \ } while(0) -#define BITFORZERO32(_out_, _n_, _start_, _inc_) do {\ - __m128i _sv = _mm_set1_epi32(_start_), *_ov=(__m128i *)(_out_), *_ove = (__m128i *)(_out_ + _n_), _cv = _mm_set_epi32(3*_inc_,2*_inc_,1*_inc_,0); \ +#define BITFORZERO32(_out_, _n_, _start_, _mindelta_) do {\ + __m128i _sv = _mm_set1_epi32(_start_), *_ov=(__m128i *)(_out_), *_ove = (__m128i *)(_out_ + _n_), _cv = _mm_set_epi32(3*_mindelta_,2*_mindelta_,1*_mindelta_,0); \ _sv = _mm_add_epi32(_sv, _cv);\ _cv = _mm_set1_epi32(4);\ do { _mm_storeu_si128(_ov++, _sv); _sv = _mm_add_epi32(_sv, _cv); } while(_ov < _ove);\ } while(0) -#define BITDIZERO32(_out_, _n_, _start_, _inc_) do { __m128i _sv = _mm_set1_epi32(_start_), _cv = _mm_set_epi32(3+_inc_,2+_inc_,1+_inc_,_inc_), *_ov=(__m128i *)(_out_), *_ove = (__m128i *)(_out_ + _n_);\ - _sv = _mm_add_epi32(_sv, _cv); _cv = _mm_set1_epi32(4*_inc_); do { _mm_storeu_si128(_ov++, _sv), _sv = _mm_add_epi32(_sv, _cv); } while(_ov < _ove);\ +#define BITDIZERO32(_out_, _n_, _start_, _mindelta_) do { __m128i _sv = _mm_set1_epi32(_start_), _cv = _mm_set_epi32(3+_mindelta_,2+_mindelta_,1+_mindelta_,_mindelta_), *_ov=(__m128i *)(_out_), *_ove = (__m128i *)(_out_ + _n_);\ + _sv = _mm_add_epi32(_sv, _cv); _cv = _mm_set1_epi32(4*_mindelta_); do { _mm_storeu_si128(_ov++, _sv), _sv = _mm_add_epi32(_sv, _cv); } while(_ov < _ove);\ } while(0) #else #define BITSIZE32( _in_, _n_, _b_) BITSIZE_(_in_, _n_, _b_, 32) -#define BITFORZERO32(_out_, _n_, _start_, _inc_) BITFORSET_(_out_, _n_, _start_, _inc_) +#define BITFORZERO32(_out_, _n_, _start_, _mindelta_) BITFORSET_(_out_, _n_, _start_, _mindelta_) #define BITZERO32( _out_, _n_, _start_) BITFORSET_(_out_, _n_, _start_, 0) #endif -#define DELTR( _in_, _n_, _start_, _inc_, _out_) { unsigned _v; for( _v = 0; _v < _n_; _v++) _out_[_v] = _in_[_v] - (_start_) - _v*(_inc_) - (_inc_); } -#define DELTRB(_in_, _n_, _start_, _inc_, _b_, _out_) { unsigned _v; for(_b_=0,_v = 0; _v < _n_; _v++) _out_[_v] = _in_[_v] - (_start_) - _v*(_inc_) - (_inc_), _b_ |= _out_[_v]; _b_ = bsr32(_b_); } +#define DELTR( _in_, _n_, _start_, _mindelta_, _out_) { unsigned _v; for( _v = 0; _v < _n_; _v++) _out_[_v] = _in_[_v] - (_start_) - _v*(_mindelta_) - (_mindelta_); } +#define DELTRB(_in_, _n_, _start_, _mindelta_, _b_, _out_) { unsigned _v; for(_b_=0,_v = 0; _v < _n_; _v++) _out_[_v] = _in_[_v] - (_start_) - _v*(_mindelta_) - (_mindelta_), _b_ |= _out_[_v]; _b_ = bsr32(_b_); } #ifdef __cplusplus extern "C" { @@ -170,103 +171,94 @@ unsigned bit32( uint32_t *in, unsigned n); unsigned bit64( uint64_t *in, unsigned n); //------------- Delta for sorted integer array ---------------------------------------------------- + //-- get delta maximum bit length of the non decreasing integer array. out[i] = in[i] - in[i-1] -unsigned bitd8( uint8_t *in, unsigned n, uint8_t start); +unsigned bitd8( uint8_t *in, unsigned n, uint8_t start); unsigned bitd16( uint16_t *in, unsigned n, uint16_t start); unsigned bitd32( uint32_t *in, unsigned n, uint32_t start); unsigned bitd64( uint64_t *in, unsigned n, uint64_t start); +//-- in-place reverse delta (encoded w/ bitdiencNN and parameter mindelta=0) +void bitddec8( uint8_t *p, unsigned n, uint8_t start); // non decreasing (out[i] = in[i] - in[i-1]) +void bitddec16( uint16_t *p, unsigned n, uint16_t start); +void bitddec32( uint32_t *p, unsigned n, uint32_t start); +void bitddec64( uint64_t *p, unsigned n, uint64_t start); //-- get delta maximum bit length of the non strictly decreasing integer array. out[i] = in[i] - in[i-1] - 1 unsigned bitd18( uint8_t *in, unsigned n, uint8_t start); unsigned bitd116( uint16_t *in, unsigned n, uint16_t start); unsigned bitd132( uint32_t *in, unsigned n, uint32_t start); unsigned bitd164( uint64_t *in, unsigned n, uint64_t start); +//-- in-place reverse delta (encoded w/ bitdiencNN and parameter mindelta = 1) +void bitd1dec8( uint8_t *p, unsigned n, uint8_t start); // non strictly decreasing (out[i] = in[i] - in[i-1] - 1) +void bitd1dec16( uint16_t *p, unsigned n, uint16_t start); +void bitd1dec32( uint32_t *p, unsigned n, uint32_t start); +void bitd1dec64( uint64_t *p, unsigned n, uint64_t start); -//-- transform sorted integer array to delta array. inc = increment: out[i] = in[i] - in[i-1] - inc -unsigned bitdenc8( uint8_t *in, unsigned n, uint8_t *out, uint8_t start, unsigned inc); -unsigned bitdenc16(uint16_t *in, unsigned n, uint16_t *out, uint16_t start, unsigned inc); -unsigned bitdenc32(uint32_t *in, unsigned n, uint32_t *out, uint32_t start, unsigned inc); -unsigned bitdenc64(uint64_t *in, unsigned n, uint64_t *out, uint64_t start, unsigned inc); -//-- in-place reverse delta transform -void bitddec8( uint8_t *p, unsigned n, uint8_t start); // non decreasing -void bitddec16( uint16_t *p, unsigned n, uint16_t start); -void bitddec32( uint32_t *p, unsigned n, uint32_t start); -void bitddec64( uint64_t *p, unsigned n, uint64_t start); - -void bitd1dec8( uint8_t *p, unsigned n, uint8_t start); // non strictly decreasing -void bitd1dec16( uint16_t *p, unsigned n, uint16_t start); -void bitd1dec32( uint32_t *p, unsigned n, uint32_t start); -void bitd1dec64( uint64_t *p, unsigned n, uint64_t start); - -void bitddecn8( uint8_t *p, unsigned n, uint8_t start, uint8_t inc); // increment -void bitddecn16( uint16_t *p, unsigned n, uint16_t start, uint16_t inc); -void bitddecn32( uint32_t *p, unsigned n, uint32_t start, uint32_t inc); -void bitddecn64( uint64_t *p, unsigned n, uint64_t start, uint64_t inc); - -uint8_t bitdi8( uint8_t *in, unsigned n, uint8_t start); -uint16_t bitdi16(uint16_t *in, unsigned n, uint16_t start); -uint32_t bitdi32(uint32_t *in, unsigned n, uint32_t start); -uint64_t bitdi64(uint64_t *in, unsigned n, uint64_t start); - -unsigned bitdienc8( uint8_t *in, unsigned n, uint8_t *out, uint8_t start, uint8_t inc); -unsigned bitdienc16(uint16_t *in, unsigned n, uint16_t *out, uint16_t start, uint16_t inc); -unsigned bitdienc32(uint32_t *in, unsigned n, uint32_t *out, uint32_t start, uint32_t inc); -unsigned bitdienc64(uint64_t *in, unsigned n, uint64_t *out, uint64_t start, uint64_t inc); - -void bitdidec8( uint8_t *p, unsigned n, uint8_t start, uint8_t inc); -void bitdidec16( uint16_t *p, unsigned n, uint16_t start, uint16_t inc); -void bitdidec32( uint32_t *p, unsigned n, uint32_t start, uint32_t inc); -void bitdidec64( uint64_t *p, unsigned n, uint64_t start, uint64_t inc); +//-- get min. delta (mindelta = in[i] - in[i-1]) +uint8_t bitdi8( uint8_t *in, unsigned n, uint8_t start); +uint16_t bitdi16( uint16_t *in, unsigned n, uint16_t start); +uint32_t bitdi32( uint32_t *in, unsigned n, uint32_t start); +uint64_t bitdi64( uint64_t *in, unsigned n, uint64_t start); +//-- encode sorted integer array to delta array: out[i] = in[i] - in[i-1] - mindelta +unsigned bitdienc8( uint8_t *in, unsigned n, uint8_t *out, uint8_t start, uint8_t mindelta); +unsigned bitdienc16(uint16_t *in, unsigned n, uint16_t *out, uint16_t start, uint16_t mindelta); +unsigned bitdienc32(uint32_t *in, unsigned n, uint32_t *out, uint32_t start, uint32_t mindelta); +unsigned bitdienc64(uint64_t *in, unsigned n, uint64_t *out, uint64_t start, uint64_t mindelta); +//-- in-place reverse delta +void bitdidec8( uint8_t *p, unsigned n, uint8_t start, uint8_t mindelta); +void bitdidec16( uint16_t *p, unsigned n, uint16_t start, uint16_t mindelta); +void bitdidec32( uint32_t *p, unsigned n, uint32_t start, uint32_t mindelta); +void bitdidec64( uint64_t *p, unsigned n, uint64_t start, uint64_t mindelta); //------------- FOR array bit length: out[i] = in[i] - start ------------------------------------- -unsigned bitf32( uint32_t *in, unsigned n, uint32_t start); // sorted -unsigned bitf132( uint32_t *in, unsigned n, uint32_t start); +unsigned bitf32( uint32_t *in, unsigned n, uint32_t start); // sorted +unsigned bitf132( uint32_t *in, unsigned n, uint32_t start); -unsigned bitfm8( uint8_t *in, unsigned n, uint8_t *pmin); // unsorted -unsigned bitfm16( uint16_t *in, unsigned n, uint16_t *pmin); -unsigned bitfm32( uint32_t *in, unsigned n, uint32_t *pmin); -unsigned bitfm64( uint64_t *in, unsigned n, uint64_t *pmin); +unsigned bitfm8( uint8_t *in, unsigned n, uint8_t *pmin); // unsorted +unsigned bitfm16( uint16_t *in, unsigned n, uint16_t *pmin); +unsigned bitfm32( uint32_t *in, unsigned n, uint32_t *pmin); +unsigned bitfm64( uint64_t *in, unsigned n, uint64_t *pmin); //------------- Zigzag encoding for unsorted integer lists: out[i] = in[i] - in[i-1] ------------- //-- get maximum zigzag bit length integer array -unsigned bitz8( uint8_t *in, unsigned n, uint8_t start); -unsigned bitz16( uint16_t *in, unsigned n, uint16_t start); -unsigned bitz32( uint32_t *in, unsigned n, uint32_t start); -unsigned bitz64( uint64_t *in, unsigned n, uint64_t start); +unsigned bitz8( uint8_t *in, unsigned n, uint8_t start); +unsigned bitz16( uint16_t *in, unsigned n, uint16_t start); +unsigned bitz32( uint32_t *in, unsigned n, uint32_t start); +unsigned bitz64( uint64_t *in, unsigned n, uint64_t start); //-- Zigzag transform -unsigned bitzenc8( uint8_t *in, unsigned n, uint8_t *out, uint8_t start, uint8_t inc); -unsigned bitzenc16(uint16_t *in, unsigned n, uint16_t *out, uint16_t start, uint16_t inc); -unsigned bitzenc32(uint32_t *in, unsigned n, uint32_t *out, uint32_t start, uint32_t inc); -unsigned bitzenc64(uint64_t *in, unsigned n, uint64_t *out, uint64_t start, uint64_t inc); +unsigned bitzenc8( uint8_t *in, unsigned n, uint8_t *out, uint8_t start, uint8_t mindelta); +unsigned bitzenc16( uint16_t *in, unsigned n, uint16_t *out, uint16_t start, uint16_t mindelta); +unsigned bitzenc32( uint32_t *in, unsigned n, uint32_t *out, uint32_t start, uint32_t mindelta); +unsigned bitzenc64( uint64_t *in, unsigned n, uint64_t *out, uint64_t start, uint64_t mindelta); //-- Zigzag reverse transform -void bitzdec8( uint8_t *p, unsigned n, uint8_t start); -void bitzdec16( uint16_t *p, unsigned n, uint16_t start); -void bitzdec32( uint32_t *p, unsigned n, uint32_t start); -void bitzdec64( uint64_t *p, unsigned n, uint64_t start); +void bitzdec8( uint8_t *p, unsigned n, uint8_t start); +void bitzdec16( uint16_t *p, unsigned n, uint16_t start); +void bitzdec32( uint32_t *p, unsigned n, uint32_t start); +void bitzdec64( uint64_t *p, unsigned n, uint64_t start); //------------- XOR encoding for unsorted integer lists: out[i] = in[i] - in[i-1] ------------- //-- get maximum zigzag bit length integer array -unsigned bitx8( uint8_t *in, unsigned n, uint8_t start); -unsigned bitx16( uint16_t *in, unsigned n, uint16_t start); -unsigned bitx32( uint32_t *in, unsigned n, uint32_t start); -unsigned bitx64( uint64_t *in, unsigned n, uint64_t start); +unsigned bitx8( uint8_t *in, unsigned n, uint8_t start); +unsigned bitx16( uint16_t *in, unsigned n, uint16_t start); +unsigned bitx32( uint32_t *in, unsigned n, uint32_t start); +unsigned bitx64( uint64_t *in, unsigned n, uint64_t start); -//-- Zigzag transform -unsigned bitxenc8( uint8_t *in, unsigned n, uint8_t *out, uint8_t start); -unsigned bitxenc16(uint16_t *in, unsigned n, uint16_t *out, uint16_t start); -unsigned bitxenc32(uint32_t *in, unsigned n, uint32_t *out, uint32_t start); -unsigned bitxenc64(uint64_t *in, unsigned n, uint64_t *out, uint64_t start); +//-- XOR transform +unsigned bitxenc8( uint8_t *in, unsigned n, uint8_t *out, uint8_t start); +unsigned bitxenc16( uint16_t *in, unsigned n, uint16_t *out, uint16_t start); +unsigned bitxenc32( uint32_t *in, unsigned n, uint32_t *out, uint32_t start); +unsigned bitxenc64( uint64_t *in, unsigned n, uint64_t *out, uint64_t start); -//-- Zigzag reverse transform -void bitxdec8( uint8_t *p, unsigned n, uint8_t start); -void bitxdec16( uint16_t *p, unsigned n, uint16_t start); -void bitxdec32( uint32_t *p, unsigned n, uint32_t start); -void bitxdec64( uint64_t *p, unsigned n, uint64_t start); +//-- XOR in-place reverse transform +void bitxdec8( uint8_t *p, unsigned n, uint8_t start); +void bitxdec16( uint16_t *p, unsigned n, uint16_t start); +void bitxdec32( uint32_t *p, unsigned n, uint32_t start); +void bitxdec64( uint64_t *p, unsigned n, uint64_t start); #ifdef __cplusplus }