Test results for amd64, meteor,big, crypto_kem/mceliece8192128f
[Page version: 20260208 13:59:43]
Measurements for amd64, meteor,big, crypto_kem
Test results for amd64, meteor,big, crypto_kem
Test results for crypto_kem/mceliece8192128f
Computer: meteor,big
Microarchitecture: amd64; Redwood Cove (a06a4-40)
Architecture: amd64
CPU ID: GenuineIntel-000a06a4-40-bfebfbff
SUPERCOP version: 20251222
Operation: crypto_kem
Primitive: mceliece8192128f
| Time | Object size | Test size | Implementation | Compiler | Benchmark date | SUPERCOP version |
|---|
| 340000 | 158103 0 0 | 204736 892 1832 | avx | clang -march=native -O3 -fwrapv -Qunused-arguments -fPIC -fPIE -gdwarf-4 -Wall | 20260115 | 20251222 |
| 380696 | 136973 0 0 | 183592 892 1832 | avx | clang -march=native -O2 -fwrapv -Qunused-arguments -fPIC -fPIE -gdwarf-4 -Wall | 20260115 | 20251222 |
| 382796 | 149675 0 0 | 195051 852 1800 | avx | gcc -march=native -mtune=native -O3 -fwrapv -fPIC -fPIE -gdwarf-4 -Wall | 20260115 | 20251222 |
| 401196 | 102717 0 0 | 146155 852 1800 | avx | gcc -march=native -mtune=native -O2 -fwrapv -fPIC -fPIE -gdwarf-4 -Wall | 20260115 | 20251222 |
| 403347 | 97271 0 0 | 140162 876 1832 | avx | clang -march=native -Os -fwrapv -Qunused-arguments -fPIC -fPIE -gdwarf-4 -Wall | 20260115 | 20251222 |
| 404865 | 101644 0 0 | 144272 884 1768 | avx | clang -march=native -O -fwrapv -Qunused-arguments -fPIC -fPIE -gdwarf-4 -Wall | 20260115 | 20251222 |
| 516432 | 140039 0 0 | 193536 876 1832 | sse | clang -march=native -O3 -fwrapv -Qunused-arguments -fPIC -fPIE -gdwarf-4 -Wall | 20260115 | 20251222 |
| 518639 | 123032 0 0 | 176520 876 1832 | sse | clang -march=native -O2 -fwrapv -Qunused-arguments -fPIC -fPIE -gdwarf-4 -Wall | 20260115 | 20251222 |
| 529463 | 190519 0 0 | 244411 852 1800 | sse | gcc -march=native -mtune=native -O3 -fwrapv -fPIC -fPIE -gdwarf-4 -Wall | 20260115 | 20251222 |
| 553773 | 86106 0 0 | 136970 868 1832 | sse | clang -march=native -Os -fwrapv -Qunused-arguments -fPIC -fPIE -gdwarf-4 -Wall | 20260115 | 20251222 |
| 559070 | 98588 0 0 | 150459 852 1800 | sse | gcc -march=native -mtune=native -O2 -fwrapv -fPIC -fPIE -gdwarf-4 -Wall | 20260115 | 20251222 |
| 626593 | 92723 0 0 | 142336 876 1768 | sse | clang -march=native -O -fwrapv -Qunused-arguments -fPIC -fPIE -gdwarf-4 -Wall | 20260115 | 20251222 |
| 743937 | 99578 0 0 | 142955 852 1800 | avx | gcc -march=native -mtune=native -O -fwrapv -fPIC -fPIE -gdwarf-4 -Wall | 20260115 | 20251222 |
| 762254 | 92916 0 0 | 134422 844 1768 | avx | gcc -march=native -mtune=native -Os -fwrapv -fPIC -fPIE -gdwarf-4 -Wall | 20260115 | 20251222 |
| 1326816 | 103870 0 0 | 159947 852 1800 | vec | gcc -march=native -mtune=native -O3 -fwrapv -fPIC -fPIE -gdwarf-4 -Wall | 20260115 | 20251222 |
| 1658367 | 96990 0 0 | 156608 876 1768 | vec | clang -mcpu=native -O3 -fwrapv -Qunused-arguments -fPIC -fPIE -gdwarf-4 -Wall | 20260115 | 20251222 |
| 1756438 | 92448 0 0 | 150184 876 1832 | vec | clang -march=native -O2 -fwrapv -Qunused-arguments -fPIC -fPIE -gdwarf-4 -Wall | 20260115 | 20251222 |
| 1784476 | 108931 0 0 | 164776 876 1832 | vec | clang -march=native -O3 -fwrapv -Qunused-arguments -fPIC -fPIE -gdwarf-4 -Wall | 20260115 | 20251222 |
| 1816870 | 60472 0 0 | 114224 884 1768 | vec | clang -march=native -O -fwrapv -Qunused-arguments -fPIC -fPIE -gdwarf-4 -Wall | 20260115 | 20251222 |
| 2114507 | 58815 0 0 | 112698 876 1832 | vec | clang -march=native -Os -fwrapv -Qunused-arguments -fPIC -fPIE -gdwarf-4 -Wall | 20260115 | 20251222 |
| 2153428 | 66404 0 0 | 120723 852 1800 | vec | gcc -march=native -mtune=native -O2 -fwrapv -fPIC -fPIE -gdwarf-4 -Wall | 20260115 | 20251222 |
| 2541617 | 51499 0 0 | 104182 844 1768 | vec | gcc -march=native -mtune=native -Os -fwrapv -fPIC -fPIE -gdwarf-4 -Wall | 20260115 | 20251222 |
| 2910300 | 62768 0 0 | 117043 852 1800 | vec | gcc -march=native -mtune=native -O -fwrapv -fPIC -fPIE -gdwarf-4 -Wall | 20260115 | 20251222 |
| 122454332 | 89253 0 0 | 140851 852 1800 | sse | gcc -march=native -mtune=native -O -fwrapv -fPIC -fPIE -gdwarf-4 -Wall | 20260115 | 20251222 |
| 122523309 | 83283 0 0 | 133158 844 1768 | sse | gcc -march=native -mtune=native -Os -fwrapv -fPIC -fPIE -gdwarf-4 -Wall | 20260115 | 20251222 |
| 314849718 | 46894 0 0 | 94442 884 1768 | ref | clang -mcpu=native -O3 -fwrapv -Qunused-arguments -fPIC -fPIE -gdwarf-4 -Wall | 20260115 | 20251222 |
| 316399077 | 48955 0 0 | 94416 876 1832 | ref | clang -march=native -O3 -fwrapv -Qunused-arguments -fPIC -fPIE -gdwarf-4 -Wall | 20260115 | 20251222 |
| 316574350 | 29757 0 0 | 75336 876 1832 | ref | clang -march=native -O2 -fwrapv -Qunused-arguments -fPIC -fPIE -gdwarf-4 -Wall | 20260115 | 20251222 |
| 342849034 | 15511 0 0 | 57316 876 1832 | ref | clang -march=native -Os -fwrapv -Qunused-arguments -fPIC -fPIE -gdwarf-4 -Wall | 20260115 | 20251222 |
| 369936288 | 15259 0 0 | 56408 876 1768 | ref | clang -march=native -O -fwrapv -Qunused-arguments -fPIC -fPIE -gdwarf-4 -Wall | 20260115 | 20251222 |
| 393799882 | 17875 0 0 | 59989 860 1800 | ref | gcc -march=native -mtune=native -O2 -fwrapv -fPIC -fPIE -gdwarf-4 -Wall | 20260115 | 20251222 |
| 406946450 | 11645 0 0 | 51744 852 1768 | ref | gcc -march=native -mtune=native -Os -fwrapv -fPIC -fPIE -gdwarf-4 -Wall | 20260115 | 20251222 |
| 413438885 | 15567 0 0 | 57307 852 1800 | ref | gcc -march=native -mtune=native -O -fwrapv -fPIC -fPIE -gdwarf-4 -Wall | 20260115 | 20251222 |
| 418355220 | 36473 0 0 | 80525 860 1800 | ref | gcc -march=native -mtune=native -O3 -fwrapv -fPIC -fPIE -gdwarf-4 -Wall | 20260115 | 20251222 |
Compiler output
bm.c: bm.c:82:37: warning: AVX vector return of type 'vec256' (aka '__m256i') without 'avx' enabled changes the ABI [-Wpsabi]
bm.c: 82 | for (i = 13; i < 16; i++) buf[i] = vec256_setzero();
bm.c: | ^
bm.c: bm.c:84:15: warning: AVX vector return of type 'vec256' (aka '__m256i') without 'avx' enabled changes the ABI [-Wpsabi]
bm.c: 84 | mask[0][0] = vec256_set1_16b(0x5555);
bm.c: | ^
bm.c: bm.c:85:15: warning: AVX vector return of type 'vec256' (aka '__m256i') without 'avx' enabled changes the ABI [-Wpsabi]
bm.c: 85 | mask[0][1] = vec256_set1_16b(0xAAAA);
bm.c: | ^
bm.c: bm.c:86:15: warning: AVX vector return of type 'vec256' (aka '__m256i') without 'avx' enabled changes the ABI [-Wpsabi]
bm.c: 86 | mask[1][0] = vec256_set1_16b(0x3333);
bm.c: | ^
bm.c: bm.c:87:15: warning: AVX vector return of type 'vec256' (aka '__m256i') without 'avx' enabled changes the ABI [-Wpsabi]
bm.c: 87 | mask[1][1] = vec256_set1_16b(0xCCCC);
bm.c: | ^
bm.c: bm.c:88:15: warning: AVX vector return of type 'vec256' (aka '__m256i') without 'avx' enabled changes the ABI [-Wpsabi]
bm.c: 88 | mask[2][0] = vec256_set1_16b(0x0F0F);
bm.c: | ^
bm.c: bm.c:89:15: warning: AVX vector return of type 'vec256' (aka '__m256i') without 'avx' enabled changes the ABI [-Wpsabi]
bm.c: 89 | mask[2][1] = vec256_set1_16b(0xF0F0);
bm.c: | ^
bm.c: bm.c:90:15: warning: AVX vector return of type 'vec256' (aka '__m256i') without 'avx' enabled changes the ABI [-Wpsabi]
bm.c: 90 | mask[3][0] = vec256_set1_16b(0x00FF);
bm.c: | ^
bm.c: bm.c:91:15: warning: AVX vector return of type 'vec256' (aka '__m256i') without 'avx' enabled changes the ABI [-Wpsabi]
bm.c: ...
Number of similar (implementation,compiler) pairs: 1, namely:
| Implementation | Compiler |
| avx | clang -mcpu=native -O3 -fwrapv -Qunused-arguments -fPIC -fPIE -gdwarf-4 -Wall (Debian_Clang_19.1.7_(3+b1)) |
Compiler output
decrypt.c: In file included from decrypt.c:10:
decrypt.c: In file included from ./vec128_gf.h:11:
decrypt.c: ./vec128.h:38:9: error: always_inline function '_mm_testz_si128' requires target feature 'sse4.1', but would be inlined into function 'vec128_testz' that is compiled without support for 'sse4.1'
decrypt.c: 38 | return _mm_testz_si128(a, a);
decrypt.c: | ^
decrypt.c: 1 error generated.
Number of similar (implementation,compiler) pairs: 1, namely:
| Implementation | Compiler |
| sse | clang -mcpu=native -O3 -fwrapv -Qunused-arguments -fPIC -fPIE -gdwarf-4 -Wall (Debian_Clang_19.1.7_(3+b1)) |
TIMECOP error (can be valgrind bug)
error 132
Process terminating with default action of signal 4 (SIGILL)
Illegal opcode at address 0x1168DD
at 0x...: weight (decrypt.c:91)
by 0x...: crypto_kem_mceliece8192128f_avx_constbranchindex_decrypt (decrypt.c:199)
by 0x...: crypto_kem_mceliece8192128f_avx_constbranchindex_operation_dec (kem_dec.c:38)
by 0x...: test (try.c:160)
by 0x...: main (try-anything.c:345)
Illegal instruction
Number of similar (implementation,compiler) pairs: 1, namely:
| Implementation | Compiler |
| avx | clang -march=native -O2 -fwrapv -Qunused-arguments -fPIC -fPIE -gdwarf-4 -Wall (Debian_Clang_19.1.7_(3+b1)) |
TIMECOP error (can be valgrind bug)
error 132
Process terminating with default action of signal 4 (SIGILL)
Illegal opcode at address 0x118571
at 0x...: weight (decrypt.c:91)
by 0x...: crypto_kem_mceliece8192128f_avx_constbranchindex_decrypt (decrypt.c:199)
by 0x...: crypto_kem_mceliece8192128f_avx_constbranchindex_operation_dec (kem_dec.c:38)
by 0x...: test (try.c:160)
by 0x...: main (try-anything.c:345)
Illegal instruction
Number of similar (implementation,compiler) pairs: 1, namely:
| Implementation | Compiler |
| avx | clang -march=native -O3 -fwrapv -Qunused-arguments -fPIC -fPIE -gdwarf-4 -Wall (Debian_Clang_19.1.7_(3+b1)) |
TIMECOP error (can be valgrind bug)
error 132
Process terminating with default action of signal 4 (SIGILL)
Illegal opcode at address 0x111088
at 0x...: weight (decrypt.c:91)
by 0x...: crypto_kem_mceliece8192128f_avx_constbranchindex_decrypt (decrypt.c:199)
by 0x...: crypto_kem_mceliece8192128f_avx_constbranchindex_operation_dec (kem_dec.c:38)
by 0x...: test (try.c:160)
by 0x...: main (try-anything.c:345)
Illegal instruction
Number of similar (implementation,compiler) pairs: 1, namely:
| Implementation | Compiler |
| avx | clang -march=native -Os -fwrapv -Qunused-arguments -fPIC -fPIE -gdwarf-4 -Wall (Debian_Clang_19.1.7_(3+b1)) |
TIMECOP error (can be valgrind bug)
error 132
Process terminating with default action of signal 4 (SIGILL)
Illegal opcode at address 0x10CC84
at 0x...: crypto_kem_mceliece8192128f_ref_constbranchindex_bitrev (util.c:67)
by 0x...: crypto_kem_mceliece8192128f_ref_constbranchindex_pk_gen (pk_gen.c:145)
by 0x...: crypto_kem_mceliece8192128f_ref_constbranchindex_operation_keypair (kem_keypair.c:74)
by 0x...: crypto_kem_mceliece8192128f_ref_constbranchindex_keypair (wrap_keypair.c:10)
by 0x...: test (try.c:126)
by 0x...: main (try-anything.c:345)
Illegal instruction
Number of similar (implementation,compiler) pairs: 1, namely:
| Implementation | Compiler |
| ref | clang -march=native -O2 -fwrapv -Qunused-arguments -fPIC -fPIE -gdwarf-4 -Wall (Debian_Clang_19.1.7_(3+b1)) |
TIMECOP error (can be valgrind bug)
error 132
Process terminating with default action of signal 4 (SIGILL)
Illegal opcode at address 0x10D404
at 0x...: crypto_kem_mceliece8192128f_ref_constbranchindex_bitrev (util.c:67)
by 0x...: crypto_kem_mceliece8192128f_ref_constbranchindex_pk_gen (pk_gen.c:145)
by 0x...: crypto_kem_mceliece8192128f_ref_constbranchindex_operation_keypair (kem_keypair.c:74)
by 0x...: crypto_kem_mceliece8192128f_ref_constbranchindex_keypair (wrap_keypair.c:10)
by 0x...: test (try.c:126)
by 0x...: main (try-anything.c:345)
Illegal instruction
Number of similar (implementation,compiler) pairs: 1, namely:
| Implementation | Compiler |
| ref | clang -march=native -O3 -fwrapv -Qunused-arguments -fPIC -fPIE -gdwarf-4 -Wall (Debian_Clang_19.1.7_(3+b1)) |
TIMECOP error (can be valgrind bug)
error 132
Process terminating with default action of signal 4 (SIGILL)
Illegal opcode at address 0x10BA24
at 0x...: crypto_kem_mceliece8192128f_ref_constbranchindex_bitrev (util.c:67)
by 0x...: crypto_kem_mceliece8192128f_ref_constbranchindex_pk_gen (pk_gen.c:145)
by 0x...: crypto_kem_mceliece8192128f_ref_constbranchindex_operation_keypair (kem_keypair.c:74)
by 0x...: crypto_kem_mceliece8192128f_ref_constbranchindex_keypair (wrap_keypair.c:10)
by 0x...: test (try.c:126)
by 0x...: main (try-anything.c:345)
Illegal instruction
Number of similar (implementation,compiler) pairs: 1, namely:
| Implementation | Compiler |
| ref | clang -march=native -O -fwrapv -Qunused-arguments -fPIC -fPIE -gdwarf-4 -Wall (Debian_Clang_19.1.7_(3+b1)) |
TIMECOP error (can be valgrind bug)
error 132
Process terminating with default action of signal 4 (SIGILL)
Illegal opcode at address 0x10B9A9
at 0x...: crypto_kem_mceliece8192128f_ref_constbranchindex_bitrev (util.c:67)
by 0x...: crypto_kem_mceliece8192128f_ref_constbranchindex_pk_gen (pk_gen.c:145)
by 0x...: crypto_kem_mceliece8192128f_ref_constbranchindex_operation_keypair (kem_keypair.c:74)
by 0x...: crypto_kem_mceliece8192128f_ref_constbranchindex_keypair (wrap_keypair.c:10)
by 0x...: test (try.c:126)
by 0x...: main (try-anything.c:345)
Illegal instruction
Number of similar (implementation,compiler) pairs: 1, namely:
| Implementation | Compiler |
| ref | clang -march=native -Os -fwrapv -Qunused-arguments -fPIC -fPIE -gdwarf-4 -Wall (Debian_Clang_19.1.7_(3+b1)) |
TIMECOP error (can be valgrind bug)
error 132
Process terminating with default action of signal 4 (SIGILL)
Illegal opcode at address 0x115AB8
at 0x...: weight (decrypt.c:88)
by 0x...: crypto_kem_mceliece8192128f_sse_constbranchindex_decrypt (decrypt.c:160)
by 0x...: crypto_kem_mceliece8192128f_sse_constbranchindex_operation_dec (kem_dec.c:38)
by 0x...: test (try.c:160)
by 0x...: main (try-anything.c:345)
Illegal instruction
Number of similar (implementation,compiler) pairs: 1, namely:
| Implementation | Compiler |
| sse | clang -march=native -O2 -fwrapv -Qunused-arguments -fPIC -fPIE -gdwarf-4 -Wall (Debian_Clang_19.1.7_(3+b1)) |
TIMECOP error (can be valgrind bug)
error 132
Process terminating with default action of signal 4 (SIGILL)
Illegal opcode at address 0x117478
at 0x...: weight (decrypt.c:88)
by 0x...: crypto_kem_mceliece8192128f_sse_constbranchindex_decrypt (decrypt.c:160)
by 0x...: crypto_kem_mceliece8192128f_sse_constbranchindex_operation_dec (kem_dec.c:38)
by 0x...: test (try.c:160)
by 0x...: main (try-anything.c:345)
Illegal instruction
Number of similar (implementation,compiler) pairs: 1, namely:
| Implementation | Compiler |
| sse | clang -march=native -O3 -fwrapv -Qunused-arguments -fPIC -fPIE -gdwarf-4 -Wall (Debian_Clang_19.1.7_(3+b1)) |
TIMECOP error (can be valgrind bug)
error 132
Process terminating with default action of signal 4 (SIGILL)
Illegal opcode at address 0x1109CA
at 0x...: weight (decrypt.c:88)
by 0x...: crypto_kem_mceliece8192128f_sse_constbranchindex_decrypt (decrypt.c:160)
by 0x...: crypto_kem_mceliece8192128f_sse_constbranchindex_operation_dec (kem_dec.c:38)
by 0x...: test (try.c:160)
by 0x...: main (try-anything.c:345)
Illegal instruction
Number of similar (implementation,compiler) pairs: 1, namely:
| Implementation | Compiler |
| sse | clang -march=native -Os -fwrapv -Qunused-arguments -fPIC -fPIE -gdwarf-4 -Wall (Debian_Clang_19.1.7_(3+b1)) |
TIMECOP error (can be valgrind bug)
error 132
Process terminating with default action of signal 4 (SIGILL)
Illegal opcode at address 0x10ABEF
at 0x...: main (try-anything.c:369)
Illegal instruction
Number of similar (implementation,compiler) pairs: 1, namely:
| Implementation | Compiler |
| vec | clang -march=native -O2 -fwrapv -Qunused-arguments -fPIC -fPIE -gdwarf-4 -Wall (Debian_Clang_19.1.7_(3+b1)) |
TIMECOP error (can be valgrind bug)
error 132
Process terminating with default action of signal 4 (SIGILL)
Illegal opcode at address 0x10ABFF
at 0x...: main (try-anything.c:369)
Illegal instruction
Number of similar (implementation,compiler) pairs: 1, namely:
| Implementation | Compiler |
| vec | clang -march=native -O3 -fwrapv -Qunused-arguments -fPIC -fPIE -gdwarf-4 -Wall (Debian_Clang_19.1.7_(3+b1)) |
TIMECOP error (can be valgrind bug)
error 132
Process terminating with default action of signal 4 (SIGILL)
Illegal opcode at address 0x10A4B5
at 0x...: main (try-anything.c:369)
Illegal instruction
Number of similar (implementation,compiler) pairs: 1, namely:
| Implementation | Compiler |
| vec | clang -march=native -Os -fwrapv -Qunused-arguments -fPIC -fPIE -gdwarf-4 -Wall (Debian_Clang_19.1.7_(3+b1)) |
Passed TIMECOP
TIMECOP iterations: 1
Number of similar (implementation,compiler) pairs: 21, namely:
| Implementation | Compiler |
| avx | clang -march=native -O -fwrapv -Qunused-arguments -fPIC -fPIE -gdwarf-4 -Wall (Debian_Clang_19.1.7_(3+b1)) |
| avx | gcc -march=native -mtune=native -O2 -fwrapv -fPIC -fPIE -gdwarf-4 -Wall (14.2.0) |
| avx | gcc -march=native -mtune=native -O3 -fwrapv -fPIC -fPIE -gdwarf-4 -Wall (14.2.0) |
| avx | gcc -march=native -mtune=native -O -fwrapv -fPIC -fPIE -gdwarf-4 -Wall (14.2.0) |
| avx | gcc -march=native -mtune=native -Os -fwrapv -fPIC -fPIE -gdwarf-4 -Wall (14.2.0) |
| ref | clang -mcpu=native -O3 -fwrapv -Qunused-arguments -fPIC -fPIE -gdwarf-4 -Wall (Debian_Clang_19.1.7_(3+b1)) |
| ref | gcc -march=native -mtune=native -O2 -fwrapv -fPIC -fPIE -gdwarf-4 -Wall (14.2.0) |
| ref | gcc -march=native -mtune=native -O3 -fwrapv -fPIC -fPIE -gdwarf-4 -Wall (14.2.0) |
| ref | gcc -march=native -mtune=native -O -fwrapv -fPIC -fPIE -gdwarf-4 -Wall (14.2.0) |
| ref | gcc -march=native -mtune=native -Os -fwrapv -fPIC -fPIE -gdwarf-4 -Wall (14.2.0) |
| sse | clang -march=native -O -fwrapv -Qunused-arguments -fPIC -fPIE -gdwarf-4 -Wall (Debian_Clang_19.1.7_(3+b1)) |
| sse | gcc -march=native -mtune=native -O2 -fwrapv -fPIC -fPIE -gdwarf-4 -Wall (14.2.0) |
| sse | gcc -march=native -mtune=native -O3 -fwrapv -fPIC -fPIE -gdwarf-4 -Wall (14.2.0) |
| sse | gcc -march=native -mtune=native -O -fwrapv -fPIC -fPIE -gdwarf-4 -Wall (14.2.0) |
| sse | gcc -march=native -mtune=native -Os -fwrapv -fPIC -fPIE -gdwarf-4 -Wall (14.2.0) |
| vec | clang -march=native -O -fwrapv -Qunused-arguments -fPIC -fPIE -gdwarf-4 -Wall (Debian_Clang_19.1.7_(3+b1)) |
| vec | clang -mcpu=native -O3 -fwrapv -Qunused-arguments -fPIC -fPIE -gdwarf-4 -Wall (Debian_Clang_19.1.7_(3+b1)) |
| vec | gcc -march=native -mtune=native -O2 -fwrapv -fPIC -fPIE -gdwarf-4 -Wall (14.2.0) |
| vec | gcc -march=native -mtune=native -O3 -fwrapv -fPIC -fPIE -gdwarf-4 -Wall (14.2.0) |
| vec | gcc -march=native -mtune=native -O -fwrapv -fPIC -fPIE -gdwarf-4 -Wall (14.2.0) |
| vec | gcc -march=native -mtune=native -Os -fwrapv -fPIC -fPIE -gdwarf-4 -Wall (14.2.0) |