superblock: Define predefined enums

10 files changed, 864 insertions, 49 deletions

diff --git a/include/fs/detail/superblock.hpp b/include/fs/detail/superblock.hpp
index dbacd48..3a23869 100644
--- a/include/fs/detail/superblock.hpp
+++ b/include/fs/detail/superblock.hpp
@@ -5,6 +5,8 @@
 
 #include <array>
 #include <cstdint>
+#include <initializer_list>
+#include <type_traits>
 
 namespace fs::detail
   {
@@ -16,54 +18,310 @@ namespace fs::detail
    */
   struct superblock
     {
-    u32 const inodes_count{}; ///< The total number of inodes in the file system
-    u32 const blocks_count{}; ///< The total number of blocks in the file system
-    u32 const reserved_blocks_count{}; ///< The number of blocks reserved for the super user
-    u32 const free_blocks_count{}; ///< The number of free blocks in the file system
-    u32 const free_inodes_count{}; ///< The mumber of free inodes in the file system
-    u32 const first_data_block_id{}; ///< The first block that carries user data in the file system
-    u32 const logical_block_size{}; ///< The logical size of a block (1024 << logical_block_size)
-    s32 const logical_fragment_size{}; ///< The logical size of a block (1024 << logical_fragment_size)
-    u32 const blocks_per_group{}; ///< The number of blocks per block group
-    u32 const fragments_per_group{}; ///< The number of fragments per block group
-    u32 const inodes_per_group{}; ///< The number of inodes per block group
-    u32 const last_mount_timestamp{}; ///< The unix timestamp when the file system was last mounted
-    u32 const last_write_timestamp{}; ///< The unix timestamp of the last write operation to the file system
-    u16 const mount_count{}; ///< The number of times the file system was mounted since the last check
-    u16 const maximum_mount_count{}; ///< The maximum number of times the file system can be mounted until a full check
-    u16 const magic_number{}; ///< The magic number identifying the file system type
-    s16 const state{}; ///< The state of the file system
-    s16 const error_behaviour{}; ///< The desired behaviour if a file system error occurs
-    s16 const revision_level_minor{}; ///< The minor revision level of the file system
-    u32 const last_check_timestamp{}; ///< The unix timestamp of the last check of the file system
-    u32 const check_interval{}; ///< The unix time interval in which to check the file system
-    u32 const creator_operating_system_id{}; ///< The operation system identifier of the OS that created the file system
-    u32 const revision_level{}; ///< The revision level of the file system
-    u16 const super_user_id{}; ///< The user ID of the super user
-    u16 const super_user_group_id{}; ///< The group ID of the super user group
-    u32 const first_inode_id{}; ///< The id of the first inode usable for standard files
-    u16 const inode_size{}; ///< The size of an inode in bytes
-    u16 const superblock_group_id{}; ///< The ID of the block group hosting this superblock
-    u32 const compatible_features{}; ///< The active compatible features
-    u32 const incompatible_features{}; ///< The active incompatible feature
-    u32 const read_only_compatible_features{}; ///< The active features compatible with read-only mode
-    u08_arr<16> const uuid{}; ///< The UUID of the file system
-    chr_arr<16> const label{}; ///< The label of the file system
-    chr_arr<64> const last_mount_point{}; ///< The location the file system was last mounted on
-    u32 const compression_algorithm{}; ///< The compression algorithm used in the file system
-    u08 const file_preallocated_blocks_count{}; ///< The number of blocks to preallocate for a file
-    u08 const directory_preallocated_blocks_count{}; ///< The number of block to preallocate for a directory
-    u16 const _padding{}; ///< Alignment padding
-    u08_arr<16> const journal_superblock_uuid{}; ///< The UUID of the superblock containing the journal
-    u32 const journal_inode_id{}; ///< The ID of the inode hosting the journal
-    u32 const journal_device_number{}; ///< The device number of the journal
-    u32 const last_orphan_inode_id{}; ///< The first inode in the list of inodes to delete
-    u32_arr<4> const hash_seed{}; ///< The seed for the directory hashing algorithm
-    u08 const hash_version{}; ///< The version of the directory hashing algorithm
-    u08_arr<3> const _reserved0{}; ///< Alignment padding
-    u32 const default_mount_options{}; ///< The default mount options for the file system
-    u32 const first_meta_block_group_id{}; ///< The ID of the first meta block group
-    u08_arr<760> const _reserved1{}; ///< Padding
+    /**
+     * @brief The operating system that created the file system
+     *
+     * The "standard" utilities to create an ext2/3/4 file system record the operating system they were used on. The values of
+     * this enumeration are the "well-known" operating systems, e.g the ones most implementations should understand.
+     *
+     * @since 1.0
+     */
+    enum struct creator_operating_system : u32
+      {
+      linux = 0, ///< Linux
+      hurd = 1, ///<  HURD
+      masix = 2, ///< MASIX
+      freebsd = 3, ///< FreeBSD
+      lites = 4, ///< Lites
+      };
+
+    /**
+     * @brief The underlying type of #creator_operating_system
+     *
+     * @since 1.0
+     */
+    using cos = std::underlying_type_t<creator_operating_system>;
+
+    /**
+     * @brief The revision level of the file system
+     *
+     * ext2/3/4 currently come in two different revision levels, known as the "Good old" revision and the "Dynamic" revision.
+     * The "Good old" format uses fixed inode size and generally lacks some "modern" features, whereas the "Dynamic" format
+     * supports, among other things, dynamic inode sizes.
+     *
+     * @since 1.0
+     */
+    enum struct revision_level : u32
+      {
+      good_old = 0, ///< The first version of ext2
+      dynamic = 1, ///< The file system supports "modern" features
+      };
+
+    /**
+     * @brief The underlying type of #revision_level
+     *
+     * @since 1.0
+     */
+    using rlv = std::underlying_type_t<revision_level>;
+
+    /**
+     * @brief The compatible features of ext2/3/4
+     *
+     * ext2/3/4 define a set of so-called compatible features. Even if the implementation does not support these features, it
+     * is safe to read and write data from and to the file system. The values of this enumeration reflect the currently
+     * "well-known" features.
+     *
+     * @note The current implementation does not support any of the "compatible features".
+     * @since 1.0
+     */
+    enum struct compatible_feature : u32
+      {
+      directory_preallocation = 1, ///< Blocks for new directories can be preallocated
+      imagic_inodes = 2, ///< TODO: Find out what this does
+      has_journal = 4, ///< The file system has an ext3 journal
+      extended_attribues = 8, ///< The file system supports extended attributes
+      resize_inode = 16, ///< The file system can be resized
+      directory_indexing = 32, ///< The file system suppors directory indexing
+      lazy_block_group_initialization = 64, ///< The file system lazily initializes block groups
+      exclude_inode = 128, ///< TODO: Find out what that does
+      exclude_bitmaps = 256, ///< The file system has snapshot-related exclude bitmaps
+      sparse_superblock_v2 = 512, ///< The file system uses version 2 of the sparse superblock
+      };
+
+    /**
+     * @brief The underlying type of compatible_feature
+     *
+     * @since 1.0
+     */
+    using cft = std::underlying_type_t<compatible_feature>;
+
+    /**
+     * @brief The incompatible features of ext2/3/4
+     *
+     * ext2/3/4 define a set of so-called incompatible features. If the file system makes use of one or more of these features
+     * and the implementation does not support the features used, it must refuse to read or write from or to the file system.
+     * The values of this enumeration are the currently "well-known" features.
+     *
+     * @note The current implementation implementation does not support any of the "incompatible features".
+     * @since 1.0
+     */
+    enum struct incompatible_feature : u32
+      {
+      compression = 1, ///< The file system uses compression
+      filetype = 2, ///< Filetypes are recorded in directory entries
+      recover = 4, ///< The fFile system needs recovery
+      journal_device = 8, ///< The file system has a separate device for the journal
+      meta_block_group = 16, ///< The file system has meta block groups
+      extents = 64, ///< The file system uses extents
+      large_file_system = 128, ///< The file system supports 2^64 blocks
+      multiple_mount_protection = 256, ///< The file system must be protected against being mounted more than once at a time
+      flexible_block_groups = 512, ///< The file system uses flexible block groups
+      large_extended_attribues_in_inodes = 1024, ///< The file system stores large extended attributes in inodes
+      data_in_directories = 4096, ///< The file system stores data directly in directory entries
+      metadata_checksum_seed_in_superblock = 8192, ///< The checksum seed for metadata is stored in the superblock
+      large_directory = 16384, ///< The file system uses a large directory or 3-level hash tree
+      data_in_inode = 32768, ///< The file system stores data directly inside inodes
+      encrypted_inodes = 65536, ///< The file system uses encrypted inodes
+      };
+
+    /**
+     * @brief The underlying type of incompatible_feature
+     *
+     * @since 1.0
+     */
+    using ift = std::underlying_type_t<incompatible_feature>;
+
+    /**
+     * @brief The read-only compatible features of ext2/3/4
+     *
+     * ext2/3/4 define a set of so-called read-only compatible features. An implementation that does not support one or more of
+     * these features might still access the file system in a read-only way. The values of this enumeration are the currently
+     * "well-known" read-only compatible features.
+     *
+     * @note The current implementation implementation does not support any of the "read-only compatible features".
+     * @since 1.0
+     */
+    enum struct read_only_compatible_feature : u32
+      {
+      sparse_superblock = 1, ///< The file system has a sparse superblock
+      large_file = 2, ///< The file system supports large files
+      binary_tree_directories = 4, ///< The file system uses sorted binary trees for directories
+      huge_file = 8, ///< The file system contains files represented by the number of logical blocks (e.g. HUGE files)
+      };
+
+    /**
+     * @brief The underlying type of read_only_compatible_feature
+     *
+     * @since 1.0
+     */
+    using rft = std::underlying_type_t<read_only_compatible_feature>;
+
+    /**
+     * @brief The compression algorithms of ext2/3/4
+     *
+     * While compression in ext2 was only supported via a patch, later iterations added the compression feature as a "core"
+     * component of the file system. The values of this enumeration are the currently "well-known" compression algorithms
+     * found in ext2/3/4.
+     *
+     * @note The current implementation implementation does not support any of these algorithms.
+     * @note A file system might be using multiple compression algorithms at a time.
+     * @since 1.0
+     */
+    enum struct compression_algorithm : u32
+      {
+      lempel_ziv = 1, ///< Lempel-Ziv compression
+      lempel_ziv_ross_williams_3a = 2, ///< Lempel-Ziv Ross-Williams 3A compression
+      gzip = 4, ///< GZIP compression
+      bzip2 = 8, ///< BZIP2 compression
+      lempel_ziv_oberhumer = 16, ///< Lempel-Ziv-Oberhumer compression
+      };
+
+    /**
+     * @brief The underlying type of compression_algorithms
+     *
+     * @since 1.0
+     */
+    using cpr = std::underlying_type_t<compression_algorithm>;
+
+    u32 inodes_count{}; ///< The total number of inodes in the file system
+    u32 blocks_count{}; ///< The total number of blocks in the file system
+    u32 reserved_blocks_count{}; ///< The number of blocks reserved for the super user
+    u32 free_blocks_count{}; ///< The number of free blocks in the file system
+    u32 free_inodes_count{}; ///< The mumber of free inodes in the file system
+    u32 first_data_block_id{}; ///< The first block that carries user data in the file system
+    u32 logical_block_size{}; ///< The logical size of a block (1024 << logical_block_size)
+    s32 logical_fragment_size{}; ///< The logical size of a block (1024 << logical_fragment_size)
+    u32 blocks_per_group{}; ///< The number of blocks per block group
+    u32 fragments_per_group{}; ///< The number of fragments per block group
+    u32 inodes_per_group{}; ///< The number of inodes per block group
+    u32 last_mount_timestamp{}; ///< The unix timestamp when the file system was last mounted
+    u32 last_write_timestamp{}; ///< The unix timestamp of the last write operation to the file system
+    u16 mount_count{}; ///< The number of times the file system was mounted since the last check
+    u16 maximum_mount_count{}; ///< The maximum number of times the file system can be mounted until a full check
+    u16 magic_number{}; ///< The magic number identifying the file system type
+    s16 state{}; ///< The state of the file system
+    s16 error_behaviour{}; ///< The desired behaviour if a file system error occurs
+    s16 revision_level_minor{}; ///< The minor revision level of the file system
+    u32 last_check_timestamp{}; ///< The unix timestamp of the last check of the file system
+    u32 check_interval{}; ///< The unix time interval in which to check the file system
+    cos creator_operating_system_id{}; ///< The operation system identifier of the OS that created the file system
+    rlv revision_level{}; ///< The revision level of the file system
+    u16 super_user_id{}; ///< The user ID of the super user
+    u16 super_user_group_id{}; ///< The group ID of the super user group
+    u32 first_inode_id{}; ///< The id of the first inode usable for standard files
+    u16 inode_size{}; ///< The size of an inode in bytes
+    u16 superblock_group_id{}; ///< The ID of the block group hosting this superblock
+    cft compatible_features_bitmap{}; ///< The active compatible features
+    ift incompatible_features_bitmap{}; ///< The active incompatible feature
+    rft read_only_compatible_features_bitmap{}; ///< The active features compatible with read-only mode
+    u08_arr<16> uuid{}; ///< The UUID of the file system
+    chr_arr<16> label{}; ///< The label of the file system
+    chr_arr<64> last_mount_point{}; ///< The location the file system was last mounted on
+    cpr compression_algorithms_bitmap{}; ///< The compression algorithms used in the file system
+    u08 file_preallocated_blocks_count{}; ///< The number of blocks to preallocate for a file
+    u08 directory_preallocated_blocks_count{}; ///< The number of block to preallocate for a directory
+    u16 _padding{}; ///< Alignment padding
+    u08_arr<16> journal_superblock_uuid{}; ///< The UUID of the superblock containing the journal
+    u32 journal_inode_id{}; ///< The ID of the inode hosting the journal
+    u32 journal_device_number{}; ///< The device number of the journal
+    u32 last_orphan_inode_id{}; ///< The first inode in the list of inodes to delete
+    u32_arr<4> hash_seed{}; ///< The seed for the directory hashing algorithm
+    u08 hash_version{}; ///< The version of the directory hashing algorithm
+    u08_arr<3> _reserved0{}; ///< Alignment padding
+    u32 default_mount_options{}; ///< The default mount options for the file system
+    u32 first_meta_block_group_id{}; ///< The ID of the first meta block group
+    u08_arr<760> _reserved1{}; ///< Padding
+
+    /**
+     * @brief Check if the file system has the desired "compatible feature"
+     *
+     * @param feature The #compatible_feature to check for
+     * @return @p true iff. the file system has the feature, @p false otherwise
+     * @see #compatible_feature
+     * @since 1.0
+     */
+    bool has(compatible_feature const feature) const;
+
+    /**
+     * @brief Check if the file system has all of the desired "compatible features"
+     *
+     * @param features The @link compatible_feature compatible_features to check for
+     * @return @p true iff. the file system has @a all features that were querried, @p false otherwise
+     * @see #compatible_feature
+     * @since 1.0
+     */
+    bool has_all(std::initializer_list<compatible_feature> const features) const;
+
+    /**
+     * @brief Check if the file system has at least one of the desired "compatible features"
+     *
+     * @param features The @link compatible_feature compatible_features to check for
+     * @return @p true iff. the file system has @a at least one of the features that were querried, @p false otherwise
+     * @see #compatible_feature
+     * @since 1.0
+     */
+    bool has_any(std::initializer_list<compatible_feature> const features) const;
+
+    /**
+     * @brief Check if the file system has the desired "incompatible feature"
+     *
+     * @param feature The #incompatible_feature to check for.
+     * @return @p true iff. the file system has the feature
+     * @see #incompatible_feature
+     * @since 1.0
+     */
+    bool has(incompatible_feature const feature) const;
+
+    /**
+     * @brief Check if the file system has all of the desired "incompatible features"
+     *
+     * @param features The @link incompatible_feature incompatible_features to check for
+     * @return @p true iff. the file system has @a all features that were querried, @p false otherwise
+     * @see #compatible_feature
+     * @since 1.0
+     */
+    bool has_all(std::initializer_list<incompatible_feature> const features) const;
+
+    /**
+     * @brief Check if the file system has at least one of the desired "incompatible features"
+     *
+     * @param features The @link incompatible_feature incompatible_features to check for
+     * @return @p true iff. the file system has @a at least one of the features that were querried, @p false otherwise
+     * @see #compatible_feature
+     * @since 1.0
+     */
+    bool has_any(std::initializer_list<incompatible_feature> const features) const;
+
+    /**
+     * @brief Check if the file system has the desired "read-only compatible feature"
+     *
+     * @param feature The #read_only_compatible_feature to check for
+     * @return @p true iff. the file system has the feature, @p false otherwise
+     * @see #compatible_feature
+     * @since 1.0
+     */
+    bool has(read_only_compatible_feature const feature) const;
+
+    /**
+     * @brief Check if the file system has all of the desired "read-only compatible features"
+     *
+     * @param features The @link read_only_compatible_feature read_only_compatible_features to check for
+     * @return @p true iff. the file system has @a all features that were querried, @p false otherwise
+     * @see #compatible_feature
+     * @since 1.0
+     */
+    bool has_all(std::initializer_list<read_only_compatible_feature> const features) const;
+
+    /**
+     * @brief Check if the file system has at least one of the desired "read-only compatible features"
+     *
+     * @param features The @link read_only_compatible_feature read_only_compatible_features to check for
+     * @return @p true iff. the file system has @a at least one of the features that were querried, @p false otherwise
+     * @see #compatible_feature
+     * @since 1.0
+     */
+    bool has_any(std::initializer_list<read_only_compatible_feature> const features) const;
+
     };
 
   static_assert(sizeof(superblock) == 1024, "An ext2/3/4 super block must have an exact size of 1024 bytes!");
diff --git a/include/test/superblock/ext2-filetype.hpp b/include/test/superblock/ext2-filetype.hpp
new file mode 100644
index 0000000..c4fce50
--- /dev/null
+++ b/include/test/superblock/ext2-filetype.hpp
@@ -0,0 +1,74 @@
+#ifndef EXT2_FILETYPE_ARRDMP
+#define EXT2_FILETYPE_ARRDMP
+#include<array>
+#include<cstdint>
+
+// generated from ext2-filetype
+std::array<std::uint8_t, 1024> const ext2_filetype = {{
+  0x80, 0x00, 0x00, 0x00, 0x00, 0x04, 0x00, 0x00, 0x33, 0x00, 0x00, 0x00, 0xde, 0x03, 0x00, 0x00,
+  0x75, 0x00, 0x00, 0x00, 0x01, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x20, 0x00, 0x00, 0x00, 0x20, 0x00, 0x00, 0x80, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x64, 0x50, 0x65, 0x58, 0x00, 0x00, 0xff, 0xff, 0x53, 0xef, 0x01, 0x00, 0x01, 0x00, 0x00, 0x00,
+  0x64, 0x50, 0x65, 0x58, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x01, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x0b, 0x00, 0x00, 0x00, 0x80, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x02, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x41, 0x8c, 0x29, 0xd4, 0x96, 0xf1, 0x44, 0x4c,
+  0xab, 0x3e, 0x81, 0x5f, 0x10, 0xf0, 0x99, 0x36, 0x65, 0x78, 0x74, 0x32, 0x66, 0x74, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0xa7, 0xbc, 0x76, 0xb6,
+  0xde, 0x41, 0x4e, 0x46, 0xb8, 0x6e, 0xf0, 0x12, 0xbb, 0x6c, 0x3f, 0x60, 0x01, 0x00, 0x00, 0x00,
+  0x0c, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x64, 0x50, 0x65, 0x58, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x01, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+}};
+
+#endif
\ No newline at end of file
diff --git a/include/test/superblock/ext2-large_file.hpp b/include/test/superblock/ext2-large_file.hpp
new file mode 100644
index 0000000..0e6ded8
--- /dev/null
+++ b/include/test/superblock/ext2-large_file.hpp
@@ -0,0 +1,74 @@
+#ifndef EXT2_LARGE_FILE_ARRDMP
+#define EXT2_LARGE_FILE_ARRDMP
+#include<array>
+#include<cstdint>
+
+// generated from ext2-large_file
+std::array<std::uint8_t, 1024> const ext2_large_file = {{
+  0x80, 0x00, 0x00, 0x00, 0x00, 0x04, 0x00, 0x00, 0x33, 0x00, 0x00, 0x00, 0xde, 0x03, 0x00, 0x00,
+  0x75, 0x00, 0x00, 0x00, 0x01, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x20, 0x00, 0x00, 0x00, 0x20, 0x00, 0x00, 0x80, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0xc0, 0x50, 0x65, 0x58, 0x00, 0x00, 0xff, 0xff, 0x53, 0xef, 0x01, 0x00, 0x01, 0x00, 0x00, 0x00,
+  0xc0, 0x50, 0x65, 0x58, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x01, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x0b, 0x00, 0x00, 0x00, 0x80, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x02, 0x00, 0x00, 0x00, 0xd3, 0x67, 0xd0, 0xe6, 0x43, 0xe4, 0x46, 0x9a,
+  0x9e, 0x25, 0xc6, 0xd6, 0x59, 0xde, 0xf0, 0x93, 0x65, 0x78, 0x74, 0x32, 0x6c, 0x66, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x35, 0x22, 0xb7, 0xb6,
+  0xed, 0x53, 0x4a, 0x83, 0xb7, 0xb7, 0x0d, 0xec, 0xa7, 0x90, 0xf6, 0x0c, 0x01, 0x00, 0x00, 0x00,
+  0x0c, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0xc0, 0x50, 0x65, 0x58, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x01, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+}};
+
+#endif
\ No newline at end of file
diff --git a/include/test/superblock/ext2-noopts.hpp b/include/test/superblock/ext2-noopts.hpp
new file mode 100644
index 0000000..6344b59
--- /dev/null
+++ b/include/test/superblock/ext2-noopts.hpp
@@ -0,0 +1,74 @@
+#ifndef EXT2_NOOPTS_ARRDMP
+#define EXT2_NOOPTS_ARRDMP
+#include<array>
+#include<cstdint>
+
+// generated from ext2-noopts
+std::array<std::uint8_t, 1024> const ext2_noopts = {{
+  0x80, 0x00, 0x00, 0x00, 0x00, 0x04, 0x00, 0x00, 0x33, 0x00, 0x00, 0x00, 0xde, 0x03, 0x00, 0x00,
+  0x75, 0x00, 0x00, 0x00, 0x01, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x20, 0x00, 0x00, 0x00, 0x20, 0x00, 0x00, 0x80, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x12, 0x50, 0x65, 0x58, 0x00, 0x00, 0xff, 0xff, 0x53, 0xef, 0x01, 0x00, 0x01, 0x00, 0x00, 0x00,
+  0x12, 0x50, 0x65, 0x58, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x01, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x0b, 0x00, 0x00, 0x00, 0x80, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0xf6, 0xfb, 0xdd, 0xe3, 0x42, 0x48, 0x4d, 0x0b,
+  0x81, 0x72, 0x60, 0x58, 0xd5, 0x62, 0x9a, 0x00, 0x65, 0x78, 0x74, 0x32, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x12, 0xbf, 0x60, 0xee,
+  0xd6, 0x37, 0x48, 0xbe, 0xb7, 0xc0, 0x5e, 0x51, 0x23, 0xd1, 0x6b, 0x75, 0x01, 0x00, 0x00, 0x00,
+  0x0c, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x12, 0x50, 0x65, 0x58, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x01, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+  0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00, 0x00,
+}};
+
+#endif
\ No newline at end of file
diff --git a/src/fs/CMakeLists.txt b/src/fs/CMakeLists.txt
index 3ca33b8..4e2d1d6 100644
--- a/src/fs/CMakeLists.txt
+++ b/src/fs/CMakeLists.txt
@@ -6,5 +6,6 @@ endif()
 
 add_library(extfs
   ${LIBRARY_TYPE}
-  extfs.cpp
+  "extfs.cpp"
+  "detail/superblock.cpp"
   )
diff --git a/src/fs/detail/superblock.cpp b/src/fs/detail/superblock.cpp
new file mode 100644
index 0000000..f238098
--- /dev/null
+++ b/src/fs/detail/superblock.cpp
@@ -0,0 +1,65 @@
+#include "fs/detail/superblock.hpp"
+
+#include <algorithm>
+
+namespace fs::detail
+  {
+
+  bool superblock::has(superblock::compatible_feature const feature) const
+    {
+    return compatible_features_bitmap & static_cast<decltype(compatible_features_bitmap)>(feature);
+    }
+
+  bool superblock::has_all(std::initializer_list<superblock::compatible_feature> const features) const
+    {
+    return std::all_of(features.begin(), features.end(), [&](auto const feature){
+      return compatible_features_bitmap & static_cast<decltype(compatible_features_bitmap)>(feature);
+    });
+    }
+
+  bool superblock::has_any(std::initializer_list<superblock::compatible_feature> const features) const
+    {
+    return std::any_of(features.begin(), features.end(), [&](auto const feature){
+      return compatible_features_bitmap & static_cast<decltype(compatible_features_bitmap)>(feature);
+    });
+    }
+
+  bool superblock::has(superblock::incompatible_feature const feature) const
+    {
+    return incompatible_features_bitmap & static_cast<decltype(incompatible_features_bitmap)>(feature);
+    }
+
+  bool superblock::has_all(std::initializer_list<superblock::incompatible_feature> const features) const
+    {
+    return std::all_of(features.begin(), features.end(), [&](auto const feature){
+      return incompatible_features_bitmap & static_cast<decltype(incompatible_features_bitmap)>(feature);
+    });
+    }
+
+  bool superblock::has_any(std::initializer_list<superblock::incompatible_feature> const features) const
+    {
+    return std::any_of(features.begin(), features.end(), [&](auto const feature){
+      return incompatible_features_bitmap & static_cast<decltype(incompatible_features_bitmap)>(feature);
+    });
+    }
+
+  bool superblock::has(superblock::read_only_compatible_feature const feature) const
+    {
+    return read_only_compatible_features_bitmap & static_cast<decltype(read_only_compatible_features_bitmap)>(feature);
+    }
+
+  bool superblock::has_all(std::initializer_list<superblock::read_only_compatible_feature> const features) const
+    {
+    return std::all_of(features.begin(), features.end(), [&](auto const feature){
+      return read_only_compatible_features_bitmap & static_cast<decltype(read_only_compatible_features_bitmap)>(feature);
+    });
+    }
+
+  bool superblock::has_any(std::initializer_list<superblock::read_only_compatible_feature> const features) const
+    {
+    return std::any_of(features.begin(), features.end(), [&](auto const feature){
+      return read_only_compatible_features_bitmap & static_cast<decltype(read_only_compatible_features_bitmap)>(feature);
+    });
+    }
+
+  }
diff --git a/test/fs/CMakeLists.txt b/test/fs/CMakeLists.txt
index e98e9bb..b2f1fcf 100644
--- a/test/fs/CMakeLists.txt
+++ b/test/fs/CMakeLists.txt
@@ -24,3 +24,5 @@ execute_process(
   )
 
 cute_test(extfs LIBRARIES extfs stdc++fs)
+
+add_subdirectory("detail")
diff --git a/test/fs/detail/CMakeLists.txt b/test/fs/detail/CMakeLists.txt
new file mode 100644
index 0000000..ed29a2c
--- /dev/null
+++ b/test/fs/detail/CMakeLists.txt
@@ -0,0 +1,2 @@
+set(CUTE_GROUP "detail")
+cute_test(superblock DEPENDENCIES ${PROJECT_SOURCE_DIR}/src/fs/detail/superblock.cpp)
diff --git a/test/fs/detail/superblock_test.cpp b/test/fs/detail/superblock_test.cpp
new file mode 100644
index 0000000..fe88ccb
--- /dev/null
+++ b/test/fs/detail/superblock_test.cpp
@@ -0,0 +1,140 @@
+#include "fs/extfs.hpp"
+
+#include "test/superblock/ext2-filetype.hpp"
+#include "test/superblock/ext2-large_file.hpp"
+#include "test/superblock/ext2-noopts.hpp"
+
+#include <cute/cute.h>
+#include <cute/cute_runner.h>
+#include <cute/ostream_listener.h>
+#include <cute/xml_listener.h>
+
+#include <cstring>
+
+using cft = fs::detail::superblock::compatible_feature;
+using ift = fs::detail::superblock::incompatible_feature;
+using rft = fs::detail::superblock::read_only_compatible_feature;
+
+auto superblock_from_bytes(std::array<std::uint8_t, 1024> const & data)
+  {
+  auto block = fs::detail::superblock{};
+  std::memcpy(reinterpret_cast<char *>(&block), data.data(), data.size());
+  return block;
+  }
+
+void default_initialized_superblock_should_have_no_compatible_features()
+  {
+  ASSERT(!fs::detail::superblock{}.has_any({
+      cft::directory_preallocation,
+      cft::imagic_inodes,
+      cft::has_journal,
+      cft::extended_attribues,
+      cft::resize_inode,
+      cft::directory_indexing,
+      cft::lazy_block_group_initialization,
+      cft::exclude_inode,
+      cft::exclude_bitmaps,
+      cft::sparse_superblock_v2,
+      }));
+  }
+
+void default_initialized_superblock_should_have_no_incompatible_features()
+  {
+  ASSERT(!fs::detail::superblock{}.has_any({
+      ift::compression,
+      ift::filetype,
+      ift::recover,
+      ift::journal_device,
+      ift::meta_block_group,
+      ift::extents,
+      ift::large_file_system,
+      ift::multiple_mount_protection,
+      ift::flexible_block_groups,
+      ift::large_extended_attribues_in_inodes,
+      ift::data_in_directories,
+      ift::metadata_checksum_seed_in_superblock,
+      ift::large_directory,
+      ift::data_in_inode,
+      ift::encrypted_inodes,
+      }));
+  }
+
+void default_initialized_superblock_should_have_no_read_only_compatible_features()
+  {
+  ASSERT(!fs::detail::superblock{}.has_any({
+      rft::sparse_superblock,
+      rft::large_file,
+      rft::binary_tree_directories,
+      rft::huge_file,
+      }));
+  }
+
+void noopts_superblock_should_have_no_opts()
+  {
+  auto block = superblock_from_bytes(ext2_noopts);
+  ASSERT(!block.has_any({
+      cft::directory_preallocation,
+      cft::imagic_inodes,
+      cft::has_journal,
+      cft::extended_attribues,
+      cft::resize_inode,
+      cft::directory_indexing,
+      cft::lazy_block_group_initialization,
+      cft::exclude_inode,
+      cft::exclude_bitmaps,
+      cft::sparse_superblock_v2,
+      }));
+
+  ASSERT(!block.has_any({
+      ift::compression,
+      ift::filetype,
+      ift::recover,
+      ift::journal_device,
+      ift::meta_block_group,
+      ift::extents,
+      ift::large_file_system,
+      ift::multiple_mount_protection,
+      ift::flexible_block_groups,
+      ift::large_extended_attribues_in_inodes,
+      ift::data_in_directories,
+      ift::metadata_checksum_seed_in_superblock,
+      ift::large_directory,
+      ift::data_in_inode,
+      ift::encrypted_inodes,
+      }));
+
+  ASSERT(!block.has_any({
+      rft::sparse_superblock,
+      rft::large_file,
+      rft::binary_tree_directories,
+      rft::huge_file,
+      }));
+  }
+
+void filetype_superblock_should_have_filetype_option()
+  {
+  auto block = superblock_from_bytes(ext2_filetype);
+  ASSERT(block.has(ift::filetype));
+  }
+
+void large_file_superblock_should_have_large_file_option()
+  {
+  auto block = superblock_from_bytes(ext2_large_file);
+  ASSERT(block.has(rft::large_file));
+  }
+
+int main(int argc, char * argv[])
+  {
+  auto tests = cute::suite{
+    CUTE(default_initialized_superblock_should_have_no_compatible_features),
+    CUTE(default_initialized_superblock_should_have_no_incompatible_features),
+    CUTE(default_initialized_superblock_should_have_no_read_only_compatible_features),
+    CUTE(noopts_superblock_should_have_no_opts),
+    CUTE(filetype_superblock_should_have_filetype_option),
+    CUTE(large_file_superblock_should_have_large_file_option),
+  };
+
+  cute::xml_file_opener resultFile{argc, argv};
+  cute::xml_listener<cute::ostream_listener<>> listener{resultFile.out};
+  return !cute::makeRunner(listener, argc, argv)(tests, "fs::detail::superblock");
+  }
diff --git a/tools/arraydump b/tools/arraydump
new file mode 100755
index 0000000..fb155e0
--- /dev/null
+++ b/tools/arraydump
@@ -0,0 +1,125 @@
+#!/usr/bin/env python3
+
+import argparse
+import os
+import pprint
+import re
+import sys
+
+from enum import Enum
+
+
+class Type(Enum):
+    INT8 = {
+        'alias': 'int8',
+        'type': 'std::int8_t',
+    }
+    UINT8 = {
+        'alias': 'uint8',
+        'type': 'std::uint8_t',
+    }
+    CHAR = {
+        'alias': 'char',
+        'type': 'char',
+    }
+    SCHAR = {
+        'alias': 'schar',
+        'type': 'signed char',
+    }
+    UCHAR = {
+        'alias': 'uchar',
+        'type': 'unsigned char',
+    }
+
+    @classmethod
+    def fromstring(cls, str):
+        return getattr(cls, str.upper(), None)
+
+
+"""The settings of the header generator"""
+configuration = {
+    'inputFiles': [],
+    'outputDirectory': '.',
+    'columns': 16,
+    'filetype': 'hpp',
+    'elementType': Type.UINT8,
+}
+
+"""The arguments supported by arraydump"""
+argp = argparse.ArgumentParser(
+    prog='arraydump',
+    description='Convert binaries to C++ headers'
+)
+argp.add_argument('input', metavar='file', type=str, nargs='+',
+                  help='The input file to process')
+argp.add_argument('--output', metavar='dir', type=str,
+                  default=configuration['outputDirectory'],
+                  help='The target directory for the generated file(s)')
+argp.add_argument('--columns', metavar='cols', type=int,
+                  default=configuration['columns'],
+                  help='The number of columns in the output')
+argp.add_argument('--extension', metavar='ext', type=str,
+                  default=configuration['filetype'],
+                  help='The file extension for the generated header')
+argp.add_argument('--type', type=str, default=Type.UINT8.value['alias'],
+                  choices=[x.value['alias'] for x in list(Type)],
+                  help='The array element type')
+
+
+def generate_array(file):
+    size = os.path.getsize(file)
+    name = os.path.basename(file)
+    cols = configuration['columns']
+    cppid = re.sub('[^a-zA-Z_0-9]', '_', name)
+
+    buffer = '#ifndef %s_ARRDMP\n' % cppid.upper()
+    buffer += '#define %s_ARRDMP\n' % cppid.upper()
+    buffer += '#include<array>\n'
+    if not configuration['elementType'] in [Type.CHAR, Type.SCHAR, Type.UCHAR]:
+        buffer += '#include<cstdint>\n'
+
+    with open(file, 'rb') as handle:
+        buffer += '\n// generated from %s\n' % name
+        buffer += 'std::array<%s, %s> const %s = {{' % (
+            configuration['elementType'].value['type'],
+            size,
+            cppid
+        )
+        count = 0
+        byte = handle.read(1)
+        while byte != b'':
+            if count % cols == 0:
+                buffer += '\n  '
+
+            buffer += '0x%02x,' % int.from_bytes(byte, byteorder='little')
+
+            if count % cols != cols - 1 and count != size - 1:
+                buffer += ' '
+
+            count += 1
+            byte = handle.read(1)
+        buffer += '\n}};\n'
+        buffer += '\n#endif'
+        return buffer
+
+
+if __name__ == '__main__':
+    parsed = argp.parse_args()
+    configuration['inputFiles'] = [os.path.abspath(p) for p in parsed.input]
+    configuration['outputDirectory'] = os.path.abspath(parsed.output)
+    configuration['columns'] = parsed.columns
+    configuration['filetype'] = parsed.extension
+    configuration['elementType'] = Type.fromstring(parsed.type)
+
+    if not os.path.isdir(configuration['outputDirectory']):
+        exit('The ouput directory does not exist')
+
+    if not all(os.path.isfile(p) for p in configuration['inputFiles']):
+        exit('One or more of the input files does not exist')
+
+    for file in configuration['inputFiles']:
+        outname = os.path.basename(file) + '.' + configuration['filetype']
+        outpath = configuration['outputDirectory'] + '/' + outname
+        data = generate_array(file)
+        with open(outpath, 'w') as outhandle:
+            outhandle.write(data)