bitstream.h 18 KB

123456789101112131415161718192021222324252627282930313233343536373839404142434445464748495051525354555657585960616263646566676869707172737475767778798081828384858687888990919293949596979899100101102103104105106107108109110111112113114115116117118119120121122123124125126127128129130131132133134135136137138139140141142143144145146147148149150151152153154155156157158159160161162163164165166167168169170171172173174175176177178179180181182183184185186187188189190191192193194195196197198199200201202203204205206207208209210211212213214215216217218219220221222223224225226227228229230231232233234235236237238239240241242243244245246247248249250251252253254255256257258259260261262263264265266267268269270271272273274275276277278279280281282283284285286287288289290291292293294295296297298299300301302303304305306307308309310311312313314315316317318319320321322323324325326327328329330331332333334335336337338339340341342343344345346347348349350351352353354355356357358359360361362363364365366367368369370371372373374375376377378379380381382383384385386387388389390391392393394395396397398399400401402403404405406407408409410411412413414415416417418419420421422423424425426427428429430431432433434435436437438439440441442443444445446447448449450451452453454455456457458459460461462463464465466467468469470471472473474475476477478
  1. /* ******************************************************************
  2. * bitstream
  3. * Part of FSE library
  4. * Copyright (c) Yann Collet, Facebook, Inc.
  5. *
  6. * You can contact the author at :
  7. * - Source repository : https://github.com/Cyan4973/FiniteStateEntropy
  8. *
  9. * This source code is licensed under both the BSD-style license (found in the
  10. * LICENSE file in the root directory of this source tree) and the GPLv2 (found
  11. * in the COPYING file in the root directory of this source tree).
  12. * You may select, at your option, one of the above-listed licenses.
  13. ****************************************************************** */
  14. #ifndef BITSTREAM_H_MODULE
  15. #define BITSTREAM_H_MODULE
  16. #if defined (__cplusplus)
  17. extern "C" {
  18. #endif
  19. /*
  20. * This API consists of small unitary functions, which must be inlined for best performance.
  21. * Since link-time-optimization is not available for all compilers,
  22. * these functions are defined into a .h to be included.
  23. */
  24. /*-****************************************
  25. * Dependencies
  26. ******************************************/
  27. #include "mem.h" /* unaligned access routines */
  28. #include "compiler.h" /* UNLIKELY() */
  29. #include "debug.h" /* assert(), DEBUGLOG(), RAWLOG() */
  30. #include "error_private.h" /* error codes and messages */
  31. /*=========================================
  32. * Target specific
  33. =========================================*/
  34. #ifndef ZSTD_NO_INTRINSICS
  35. # if defined(__BMI__) && defined(__GNUC__)
  36. # include <immintrin.h> /* support for bextr (experimental) */
  37. # elif defined(__ICCARM__)
  38. # include <intrinsics.h>
  39. # endif
  40. #endif
  41. #define STREAM_ACCUMULATOR_MIN_32 25
  42. #define STREAM_ACCUMULATOR_MIN_64 57
  43. #define STREAM_ACCUMULATOR_MIN ((U32)(MEM_32bits() ? STREAM_ACCUMULATOR_MIN_32 : STREAM_ACCUMULATOR_MIN_64))
  44. /*-******************************************
  45. * bitStream encoding API (write forward)
  46. ********************************************/
  47. /* bitStream can mix input from multiple sources.
  48. * A critical property of these streams is that they encode and decode in **reverse** direction.
  49. * So the first bit sequence you add will be the last to be read, like a LIFO stack.
  50. */
  51. typedef struct {
  52. size_t bitContainer;
  53. unsigned bitPos;
  54. char* startPtr;
  55. char* ptr;
  56. char* endPtr;
  57. } BIT_CStream_t;
  58. MEM_STATIC size_t BIT_initCStream(BIT_CStream_t* bitC, void* dstBuffer, size_t dstCapacity);
  59. MEM_STATIC void BIT_addBits(BIT_CStream_t* bitC, size_t value, unsigned nbBits);
  60. MEM_STATIC void BIT_flushBits(BIT_CStream_t* bitC);
  61. MEM_STATIC size_t BIT_closeCStream(BIT_CStream_t* bitC);
  62. /* Start with initCStream, providing the size of buffer to write into.
  63. * bitStream will never write outside of this buffer.
  64. * `dstCapacity` must be >= sizeof(bitD->bitContainer), otherwise @return will be an error code.
  65. *
  66. * bits are first added to a local register.
  67. * Local register is size_t, hence 64-bits on 64-bits systems, or 32-bits on 32-bits systems.
  68. * Writing data into memory is an explicit operation, performed by the flushBits function.
  69. * Hence keep track how many bits are potentially stored into local register to avoid register overflow.
  70. * After a flushBits, a maximum of 7 bits might still be stored into local register.
  71. *
  72. * Avoid storing elements of more than 24 bits if you want compatibility with 32-bits bitstream readers.
  73. *
  74. * Last operation is to close the bitStream.
  75. * The function returns the final size of CStream in bytes.
  76. * If data couldn't fit into `dstBuffer`, it will return a 0 ( == not storable)
  77. */
  78. /*-********************************************
  79. * bitStream decoding API (read backward)
  80. **********************************************/
  81. typedef struct {
  82. size_t bitContainer;
  83. unsigned bitsConsumed;
  84. const char* ptr;
  85. const char* start;
  86. const char* limitPtr;
  87. } BIT_DStream_t;
  88. typedef enum { BIT_DStream_unfinished = 0,
  89. BIT_DStream_endOfBuffer = 1,
  90. BIT_DStream_completed = 2,
  91. BIT_DStream_overflow = 3 } BIT_DStream_status; /* result of BIT_reloadDStream() */
  92. /* 1,2,4,8 would be better for bitmap combinations, but slows down performance a bit ... :( */
  93. MEM_STATIC size_t BIT_initDStream(BIT_DStream_t* bitD, const void* srcBuffer, size_t srcSize);
  94. MEM_STATIC size_t BIT_readBits(BIT_DStream_t* bitD, unsigned nbBits);
  95. MEM_STATIC BIT_DStream_status BIT_reloadDStream(BIT_DStream_t* bitD);
  96. MEM_STATIC unsigned BIT_endOfDStream(const BIT_DStream_t* bitD);
  97. /* Start by invoking BIT_initDStream().
  98. * A chunk of the bitStream is then stored into a local register.
  99. * Local register size is 64-bits on 64-bits systems, 32-bits on 32-bits systems (size_t).
  100. * You can then retrieve bitFields stored into the local register, **in reverse order**.
  101. * Local register is explicitly reloaded from memory by the BIT_reloadDStream() method.
  102. * A reload guarantee a minimum of ((8*sizeof(bitD->bitContainer))-7) bits when its result is BIT_DStream_unfinished.
  103. * Otherwise, it can be less than that, so proceed accordingly.
  104. * Checking if DStream has reached its end can be performed with BIT_endOfDStream().
  105. */
  106. /*-****************************************
  107. * unsafe API
  108. ******************************************/
  109. MEM_STATIC void BIT_addBitsFast(BIT_CStream_t* bitC, size_t value, unsigned nbBits);
  110. /* faster, but works only if value is "clean", meaning all high bits above nbBits are 0 */
  111. MEM_STATIC void BIT_flushBitsFast(BIT_CStream_t* bitC);
  112. /* unsafe version; does not check buffer overflow */
  113. MEM_STATIC size_t BIT_readBitsFast(BIT_DStream_t* bitD, unsigned nbBits);
  114. /* faster, but works only if nbBits >= 1 */
  115. /*-**************************************************************
  116. * Internal functions
  117. ****************************************************************/
  118. MEM_STATIC unsigned BIT_highbit32 (U32 val)
  119. {
  120. assert(val != 0);
  121. {
  122. # if defined(_MSC_VER) /* Visual */
  123. # if STATIC_BMI2 == 1
  124. return _lzcnt_u32(val) ^ 31;
  125. # else
  126. if (val != 0) {
  127. unsigned long r;
  128. _BitScanReverse(&r, val);
  129. return (unsigned)r;
  130. } else {
  131. /* Should not reach this code path */
  132. __assume(0);
  133. }
  134. # endif
  135. # elif defined(__GNUC__) && (__GNUC__ >= 3) /* Use GCC Intrinsic */
  136. return __builtin_clz (val) ^ 31;
  137. # elif defined(__ICCARM__) /* IAR Intrinsic */
  138. return 31 - __CLZ(val);
  139. # else /* Software version */
  140. static const unsigned DeBruijnClz[32] = { 0, 9, 1, 10, 13, 21, 2, 29,
  141. 11, 14, 16, 18, 22, 25, 3, 30,
  142. 8, 12, 20, 28, 15, 17, 24, 7,
  143. 19, 27, 23, 6, 26, 5, 4, 31 };
  144. U32 v = val;
  145. v |= v >> 1;
  146. v |= v >> 2;
  147. v |= v >> 4;
  148. v |= v >> 8;
  149. v |= v >> 16;
  150. return DeBruijnClz[ (U32) (v * 0x07C4ACDDU) >> 27];
  151. # endif
  152. }
  153. }
  154. /*===== Local Constants =====*/
  155. static const unsigned BIT_mask[] = {
  156. 0, 1, 3, 7, 0xF, 0x1F,
  157. 0x3F, 0x7F, 0xFF, 0x1FF, 0x3FF, 0x7FF,
  158. 0xFFF, 0x1FFF, 0x3FFF, 0x7FFF, 0xFFFF, 0x1FFFF,
  159. 0x3FFFF, 0x7FFFF, 0xFFFFF, 0x1FFFFF, 0x3FFFFF, 0x7FFFFF,
  160. 0xFFFFFF, 0x1FFFFFF, 0x3FFFFFF, 0x7FFFFFF, 0xFFFFFFF, 0x1FFFFFFF,
  161. 0x3FFFFFFF, 0x7FFFFFFF}; /* up to 31 bits */
  162. #define BIT_MASK_SIZE (sizeof(BIT_mask) / sizeof(BIT_mask[0]))
  163. /*-**************************************************************
  164. * bitStream encoding
  165. ****************************************************************/
  166. /*! BIT_initCStream() :
  167. * `dstCapacity` must be > sizeof(size_t)
  168. * @return : 0 if success,
  169. * otherwise an error code (can be tested using ERR_isError()) */
  170. MEM_STATIC size_t BIT_initCStream(BIT_CStream_t* bitC,
  171. void* startPtr, size_t dstCapacity)
  172. {
  173. bitC->bitContainer = 0;
  174. bitC->bitPos = 0;
  175. bitC->startPtr = (char*)startPtr;
  176. bitC->ptr = bitC->startPtr;
  177. bitC->endPtr = bitC->startPtr + dstCapacity - sizeof(bitC->bitContainer);
  178. if (dstCapacity <= sizeof(bitC->bitContainer)) return ERROR(dstSize_tooSmall);
  179. return 0;
  180. }
  181. /*! BIT_addBits() :
  182. * can add up to 31 bits into `bitC`.
  183. * Note : does not check for register overflow ! */
  184. MEM_STATIC void BIT_addBits(BIT_CStream_t* bitC,
  185. size_t value, unsigned nbBits)
  186. {
  187. DEBUG_STATIC_ASSERT(BIT_MASK_SIZE == 32);
  188. assert(nbBits < BIT_MASK_SIZE);
  189. assert(nbBits + bitC->bitPos < sizeof(bitC->bitContainer) * 8);
  190. bitC->bitContainer |= (value & BIT_mask[nbBits]) << bitC->bitPos;
  191. bitC->bitPos += nbBits;
  192. }
  193. /*! BIT_addBitsFast() :
  194. * works only if `value` is _clean_,
  195. * meaning all high bits above nbBits are 0 */
  196. MEM_STATIC void BIT_addBitsFast(BIT_CStream_t* bitC,
  197. size_t value, unsigned nbBits)
  198. {
  199. assert((value>>nbBits) == 0);
  200. assert(nbBits + bitC->bitPos < sizeof(bitC->bitContainer) * 8);
  201. bitC->bitContainer |= value << bitC->bitPos;
  202. bitC->bitPos += nbBits;
  203. }
  204. /*! BIT_flushBitsFast() :
  205. * assumption : bitContainer has not overflowed
  206. * unsafe version; does not check buffer overflow */
  207. MEM_STATIC void BIT_flushBitsFast(BIT_CStream_t* bitC)
  208. {
  209. size_t const nbBytes = bitC->bitPos >> 3;
  210. assert(bitC->bitPos < sizeof(bitC->bitContainer) * 8);
  211. assert(bitC->ptr <= bitC->endPtr);
  212. MEM_writeLEST(bitC->ptr, bitC->bitContainer);
  213. bitC->ptr += nbBytes;
  214. bitC->bitPos &= 7;
  215. bitC->bitContainer >>= nbBytes*8;
  216. }
  217. /*! BIT_flushBits() :
  218. * assumption : bitContainer has not overflowed
  219. * safe version; check for buffer overflow, and prevents it.
  220. * note : does not signal buffer overflow.
  221. * overflow will be revealed later on using BIT_closeCStream() */
  222. MEM_STATIC void BIT_flushBits(BIT_CStream_t* bitC)
  223. {
  224. size_t const nbBytes = bitC->bitPos >> 3;
  225. assert(bitC->bitPos < sizeof(bitC->bitContainer) * 8);
  226. assert(bitC->ptr <= bitC->endPtr);
  227. MEM_writeLEST(bitC->ptr, bitC->bitContainer);
  228. bitC->ptr += nbBytes;
  229. if (bitC->ptr > bitC->endPtr) bitC->ptr = bitC->endPtr;
  230. bitC->bitPos &= 7;
  231. bitC->bitContainer >>= nbBytes*8;
  232. }
  233. /*! BIT_closeCStream() :
  234. * @return : size of CStream, in bytes,
  235. * or 0 if it could not fit into dstBuffer */
  236. MEM_STATIC size_t BIT_closeCStream(BIT_CStream_t* bitC)
  237. {
  238. BIT_addBitsFast(bitC, 1, 1); /* endMark */
  239. BIT_flushBits(bitC);
  240. if (bitC->ptr >= bitC->endPtr) return 0; /* overflow detected */
  241. return (bitC->ptr - bitC->startPtr) + (bitC->bitPos > 0);
  242. }
  243. /*-********************************************************
  244. * bitStream decoding
  245. **********************************************************/
  246. /*! BIT_initDStream() :
  247. * Initialize a BIT_DStream_t.
  248. * `bitD` : a pointer to an already allocated BIT_DStream_t structure.
  249. * `srcSize` must be the *exact* size of the bitStream, in bytes.
  250. * @return : size of stream (== srcSize), or an errorCode if a problem is detected
  251. */
  252. MEM_STATIC size_t BIT_initDStream(BIT_DStream_t* bitD, const void* srcBuffer, size_t srcSize)
  253. {
  254. if (srcSize < 1) { ZSTD_memset(bitD, 0, sizeof(*bitD)); return ERROR(srcSize_wrong); }
  255. bitD->start = (const char*)srcBuffer;
  256. bitD->limitPtr = bitD->start + sizeof(bitD->bitContainer);
  257. if (srcSize >= sizeof(bitD->bitContainer)) { /* normal case */
  258. bitD->ptr = (const char*)srcBuffer + srcSize - sizeof(bitD->bitContainer);
  259. bitD->bitContainer = MEM_readLEST(bitD->ptr);
  260. { BYTE const lastByte = ((const BYTE*)srcBuffer)[srcSize-1];
  261. bitD->bitsConsumed = lastByte ? 8 - BIT_highbit32(lastByte) : 0; /* ensures bitsConsumed is always set */
  262. if (lastByte == 0) return ERROR(GENERIC); /* endMark not present */ }
  263. } else {
  264. bitD->ptr = bitD->start;
  265. bitD->bitContainer = *(const BYTE*)(bitD->start);
  266. switch(srcSize)
  267. {
  268. case 7: bitD->bitContainer += (size_t)(((const BYTE*)(srcBuffer))[6]) << (sizeof(bitD->bitContainer)*8 - 16);
  269. ZSTD_FALLTHROUGH;
  270. case 6: bitD->bitContainer += (size_t)(((const BYTE*)(srcBuffer))[5]) << (sizeof(bitD->bitContainer)*8 - 24);
  271. ZSTD_FALLTHROUGH;
  272. case 5: bitD->bitContainer += (size_t)(((const BYTE*)(srcBuffer))[4]) << (sizeof(bitD->bitContainer)*8 - 32);
  273. ZSTD_FALLTHROUGH;
  274. case 4: bitD->bitContainer += (size_t)(((const BYTE*)(srcBuffer))[3]) << 24;
  275. ZSTD_FALLTHROUGH;
  276. case 3: bitD->bitContainer += (size_t)(((const BYTE*)(srcBuffer))[2]) << 16;
  277. ZSTD_FALLTHROUGH;
  278. case 2: bitD->bitContainer += (size_t)(((const BYTE*)(srcBuffer))[1]) << 8;
  279. ZSTD_FALLTHROUGH;
  280. default: break;
  281. }
  282. { BYTE const lastByte = ((const BYTE*)srcBuffer)[srcSize-1];
  283. bitD->bitsConsumed = lastByte ? 8 - BIT_highbit32(lastByte) : 0;
  284. if (lastByte == 0) return ERROR(corruption_detected); /* endMark not present */
  285. }
  286. bitD->bitsConsumed += (U32)(sizeof(bitD->bitContainer) - srcSize)*8;
  287. }
  288. return srcSize;
  289. }
  290. MEM_STATIC FORCE_INLINE_ATTR size_t BIT_getUpperBits(size_t bitContainer, U32 const start)
  291. {
  292. return bitContainer >> start;
  293. }
  294. MEM_STATIC FORCE_INLINE_ATTR size_t BIT_getMiddleBits(size_t bitContainer, U32 const start, U32 const nbBits)
  295. {
  296. U32 const regMask = sizeof(bitContainer)*8 - 1;
  297. /* if start > regMask, bitstream is corrupted, and result is undefined */
  298. assert(nbBits < BIT_MASK_SIZE);
  299. /* x86 transform & ((1 << nbBits) - 1) to bzhi instruction, it is better
  300. * than accessing memory. When bmi2 instruction is not present, we consider
  301. * such cpus old (pre-Haswell, 2013) and their performance is not of that
  302. * importance.
  303. */
  304. #if defined(__x86_64__) || defined(_M_X86)
  305. return (bitContainer >> (start & regMask)) & ((((U64)1) << nbBits) - 1);
  306. #else
  307. return (bitContainer >> (start & regMask)) & BIT_mask[nbBits];
  308. #endif
  309. }
  310. MEM_STATIC FORCE_INLINE_ATTR size_t BIT_getLowerBits(size_t bitContainer, U32 const nbBits)
  311. {
  312. #if defined(STATIC_BMI2) && STATIC_BMI2 == 1
  313. return _bzhi_u64(bitContainer, nbBits);
  314. #else
  315. assert(nbBits < BIT_MASK_SIZE);
  316. return bitContainer & BIT_mask[nbBits];
  317. #endif
  318. }
  319. /*! BIT_lookBits() :
  320. * Provides next n bits from local register.
  321. * local register is not modified.
  322. * On 32-bits, maxNbBits==24.
  323. * On 64-bits, maxNbBits==56.
  324. * @return : value extracted */
  325. MEM_STATIC FORCE_INLINE_ATTR size_t BIT_lookBits(const BIT_DStream_t* bitD, U32 nbBits)
  326. {
  327. /* arbitrate between double-shift and shift+mask */
  328. #if 1
  329. /* if bitD->bitsConsumed + nbBits > sizeof(bitD->bitContainer)*8,
  330. * bitstream is likely corrupted, and result is undefined */
  331. return BIT_getMiddleBits(bitD->bitContainer, (sizeof(bitD->bitContainer)*8) - bitD->bitsConsumed - nbBits, nbBits);
  332. #else
  333. /* this code path is slower on my os-x laptop */
  334. U32 const regMask = sizeof(bitD->bitContainer)*8 - 1;
  335. return ((bitD->bitContainer << (bitD->bitsConsumed & regMask)) >> 1) >> ((regMask-nbBits) & regMask);
  336. #endif
  337. }
  338. /*! BIT_lookBitsFast() :
  339. * unsafe version; only works if nbBits >= 1 */
  340. MEM_STATIC size_t BIT_lookBitsFast(const BIT_DStream_t* bitD, U32 nbBits)
  341. {
  342. U32 const regMask = sizeof(bitD->bitContainer)*8 - 1;
  343. assert(nbBits >= 1);
  344. return (bitD->bitContainer << (bitD->bitsConsumed & regMask)) >> (((regMask+1)-nbBits) & regMask);
  345. }
  346. MEM_STATIC FORCE_INLINE_ATTR void BIT_skipBits(BIT_DStream_t* bitD, U32 nbBits)
  347. {
  348. bitD->bitsConsumed += nbBits;
  349. }
  350. /*! BIT_readBits() :
  351. * Read (consume) next n bits from local register and update.
  352. * Pay attention to not read more than nbBits contained into local register.
  353. * @return : extracted value. */
  354. MEM_STATIC FORCE_INLINE_ATTR size_t BIT_readBits(BIT_DStream_t* bitD, unsigned nbBits)
  355. {
  356. size_t const value = BIT_lookBits(bitD, nbBits);
  357. BIT_skipBits(bitD, nbBits);
  358. return value;
  359. }
  360. /*! BIT_readBitsFast() :
  361. * unsafe version; only works only if nbBits >= 1 */
  362. MEM_STATIC size_t BIT_readBitsFast(BIT_DStream_t* bitD, unsigned nbBits)
  363. {
  364. size_t const value = BIT_lookBitsFast(bitD, nbBits);
  365. assert(nbBits >= 1);
  366. BIT_skipBits(bitD, nbBits);
  367. return value;
  368. }
  369. /*! BIT_reloadDStreamFast() :
  370. * Similar to BIT_reloadDStream(), but with two differences:
  371. * 1. bitsConsumed <= sizeof(bitD->bitContainer)*8 must hold!
  372. * 2. Returns BIT_DStream_overflow when bitD->ptr < bitD->limitPtr, at this
  373. * point you must use BIT_reloadDStream() to reload.
  374. */
  375. MEM_STATIC BIT_DStream_status BIT_reloadDStreamFast(BIT_DStream_t* bitD)
  376. {
  377. if (UNLIKELY(bitD->ptr < bitD->limitPtr))
  378. return BIT_DStream_overflow;
  379. assert(bitD->bitsConsumed <= sizeof(bitD->bitContainer)*8);
  380. bitD->ptr -= bitD->bitsConsumed >> 3;
  381. bitD->bitsConsumed &= 7;
  382. bitD->bitContainer = MEM_readLEST(bitD->ptr);
  383. return BIT_DStream_unfinished;
  384. }
  385. /*! BIT_reloadDStream() :
  386. * Refill `bitD` from buffer previously set in BIT_initDStream() .
  387. * This function is safe, it guarantees it will not read beyond src buffer.
  388. * @return : status of `BIT_DStream_t` internal register.
  389. * when status == BIT_DStream_unfinished, internal register is filled with at least 25 or 57 bits */
  390. MEM_STATIC BIT_DStream_status BIT_reloadDStream(BIT_DStream_t* bitD)
  391. {
  392. if (bitD->bitsConsumed > (sizeof(bitD->bitContainer)*8)) /* overflow detected, like end of stream */
  393. return BIT_DStream_overflow;
  394. if (bitD->ptr >= bitD->limitPtr) {
  395. return BIT_reloadDStreamFast(bitD);
  396. }
  397. if (bitD->ptr == bitD->start) {
  398. if (bitD->bitsConsumed < sizeof(bitD->bitContainer)*8) return BIT_DStream_endOfBuffer;
  399. return BIT_DStream_completed;
  400. }
  401. /* start < ptr < limitPtr */
  402. { U32 nbBytes = bitD->bitsConsumed >> 3;
  403. BIT_DStream_status result = BIT_DStream_unfinished;
  404. if (bitD->ptr - nbBytes < bitD->start) {
  405. nbBytes = (U32)(bitD->ptr - bitD->start); /* ptr > start */
  406. result = BIT_DStream_endOfBuffer;
  407. }
  408. bitD->ptr -= nbBytes;
  409. bitD->bitsConsumed -= nbBytes*8;
  410. bitD->bitContainer = MEM_readLEST(bitD->ptr); /* reminder : srcSize > sizeof(bitD->bitContainer), otherwise bitD->ptr == bitD->start */
  411. return result;
  412. }
  413. }
  414. /*! BIT_endOfDStream() :
  415. * @return : 1 if DStream has _exactly_ reached its end (all bits consumed).
  416. */
  417. MEM_STATIC unsigned BIT_endOfDStream(const BIT_DStream_t* DStream)
  418. {
  419. return ((DStream->ptr == DStream->start) && (DStream->bitsConsumed == sizeof(DStream->bitContainer)*8));
  420. }
  421. #if defined (__cplusplus)
  422. }
  423. #endif
  424. #endif /* BITSTREAM_H_MODULE */